123 lines · plain
1# RUN: yaml2obj %s -o %t.o2# RUN: llvm-readobj --notes %t.o | FileCheck %s --check-prefix=LLVM3# RUN: llvm-readelf --notes %t.o | FileCheck %s --check-prefix=GNU4 5# GNU: Displaying notes found in: .note.foo6# GNU-NEXT: Owner Data size Description7# GNU-NEXT: AMDGPU 0x000000fb NT_AMDGPU_METADATA (AMDGPU Metadata)8# GNU-NEXT: AMDGPU Metadata:9# GNU-NEXT: ---10# GNU-NEXT: amdhsa.kernels:11# GNU-NEXT: - .group_segment_fixed_size: 212# GNU-NEXT: .kernarg_segment_align: 413# GNU-NEXT: .kernarg_segment_size: 114# GNU-NEXT: .max_flat_workgroup_size: 815# GNU-NEXT: .name: foo16# GNU-NEXT: .private_segment_fixed_size: 317# GNU-NEXT: .sgpr_count: 618# GNU-NEXT: .symbol: foo19# GNU-NEXT: .uses_dynamic_stack: true20# GNU-NEXT: .vgpr_count: 721# GNU-NEXT: .wavefront_size: 522# GNU-NEXT: amdhsa.version:23# GNU-NEXT: - 124# GNU-NEXT: - 025# GNU-NEXT: ...26# GNU-EMPTY:27# GNU-EMPTY:28# GNU-NEXT: Displaying notes found in: .note.unknown29# GNU-NEXT: Owner Data size Description30# GNU-NEXT: AMDGPU 0x00000002 Unknown note type: (0x00000101)31# GNU-NEXT: description data: ab cd32# GNU-EMPTY:33 34# LLVM: NoteSections [35# LLVM-NEXT: NoteSection {36# LLVM-NEXT: Name: .note.foo37# LLVM-NEXT: Offset:38# LLVM-NEXT: Size:39# LLVM-NEXT: Notes [40# LLVM-NEXT: {41# LLVM-NEXT: Owner: AMDGPU42# LLVM-NEXT: Data size: 0xFB43# LLVM-NEXT: Type: NT_AMDGPU_METADATA (AMDGPU Metadata)44# LLVM-NEXT: AMDGPU Metadata: ---45# LLVM-NEXT: amdhsa.kernels:46# LLVM-NEXT: - .group_segment_fixed_size: 247# LLVM-NEXT: .kernarg_segment_align: 448# LLVM-NEXT: .kernarg_segment_size: 149# LLVM-NEXT: .max_flat_workgroup_size: 850# LLVM-NEXT: .name: foo51# LLVM-NEXT: .private_segment_fixed_size: 352# LLVM-NEXT: .sgpr_count: 653# LLVM-NEXT: .symbol: foo54# LLVM-NEXT: .uses_dynamic_stack: true55# LLVM-NEXT: .vgpr_count: 756# LLVM-NEXT: .wavefront_size: 557# LLVM-NEXT: amdhsa.version:58# LLVM-NEXT: - 159# LLVM-NEXT: - 060# LLVM-NEXT: ...61# LLVM-EMPTY:62# LLVM-NEXT: }63# LLVM-NEXT: ]64# LLVM-NEXT: }65# LLVM-NEXT: NoteSection {66# LLVM-NEXT: Name: .note.unknown67# LLVM-NEXT: Offset: 0x15068# LLVM-NEXT: Size: 0x1869# LLVM-NEXT: Notes [70# LLVM-NEXT: {71# LLVM-NEXT: Owner: AMDGPU72# LLVM-NEXT: Data size: 0x273# LLVM-NEXT: Type: Unknown (0x00000101)74# LLVM-NEXT: Description data (75# LLVM-NEXT: 0000: ABCD |..|76# LLVM-NEXT: )77# LLVM-NEXT: }78# LLVM-NEXT: ]79# LLVM-NEXT: }80# LLVM-NEXT: ]81 82## Use yaml2obj instead of llvm-mc for more test portability. This was83## generated by grabbing section data from an object built via:84# $ llvm-mc -filetype=obj -triple amdgcn-amd-amdhsa %s -o %t.o85## On input:86# .amdgpu_metadata87# amdhsa.version:88# - 189# - 090# amdhsa.kernels:91# - .name: foo92# .symbol: foo93# .kernarg_segment_size: 194# .group_segment_fixed_size: 295# .private_segment_fixed_size: 396# .uses_dynamic_stack: true97# .kernarg_segment_align: 498# .wavefront_size: 599# .sgpr_count: 6100# .vgpr_count: 7101# .max_flat_workgroup_size: 8102# .end_amdgpu_metadata103#104## Here's one way to get the contents of .note.foo in the test input from %t.o:105# $ llvm-objcopy -O binary --only-section=.note %t.o note.out106# $ xxd -p note.out | tr -d '\n' | tr a-z A-Z107 108--- !ELF109FileHeader:110 Class: ELFCLASS64111 Data: ELFDATA2LSB112 Type: ET_REL113Sections:114 - Name: .note.foo115 Type: SHT_NOTE116 Content: 07000000FB00000020000000414D44475055000082AE616D646873612E6B65726E656C73918BB92E67726F75705F7365676D656E745F66697865645F73697A6502B62E6B65726E6172675F7365676D656E745F616C69676E04B52E6B65726E6172675F7365676D656E745F73697A6501B82E6D61785F666C61745F776F726B67726F75705F73697A6508A52E6E616D65A3666F6FBB2E707269766174655F7365676D656E745F66697865645F73697A6503AB2E736770725F636F756E7406A72E73796D626F6CA3666F6FB32E757365735F64796E616D69635F737461636BC3AB2E766770725F636F756E7407AF2E7761766566726F6E745F73697A6505AE616D646873612E76657273696F6E92010000117 - Name: .note.unknown118 Type: SHT_NOTE119 Notes:120 - Name: AMDGPU121 Type: NT_GNU_BUILD_ATTRIBUTE_FUNC122 Desc: 'abcd'123