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# GNU-EMPTY:
26# GNU-EMPTY:
27# GNU-NEXT: Displaying notes found in: .note.unknown
28# GNU-NEXT:   Owner                Data size 	Description
29# GNU-NEXT:   AMDGPU               0x00000002	Unknown note type: (0x00000101)
30# GNU-NEXT:    description data: ab cd
31# GNU-EMPTY:
32
33# LLVM:      Notes [
34# LLVM-NEXT:   NoteSection {
35# LLVM-NEXT:     Name: .note.foo
36# LLVM-NEXT:     Offset:
37# LLVM-NEXT:     Size:
38# LLVM-NEXT:     Note {
39# LLVM-NEXT:       Owner: AMDGPU
40# LLVM-NEXT:       Data size: 0xE6
41# LLVM-NEXT:       Type: NT_AMDGPU_METADATA (AMDGPU Metadata)
42# LLVM-NEXT:       AMDGPU Metadata: ---
43# LLVM-NEXT: amdhsa.kernels:
44# LLVM-NEXT:   - .group_segment_fixed_size: 2
45# LLVM-NEXT:     .kernarg_segment_align: 4
46# LLVM-NEXT:     .kernarg_segment_size: 1
47# LLVM-NEXT:     .max_flat_workgroup_size: 8
48# LLVM-NEXT:     .name:           foo
49# LLVM-NEXT:     .private_segment_fixed_size: 3
50# LLVM-NEXT:     .sgpr_count:     6
51# LLVM-NEXT:     .symbol:         foo
52# LLVM-NEXT:     .vgpr_count:     7
53# LLVM-NEXT:     .wavefront_size: 5
54# LLVM-NEXT: amdhsa.version:
55# LLVM-NEXT:   - 1
56# LLVM-NEXT:   - 0
57# LLVM-NEXT: ...
58# LLVM-EMPTY:
59# LLVM-NEXT:     }
60# LLVM-NEXT:   }
61# LLVM-NEXT:   NoteSection {
62# LLVM-NEXT:     Name: .note.unknown
63# LLVM-NEXT:     Offset: 0x13C
64# LLVM-NEXT:     Size: 0x18
65# LLVM-NEXT:     Note {
66# LLVM-NEXT:       Owner: AMDGPU
67# LLVM-NEXT:       Data size: 0x2
68# LLVM-NEXT:       Type: Unknown (0x00000101)
69# LLVM-NEXT:       Description data (
70# LLVM-NEXT:         0000: ABCD                                 |..|
71# LLVM-NEXT:       )
72# LLVM-NEXT:     }
73# LLVM-NEXT:   }
74# LLVM-NEXT: ]
75
76## Use yaml2obj instead of llvm-mc for more test portability. This was
77## generated by grabbing section data from an object built via:
78# $ llvm-mc -filetype=obj -triple amdgcn-amd-amdhsa %s -o %t.o
79## On input:
80# .amdgpu_metadata
81#   amdhsa.version:
82#     - 1
83#     - 0
84#   amdhsa.kernels:
85#     - .name:   foo
86#       .symbol: foo
87#       .kernarg_segment_size: 1
88#       .group_segment_fixed_size: 2
89#       .private_segment_fixed_size: 3
90#       .kernarg_segment_align: 4
91#       .wavefront_size: 5
92#       .sgpr_count: 6
93#       .vgpr_count: 7
94#       .max_flat_workgroup_size: 8
95# .end_amdgpu_metadata
96
97--- !ELF
98FileHeader:
99  Class: ELFCLASS64
100  Data:  ELFDATA2LSB
101  Type:  ET_REL
102Sections:
103  - Name:        .note.foo
104    Type:        SHT_NOTE
105    Content:     07000000E600000020000000414D44475055000082AE616D646873612E6B65726E656C73918AB92E67726F75705F7365676D656E745F66697865645F73697A6502B62E6B65726E6172675F7365676D656E745F616C69676E04B52E6B65726E6172675F7365676D656E745F73697A6501B82E6D61785F666C61745F776F726B67726F75705F73697A6508A52E6E616D65A3666F6FBB2E707269766174655F7365676D656E745F66697865645F73697A6503AB2E736770725F636F756E7406A72E73796D626F6CA3666F6FAB2E766770725F636F756E7407AF2E7761766566726F6E745F73697A6505AE616D646873612E76657273696F6E9201000000
106  - Name:        .note.unknown
107    Type:        SHT_NOTE
108    Notes:
109      - Name: AMDGPU
110        Type: NT_GNU_BUILD_ATTRIBUTE_FUNC
111        Desc: 'abcd'
112