llvm/test/tools/llvm-readobj/ELF/note-amdgpu.test

   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
 109 FileHeader:
 110   Class: ELFCLASS64
 111   Data:  ELFDATA2LSB
 112   Type:  ET_REL
 113 Sections:
 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'