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

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