92 lines · plain
1; RUN: llc -mtriple=amdgcn-amd-unknown -mcpu=gfx802 < %s | FileCheck --check-prefix=OSABI-UNK %s2; RUN: llc -mtriple=amdgcn-amd-unknown -mcpu=iceland < %s | FileCheck --check-prefix=OSABI-UNK %s3; RUN: llc -mtriple=amdgcn-amd-unknown -mcpu=gfx802 -filetype=obj < %s | llvm-readelf --notes - | FileCheck --check-prefix=OSABI-UNK-ELF %s4; RUN: llc -mtriple=amdgcn-amd-amdhsa -mcpu=gfx802 < %s| FileCheck --check-prefix=OSABI-HSA %s5; RUN: llc -mtriple=amdgcn-amd-amdhsa -mcpu=iceland < %s | FileCheck --check-prefix=OSABI-HSA %s6; RUN: llc -mtriple=amdgcn-amd-amdhsa -mcpu=gfx802 -filetype=obj < %s | llvm-readelf --notes - | FileCheck --check-prefix=OSABI-HSA-ELF %s7; RUN: llc -mtriple=amdgcn-amd-amdpal -mcpu=gfx802 < %s | FileCheck --check-prefix=OSABI-PAL %s8; RUN: llc -mtriple=amdgcn-amd-amdpal -mcpu=iceland < %s | FileCheck --check-prefix=OSABI-PAL %s9; RUN: llc -mtriple=amdgcn-amd-amdpal -mcpu=gfx802 -filetype=obj < %s | llvm-readelf --notes - | FileCheck --check-prefix=OSABI-PAL-ELF %s10; RUN: llc -mtriple=r600 < %s | FileCheck --check-prefix=R600 %s11 12; OSABI-UNK-NOT: .hsa_code_object_version13; OSABI-UNK-NOT: .hsa_code_object_isa14; OSABI-UNK: .amd_amdgpu_isa "amdgcn-amd-unknown--gfx802"15; OSABI-UNK-NOT: .amd_amdgpu_hsa_metadata16; OSABI-UNK-NOT: .amd_amdgpu_pal_metadata17 18; OSABI-UNK-ELF-NOT: Unknown note type19; OSABI-UNK-ELF: NT_AMD_HSA_ISA_NAME (AMD HSA ISA Name)20; OSABI-UNK-ELF: AMD HSA ISA Name:21; OSABI-UNK-ELF: amdgcn-amd-unknown--gfx80222; OSABI-UNK-ELF-NOT: Unknown note type23; OSABI-UNK-ELF-NOT: NT_AMD_HSA_METADATA (AMD HSA Metadata)24; OSABI-UNK-ELF-NOT: Unknown note type25; OSABI-UNK-ELF-NOT: NT_AMD_PAL_METADATA (AMD PAL Metadata)26; OSABI-UNK-ELF-NOT: Unknown note type27 28; OSABI-HSA: amdhsa.target: amdgcn-amd-amdhsa--gfx80229; OSABI-HSA: amdhsa.version:30; OSABI-HSA: .end_amdgpu_metadata31; OSABI-HSA-NOT: .amd_amdgpu_pal_metadata32 33; OSABI-HSA-ELF: NT_AMDGPU_METADATA (AMDGPU Metadata)34; OSABI-HSA-ELF: ---35; OSABI-HSA-ELF: amdhsa.kernels:36; OSABI-HSA-ELF: - .args: []37; OSABI-HSA-ELF: .group_segment_fixed_size: 038; OSABI-HSA-ELF: .kernarg_segment_align: 439; OSABI-HSA-ELF: .kernarg_segment_size: 040; OSABI-HSA-ELF: .max_flat_workgroup_size: 102441; OSABI-HSA-ELF: .name: elf_notes42; OSABI-HSA-ELF: .private_segment_fixed_size: 043; OSABI-HSA-ELF: .sgpr_count: 9644; OSABI-HSA-ELF: .sgpr_spill_count: 045; OSABI-HSA-ELF: .symbol: elf_notes.kd46; OSABI-HSA-ELF: .vgpr_count: 047; OSABI-HSA-ELF: .vgpr_spill_count: 048; OSABI-HSA-ELF: .wavefront_size: 6449; OSABI-HSA-ELF: amdhsa.target: amdgcn-amd-amdhsa--gfx80250; OSABI-HSA-ELF: amdhsa.version:51; OSABI-HSA-ELF: - 152; OSABI-HSA-ELF: - 153; OSABI-HSA-ELF: ...54; OSABI-HSA-ELF-NOT: NT_AMD_PAL_METADATA (AMD PAL Metadata)55 56; OSABI-PAL: .amd_amdgpu_isa "amdgcn-amd-amdpal--gfx802"57; OSABI-PAL: .amdgpu_pal_metadata58; OSABI-PAL-NOT: .amd_amdgpu_hsa_metadata59 60; OSABI-PAL-ELF: NT_AMD_HSA_ISA_NAME (AMD HSA ISA Name)61; OSABI-PAL-ELF: AMD HSA ISA Name:62; OSABI-PAL-ELF: amdgcn-amd-amdpal--gfx80263; OSABI-PAL-ELF-NOT: NT_AMD_HSA_METADATA (AMD HSA Metadata)64; OSABI-PAL-ELF: NT_AMDGPU_METADATA (AMDGPU Metadata)65; OSABI-PAL-ELF: AMDGPU Metadata:66; OSABI-PAL-ELF: amdpal.pipelines:67; OSABI-PAL-ELF: - .hardware_stages:68; OSABI-PAL-ELF: .cs:69; OSABI-PAL-ELF: .entry_point: _amdgpu_cs_main70; OSABI-PAL-ELF: .entry_point_symbol: elf_notes71; OSABI-PAL-ELF: .scratch_memory_size: 072; OSABI-PAL-ELF: .sgpr_count: 9673; OSABI-PAL-ELF: .vgpr_count: 174; OSABI-PAL-ELF: .registers:75; OSABI-PAL-ELF: 11794: 1146950476; OSABI-PAL-ELF: 11795: 12877 78; R600-NOT: .hsa_code_object_version79; R600-NOT: .hsa_code_object_isa80; R600-NOT: .amd_amdgpu_isa81; R600-NOT: .amd_amdgpu_hsa_metadata82; R600-NOT: .amd_amdgpu_pal_metadata83 84define amdgpu_kernel void @elf_notes() #0 {85 ret void86}87 88attributes #0 = { "amdgpu-no-dispatch-id" "amdgpu-no-dispatch-ptr" "amdgpu-no-implicitarg-ptr" "amdgpu-no-lds-kernel-id" "amdgpu-no-multigrid-sync-arg" "amdgpu-no-queue-ptr" "amdgpu-no-workgroup-id-x" "amdgpu-no-cluster-id-x" "amdgpu-no-workgroup-id-y" "amdgpu-no-cluster-id-y" "amdgpu-no-workgroup-id-z" "amdgpu-no-cluster-id-z" "amdgpu-no-workitem-id-x" "amdgpu-no-workitem-id-y" "amdgpu-no-workitem-id-z" }89 90!llvm.module.flags = !{!0}91!0 = !{i32 1, !"amdhsa_code_object_version", i32 400}92