1# RUN: yaml2obj %s -o %t.o 2# RUN: llvm-readobj --notes %t.o | FileCheck %s --check-prefix=LLVM 3# RUN: llvm-readelf --notes %t.o | FileCheck %s --check-prefix=GNU 4 5# GNU: Displaying notes found in: .note.foo 6# GNU-NEXT: Owner Data size Description 7# 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: 2 12# GNU-NEXT: .kernarg_segment_align: 4 13# GNU-NEXT: .kernarg_segment_size: 1 14# GNU-NEXT: .max_flat_workgroup_size: 8 15# GNU-NEXT: .name: foo 16# GNU-NEXT: .private_segment_fixed_size: 3 17# GNU-NEXT: .sgpr_count: 6 18# GNU-NEXT: .symbol: foo 19# GNU-NEXT: .uses_dynamic_stack: true 20# GNU-NEXT: .vgpr_count: 7 21# GNU-NEXT: .wavefront_size: 5 22# GNU-NEXT: amdhsa.version: 23# GNU-NEXT: - 1 24# GNU-NEXT: - 0 25# GNU-NEXT: ... 26# GNU-EMPTY: 27# GNU-EMPTY: 28# GNU-NEXT: Displaying notes found in: .note.unknown 29# GNU-NEXT: Owner Data size Description 30# GNU-NEXT: AMDGPU 0x00000002 Unknown note type: (0x00000101) 31# GNU-NEXT: description data: ab cd 32# GNU-EMPTY: 33 34# LLVM: NoteSections [ 35# LLVM-NEXT: NoteSection { 36# LLVM-NEXT: Name: .note.foo 37# LLVM-NEXT: Offset: 38# LLVM-NEXT: Size: 39# LLVM-NEXT: Notes [ 40# LLVM-NEXT: { 41# LLVM-NEXT: Owner: AMDGPU 42# LLVM-NEXT: Data size: 0xFB 43# 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: 2 47# LLVM-NEXT: .kernarg_segment_align: 4 48# LLVM-NEXT: .kernarg_segment_size: 1 49# LLVM-NEXT: .max_flat_workgroup_size: 8 50# LLVM-NEXT: .name: foo 51# LLVM-NEXT: .private_segment_fixed_size: 3 52# LLVM-NEXT: .sgpr_count: 6 53# LLVM-NEXT: .symbol: foo 54# LLVM-NEXT: .uses_dynamic_stack: true 55# LLVM-NEXT: .vgpr_count: 7 56# LLVM-NEXT: .wavefront_size: 5 57# LLVM-NEXT: amdhsa.version: 58# LLVM-NEXT: - 1 59# LLVM-NEXT: - 0 60# LLVM-NEXT: ... 61# LLVM-EMPTY: 62# LLVM-NEXT: } 63# LLVM-NEXT: ] 64# LLVM-NEXT: } 65# LLVM-NEXT: NoteSection { 66# LLVM-NEXT: Name: .note.unknown 67# LLVM-NEXT: Offset: 0x150 68# LLVM-NEXT: Size: 0x18 69# LLVM-NEXT: Notes [ 70# LLVM-NEXT: { 71# LLVM-NEXT: Owner: AMDGPU 72# LLVM-NEXT: Data size: 0x2 73# 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 was 83## generated by grabbing section data from an object built via: 84# $ llvm-mc -filetype=obj -triple amdgcn-amd-amdhsa %s -o %t.o 85## On input: 86# .amdgpu_metadata 87# amdhsa.version: 88# - 1 89# - 0 90# amdhsa.kernels: 91# - .name: foo 92# .symbol: foo 93# .kernarg_segment_size: 1 94# .group_segment_fixed_size: 2 95# .private_segment_fixed_size: 3 96# .uses_dynamic_stack: true 97# .kernarg_segment_align: 4 98# .wavefront_size: 5 99# .sgpr_count: 6 100# .vgpr_count: 7 101# .max_flat_workgroup_size: 8 102# .end_amdgpu_metadata 103# 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.out 106# $ xxd -p note.out | tr -d '\n' | tr a-z A-Z 107 108--- !ELF 109FileHeader: 110 Class: ELFCLASS64 111 Data: ELFDATA2LSB 112 Type: ET_REL 113Sections: 114 - Name: .note.foo 115 Type: SHT_NOTE 116 Content: 07000000FB00000020000000414D44475055000082AE616D646873612E6B65726E656C73918BB92E67726F75705F7365676D656E745F66697865645F73697A6502B62E6B65726E6172675F7365676D656E745F616C69676E04B52E6B65726E6172675F7365676D656E745F73697A6501B82E6D61785F666C61745F776F726B67726F75705F73697A6508A52E6E616D65A3666F6FBB2E707269766174655F7365676D656E745F66697865645F73697A6503AB2E736770725F636F756E7406A72E73796D626F6CA3666F6FB32E757365735F64796E616D69635F737461636BC3AB2E766770725F636F756E7407AF2E7761766566726F6E745F73697A6505AE616D646873612E76657273696F6E92010000 117 - Name: .note.unknown 118 Type: SHT_NOTE 119 Notes: 120 - Name: AMDGPU 121 Type: NT_GNU_BUILD_ATTRIBUTE_FUNC 122 Desc: 'abcd' 123