Skip to content

Commit 7f1c923

Browse files
jcranmer-intelsys-ce-bb
jcranmer-intel
authored and
sys-ce-bb
committed
Switch the default of reverse translation to emitting opaque pointers. (#2074)
Most of the changes are adding -emit-opaque-pointers=0 lines to test code. The code generally works in the forward translation at this point, although there is still substantial work that needs to be done to finish porting the tests. Original commit: KhronosGroup/SPIRV-LLVM-Translator@10b1354
1 parent 8e68fb0 commit 7f1c923

File tree

49 files changed

+70
-71
lines changed

Some content is hidden

Large Commits have some content hidden by default. Use the searchbox below for content that may be hidden.

49 files changed

+70
-71
lines changed

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_blocking_pipes/PipeBlocking.ll

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3,10 +3,10 @@
33
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
44
; FIXME: add more negative test cases
55
; RUN: llvm-spirv %t.spt -to-binary -o %t.spv
6-
; RUN: llvm-spirv -r %t.spv -o %t.bc
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc
77
; RUN: llvm-dis -opaque-pointers=0 < %t.bc | FileCheck %s --check-prefix=CHECK-LLVM
88

9-
; RUN: llvm-spirv -r %t.spv -o %t.bc --spirv-target-env=SPV-IR
9+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc --spirv-target-env=SPV-IR
1010
; RUN: llvm-dis -opaque-pointers=0 < %t.bc | FileCheck %s --check-prefix=CHECK-SPV-IR
1111

1212
; ModuleID = 'test/CodeGenOpenCL/pipe_builtin.cl'

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_device_side_avc_motion_esimation/subgroup_avc_intel_generic.cl

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3,9 +3,9 @@
33
// RUN: llvm-spirv %t.spv --to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV
44
// There is no validation for SPV_INTEL_device_side_avc_motion_estimation implemented in
55
// SPIRV-Tools. TODO: spirv-val %t.spv
6-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefixes=CHECK-LLVM-COMMON,CHECK-LLVM
8-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
8+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
99
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefixes=CHECK-LLVM-COMMON,CHECK-LLVM-SPIRV
1010
// RUN: llvm-spirv %t.rev.bc -opaque-pointers=0 --spirv-ext=+SPV_INTEL_device_side_avc_motion_estimation -o %t.spv
1111
// RUN: llvm-spirv %t.spv --to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_device_side_avc_motion_esimation/subgroup_avc_intel_types.spt

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -93,9 +93,9 @@
9393
1 FunctionEnd
9494

9595
; RUN: llvm-spirv %s -to-binary -o %t.spv
96-
; RUN: llvm-spirv -r %t.spv -o %t.bc
96+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc
9797
; RUN: llvm-dis -opaque-pointers=0 < %t.bc | FileCheck %s --check-prefixes=CHECK-COMMON,CHECK-LLVM
98-
; RUN: llvm-spirv -r %t.spv -o %t.bc --spirv-target-env=SPV-IR
98+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc --spirv-target-env=SPV-IR
9999
; RUN: llvm-dis -opaque-pointers=0 < %t.bc | FileCheck %s --check-prefixes=CHECK-COMMON,CHECK-LLVM-SPIRV
100100

101101
; CHECK-LLVM: %opencl.intel_sub_group_avc_mce_payload_t = type opaque

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_device_side_avc_motion_esimation/subgroup_avc_intel_vme_image.cl

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3,9 +3,9 @@
33
// RUN: llvm-spirv %t.spv --to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV
44
// There is no validation for SPV_INTEL_device_side_avc_motion_estimation implemented in
55
// SPIRV-Tools. TODO: spirv-val %t.spv
6-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefixes=CHECK-LLVM-COMMON,CHECK-LLVM
8-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
8+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
99
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefixes=CHECK-LLVM-COMMON,CHECK-LLVM-SPIRV
1010
// RUN: llvm-spirv %t.rev.bc -opaque-pointers=0 --spirv-ext=+SPV_INTEL_device_side_avc_motion_estimation -o %t.rev.spv
1111
// RUN: llvm-spirv %t.rev.spv --to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_fpga_loop_controls/FPGAIVDepLoopAttrOnClosure.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -41,7 +41,7 @@
4141
; RUN: llvm-spirv -to-text %t.spv -o %t.spt
4242
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
4343

44-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
44+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
4545
; RUN: llvm-dis -opaque-pointers=0 %t.rev.bc -o %t.rev.ll
4646

4747
; CHECK-LLVM is the base prefix, which includes simple checks for

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_fpga_memory_attributes/IntelFPGAMemoryAttributesForStruct.ll

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -186,10 +186,10 @@
186186
; RUN: llvm-spirv %t.spv --spirv-ext=+SPV_INTEL_fpga_memory_attributes -to-text -o %t.spt
187187
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
188188

189-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
189+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
190190
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
191191

192-
; RUN: llvm-spirv -spirv-text -r %t.spt -o %t.rev.bc
192+
; RUN: llvm-spirv -spirv-text -r -emit-opaque-pointers=0 %t.spt -o %t.rev.bc
193193
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
194194

195195
; TODO: add a bunch of different tests for --spirv-ext option

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_fpga_reg/IntelFPGAReg.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -60,7 +60,7 @@
6060
; RUN: llvm-spirv %t.spv -to-text -o %t.spt
6161
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
6262

63-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
63+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
6464
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
6565

6666
; CHECK-SPIRV: Capability FPGARegINTEL

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_io_pipes/PipeStorageIOINTEL.ll

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3,10 +3,10 @@
33
; RUN: llvm-spirv %t.spv -to-text -o %t.spt
44
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
55

6-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88

9-
; RUN: llvm-spirv -spirv-text -r %t.spt -o %t.rev.bc
9+
; RUN: llvm-spirv -spirv-text -r -emit-opaque-pointers=0 %t.spt -o %t.rev.bc
1010
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
1111

1212
; CHECK-LLVM-DAG: %spirv.ConstantPipeStorage = type { i32, i32, i32 }

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_joint_matrix/joint_matrix.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -spirv-ext=+SPV_INTEL_joint_matrix -o %t.spv
33
; RUN: llvm-spirv %t.spv -to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV
44

5-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
5+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
66
; RUN: llvm-dis -opaque-pointers=0 %t.rev.bc -o - | FileCheck %s --check-prefix=CHECK-LLVM
77

88
; CHECK-SPIRV: Capability JointMatrixINTEL

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_joint_matrix/joint_matrix_bfloat16.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -8,7 +8,7 @@
88
; RUN: llvm-spirv %t.spv -to-text -o %t.spt
99
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
1010

11-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
11+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
1212
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
1313

1414
; CHECK-REGULARIZED: %[[Alloca:.*]] = alloca %"class.cl::sycl::ext::intel::experimental::bfloat16", align 2

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_joint_matrix/joint_matrix_half.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -spirv-ext=+SPV_INTEL_joint_matrix -o %t.spv
33
; RUN: llvm-spirv %t.spv -to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV
44

5-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
5+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
66
; RUN: llvm-dis -opaque-pointers=0 %t.rev.bc -o - | FileCheck %s --check-prefix=CHECK-LLVM
77

88
; CHECK-SPIRV-DAG: TypeFloat [[#FloatTy:]] 32

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_joint_matrix/joint_matrix_tf32.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -4,7 +4,7 @@
44
; RUN: llvm-spirv %t.spv -to-text -o %t.spt
55
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
66

7-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
7+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
88
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
99

1010
; CHECK-SPIRV-DAG: Capability TensorFloat32RoundingINTEL

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_joint_matrix/opaque_joint_matrix.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -3,7 +3,7 @@
33
; RUN: llvm-spirv %t.spv -to-text -o %t.spt
44
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
55

6-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc -opaque-pointers=0
6+
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc -emit-opaque-pointers=0
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88

99
; CHECK-SPIRV-DAG: Capability JointMatrixINTEL

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_masked_gather_scatter/intel-basic-vector-pointers.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -3,7 +3,7 @@
33
; RUN: llvm-spirv %t.spv --to-text -o %t.spt
44
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
55

6-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88

99
; RUN: not llvm-spirv %t.bc -opaque-pointers=0 2>&1 | FileCheck %s --check-prefix=CHECK-ERROR

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_masked_gather_scatter/intel-gather-scatter.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -3,7 +3,7 @@
33
; RUN: llvm-spirv %t.spv --to-text -o %t.spt
44
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
55

6-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88

99
; RUN: llvm-spirv %t.bc --spirv-ext=+SPV_INTEL_masked_gather_scatter -o %t.spv -spirv-allow-unknown-intrinsics

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_media_block_io/SPV_INTEL_media_block_io.cl

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -2,9 +2,9 @@
22
// RUN: llvm-spirv --spirv-ext=+SPV_INTEL_media_block_io %t.bc -o %t.spv
33
// RUN: llvm-spirv %t.spv -to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV
44
// RUN: spirv-val %t.spv
5-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc
5+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
66
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
7-
// RUN: llvm-spirv -r --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
7+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
88
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-SPV-IR
99

1010
uchar __attribute__((overloadable)) intel_sub_group_media_block_read_uc(int2 src_offset, int width, int height, read_only image2d_t image);

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_subgroups/cl_intel_sub_groups.ll

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -36,9 +36,9 @@
3636
; RUN: llvm-as -opaque-pointers=0 %s -o %t.bc
3737
; RUN: llvm-spirv %t.bc -o - -spirv-text --spirv-ext=+SPV_INTEL_subgroups | FileCheck %s --check-prefix=CHECK-SPIRV
3838
; RUN: llvm-spirv %t.bc -o %t.spv --spirv-ext=+SPV_INTEL_subgroups
39-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
39+
; RUN: llvm-spirv -r %t.spv -emit-opaque-pointers=0 -o %t.rev.bc
4040
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
41-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
41+
; RUN: llvm-spirv -r %t.spv -emit-opaque-pointers=0 -o %t.rev.bc --spirv-target-env=SPV-IR
4242
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM-SPIRV
4343
; RUN: llvm-spirv %t.rev.bc -o - -spirv-text --spirv-ext=+SPV_INTEL_subgroups | FileCheck %s --check-prefix=CHECK-SPIRV
4444

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_vector_compute/buffer_surface_intel.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -1,7 +1,7 @@
11
; RUN: llvm-as -opaque-pointers=0 %s -o %t.bc
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv --spirv-ext=+SPV_INTEL_vector_compute --spirv-allow-unknown-intrinsics
33
; RUN: llvm-spirv %t.spv -o %t.spt --to-text
4-
; RUN: llvm-spirv -r %t.spv -o %t.bc
4+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc
55
; RUN: llvm-dis -opaque-pointers=0 %t.bc -o %t.ll
66
; RUN: FileCheck %s --input-file %t.spt -check-prefix=SPV
77
; RUN: FileCheck %s --input-file %t.ll -check-prefix=LLVM

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_vector_compute/decoration_media_block_io.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -1,7 +1,7 @@
11
; RUN: llvm-as -opaque-pointers=0 %s -o %t.bc
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv --spirv-ext=+SPV_INTEL_vector_compute --spirv-allow-unknown-intrinsics=llvm.genx
33
; RUN: llvm-spirv %t.spv -o %t.spt --to-text
4-
; RUN: llvm-spirv -r %t.spv -o %t.bc
4+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc
55
; RUN: llvm-dis -opaque-pointers=0 %t.bc -o %t.ll
66
; RUN: FileCheck %s --input-file %t.spt -check-prefix=SPV
77
; RUN: FileCheck %s --input-file %t.ll -check-prefix=LLVM

‎llvm-spirv/test/image.ll

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -1,11 +1,11 @@
11
; RUN: llvm-as -opaque-pointers=0 %s -o %t.bc
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -spirv-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV
33
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
4-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
4+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
55
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
6-
; RUN: llvm-spirv -r --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-SPV-IR
8-
; RUN: llvm-spirv %t.rev.bc -opaque-pointers=0 -o %t.rev.spv
8+
; RUN: llvm-spirv %t.rev.bc -emit-opaque-pointers=0 -o %t.rev.spv
99
; RUN: spirv-val %t.rev.spv
1010

1111
; CHECK-SPIRV: 2 TypeVoid [[VOID_TY:[0-9]+]]

‎llvm-spirv/test/image_without_access_qualifier.spt

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -66,7 +66,7 @@
6666

6767
; RUN: llvm-spirv %s -to-binary -o %t.spv
6868
; RUN: spirv-val %t.spv
69-
; RUN: llvm-spirv -r %t.spv -o %t.bc
69+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc
7070
; RUN: llvm-dis -opaque-pointers=0 < %t.bc | FileCheck %s --check-prefix=CHECK-LLVM
7171

7272
; CHECK-LLVM: %opencl.image2d_ro_t = type opaque

‎llvm-spirv/test/llvm-intrinsics/memset-opaque.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
; RUN: llvm-spirv %t.bc -spirv-text -o %t.spt
33
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
44
; RUN: llvm-spirv %t.bc -o %t.spv
5-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
5+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
66
; RUN: spirv-val %t.spv
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88
; RUN: llvm-spirv -r %t.spv -o - -emit-opaque-pointers | llvm-dis | FileCheck %s --check-prefix=CHECK-LLVM-OPAQUE

‎llvm-spirv/test/llvm-intrinsics/memset.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -spirv-text -o %t.spt
33
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
44
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
5-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
5+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
66
; RUN: spirv-val %t.spv
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88
; RUN: llvm-spirv -r %t.spv -o - -emit-opaque-pointers | llvm-dis | FileCheck %s --check-prefix=CHECK-LLVM-OPAQUE

‎llvm-spirv/test/read_image.cl

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
// RUN: llvm-spirv --spirv-max-version=1.3 %t.bc -o %t.spv
33
// RUN: spirv-val %t.spv
44
// RUN: llvm-spirv %t.spv -to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV
5-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
5+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
66
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-SPV-LLVM
77
// RUN: llvm-spirv --spirv-max-version=1.3 %t.rev.bc -o %t.rev.spv
88
// RUN: spirv-val %t.rev.spv

‎llvm-spirv/test/transcoding/CreatePipeFromPipeStorage.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -spirv-text -o %t.txt
33
; RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
44
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
5-
; RUN: llvm-spirv -r --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
5+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
66
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-SPV-IR
77

88

‎llvm-spirv/test/transcoding/ForwardPtr.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,6 @@
11
; RUN: llvm-as -opaque-pointers=0 < %s | llvm-spirv -opaque-pointers=0 -spirv-ext=+all -o %t.spv
22
; RUN: llvm-spirv -to-text %t.spv -o - | FileCheck %s --check-prefix=CHECK-SPIRV
3-
; RUN: llvm-spirv -r %t.spv -o %t.bc
3+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc
44
; RUN: llvm-dis -opaque-pointers=0 %t.bc -o - | FileCheck %s --check-prefix=CHECK-LLVM
55

66
; CHECK-SPIRV: TypeForwardPointer [[#FwdPtr:]] 8

‎llvm-spirv/test/transcoding/OpGroupAsyncCopy.ll

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3,9 +3,9 @@
33
; RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
44
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
55
; RUN: spirv-val %t.spv
6-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
8-
; RUN: llvm-spirv -r --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
8+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
99
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-SPV-IR
1010

1111
; CHECK-LLVM: call spir_func %opencl.event_t{{.*}}* @_Z29async_work_group_strided_copyPU3AS1Dv2_hPU3AS3KS_jj9ocl_event(

‎llvm-spirv/test/transcoding/OpImageQuerySize.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -7,7 +7,7 @@ target triple = "spir64-unknown-unknown"
77
; RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
88
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
99
; RUN: spirv-val %t.spv
10-
; RUN: llvm-spirv -r %t.spv -o %t.bc
10+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.bc
1111
; RUN: llvm-dis -opaque-pointers=0 < %t.bc | FileCheck %s
1212

1313
; Check conversion of get_image_width, get_image_height, get_image_depth,

‎llvm-spirv/test/transcoding/OpImageReadMS.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
; RUN: llvm-spirv %t.bc -spirv-text -o %t.txt
33
; RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
44
; RUN: llvm-spirv %t.bc -o %t.spv
5-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
5+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
66
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
77

88
; CHECK-LLVM: call spir_func <4 x float> @_Z11read_imagef19ocl_image2d_msaa_roDv2_ii(%opencl.image2d_msaa_ro_t

‎llvm-spirv/test/transcoding/OpImageSampleExplicitLod.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -3,7 +3,7 @@
33
; RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
44
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
55
; RUN: spirv-val %t.spv
6-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88

99
; CHECK-LLVM: call spir_func float @_Z11read_imagef20ocl_image2d_depth_ro11ocl_samplerDv2_i(%opencl.image2d_depth_ro_t

‎llvm-spirv/test/transcoding/OpImageSampleExplicitLod_arg.cl

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -3,7 +3,7 @@
33
// RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
44
// RUN: llvm-spirv %t.bc -o %t.spv
55
// RUN: spirv-val %t.spv
6-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
88

99
void __kernel sample_kernel_read( __global float4 *results,

‎llvm-spirv/test/transcoding/PipeStorage.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -spirv-text -o %t.txt
33
; RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
44
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
5-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
5+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
66
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
77

88
; CHECK-LLVM-DAG: %spirv.ConstantPipeStorage = type { i32, i32, i32 }

‎llvm-spirv/test/transcoding/RecursiveType.ll

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -6,10 +6,10 @@
66
; RUN: llvm-spirv %t.spv -to-text -o %t.spt
77
; RUN: FileCheck < %t.spt %s --check-prefix=CHECK-SPIRV
88

9-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
9+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
1010
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
1111

12-
; RUN: llvm-spirv -r %t.spt -spirv-text -o %t.rev.bc
12+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spt -spirv-text -o %t.rev.bc
1313
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
1414

1515
target datalayout = "e-p:32:32-i64:64-v16:16-v24:32-v32:32-v48:64-v96:128-v192:256-v256:256-v512:512-v1024:1024"

‎llvm-spirv/test/transcoding/SampledImage.cl

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3,9 +3,9 @@
33
// RUN: FileCheck < %t.txt %s --check-prefix=CHECK-SPIRV
44
// RUN: llvm-spirv --spirv-max-version=1.3 %t.bc -o %t.spv
55
// RUN: spirv-val %t.spv
6-
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc
6+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
77
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
8-
// RUN: llvm-spirv -r --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
8+
// RUN: llvm-spirv -r -emit-opaque-pointers=0 --spirv-target-env=SPV-IR %t.spv -o %t.rev.bc
99
// RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-SPV-IR
1010
// RUN: llvm-spirv %t.rev.bc -opaque-pointers=0 -spirv-text -o %t.rev.spt
1111
// RUN: FileCheck < %t.rev.spt %s --check-prefix=CHECK-SPIRV

‎llvm-spirv/test/transcoding/check_ro_qualifier.ll

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -1,9 +1,9 @@
11
; RUN: llvm-as -opaque-pointers=0 %s -o %t.bc
22
; RUN: llvm-spirv %t.bc -o %t.spv
33
; RUN: spirv-val %t.spv
4-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
4+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
55
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
6-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
6+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc --spirv-target-env=SPV-IR
77
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-SPV-LLVM
88
; RUN: llvm-spirv %t.rev.bc -o %t.back.spv
99
; RUN: llvm-spirv %t.back.spv --to-text -o - | FileCheck %s --check-prefix=CHECK-SPIRV

‎llvm-spirv/test/transcoding/check_wo_qualifier.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -1,7 +1,7 @@
11
; RUN: llvm-as -opaque-pointers=0 %s -o %t.bc
22
; RUN: llvm-spirv %t.bc -o %t.spv
33
; RUN: spirv-val %t.spv
4-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
4+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
55
; RUN: llvm-dis -opaque-pointers=0 < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
66

77
; CHECK-LLVM: opencl.image2d_array_wo_t = type opaque

‎llvm-spirv/test/transcoding/cl-types.ll

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -22,7 +22,7 @@
2222
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -spirv-text -o %t.spv.txt
2323
; RUN: FileCheck < %t.spv.txt %s --check-prefix=CHECK-SPIRV
2424
; RUN: llvm-spirv %t.bc -opaque-pointers=0 -o %t.spv
25-
; RUN: llvm-spirv -r %t.spv -o %t.rev.bc
25+
; RUN: llvm-spirv -r -emit-opaque-pointers=0 %t.spv -o %t.rev.bc
2626
; RUN: llvm-dis -opaque-pointers=0 %t.rev.bc
2727
; RUN: FileCheck < %t.rev.ll %s --check-prefix=CHECK-LLVM
2828

0 commit comments

Comments
 (0)