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 0x000000e6 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: .vgpr_count: 7 20# GNU-NEXT: .wavefront_size: 5 21# GNU-NEXT: amdhsa.version: 22# GNU-NEXT: - 1 23# GNU-NEXT: - 0 24# GNU-NEXT: ... 25 26# LLVM: Notes [ 27# LLVM-NEXT: NoteSection { 28# LLVM-NEXT: Name: .note.foo 29# LLVM-NEXT: Offset: 30# LLVM-NEXT: Size: 31# LLVM-NEXT: Note { 32# LLVM-NEXT: Owner: AMDGPU 33# LLVM-NEXT: Data size: 0xE6 34# LLVM-NEXT: Type: NT_AMDGPU_METADATA (AMDGPU Metadata) 35# LLVM-NEXT: AMDGPU Metadata: --- 36# LLVM-NEXT: amdhsa.kernels: 37# LLVM-NEXT: - .group_segment_fixed_size: 2 38# LLVM-NEXT: .kernarg_segment_align: 4 39# LLVM-NEXT: .kernarg_segment_size: 1 40# LLVM-NEXT: .max_flat_workgroup_size: 8 41# LLVM-NEXT: .name: foo 42# LLVM-NEXT: .private_segment_fixed_size: 3 43# LLVM-NEXT: .sgpr_count: 6 44# LLVM-NEXT: .symbol: foo 45# LLVM-NEXT: .vgpr_count: 7 46# LLVM-NEXT: .wavefront_size: 5 47# LLVM-NEXT: amdhsa.version: 48# LLVM-NEXT: - 1 49# LLVM-NEXT: - 0 50# LLVM-NEXT: ... 51# LLVM-EMPTY: 52# LLVM-NEXT: } 53# LLVM-NEXT: } 54# LLVM-NEXT: ] 55 56## Use yaml2obj instead of llvm-mc for more test portability. This was 57## generated by grabbing section data from an object built via: 58# $ llvm-mc -filetype=obj -triple amdgcn-amd-amdhsa %s -o %t.o 59## On input: 60# .amdgpu_metadata 61# amdhsa.version: 62# - 1 63# - 0 64# amdhsa.kernels: 65# - .name: foo 66# .symbol: foo 67# .kernarg_segment_size: 1 68# .group_segment_fixed_size: 2 69# .private_segment_fixed_size: 3 70# .kernarg_segment_align: 4 71# .wavefront_size: 5 72# .sgpr_count: 6 73# .vgpr_count: 7 74# .max_flat_workgroup_size: 8 75# .end_amdgpu_metadata 76 77--- !ELF 78FileHeader: 79 Class: ELFCLASS64 80 Data: ELFDATA2LSB 81 Type: ET_REL 82Sections: 83 - Name: .note.foo 84 Type: SHT_NOTE 85 Content: 07000000E600000020000000414D44475055000082AE616D646873612E6B65726E656C73918AB92E67726F75705F7365676D656E745F66697865645F73697A6502B62E6B65726E6172675F7365676D656E745F616C69676E04B52E6B65726E6172675F7365676D656E745F73697A6501B82E6D61785F666C61745F776F726B67726F75705F73697A6508A52E6E616D65A3666F6FBB2E707269766174655F7365676D656E745F66697865645F73697A6503AB2E736770725F636F756E7406A72E73796D626F6CA3666F6FAB2E766770725F636F756E7407AF2E7761766566726F6E745F73697A6505AE616D646873612E76657273696F6E9201000000 86