Skip to content

Commit 38c794f

Browse files
vmaksimosys-ce-bb
vmaksimo
authored and
sys-ce-bb
committed
Update tests after community changes in llorg (#3118)
Original commit: KhronosGroup/SPIRV-LLVM-Translator@6f29f0b612d381c
1 parent 2c5af09 commit 38c794f

File tree

11 files changed

+169
-104
lines changed

11 files changed

+169
-104
lines changed

‎llvm-spirv/test/DebugInfo/NonSemantic/DebugFunction.cl‎

Lines changed: 3 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -26,14 +26,16 @@ void kernel k() {
2626
// CHECK-SPIRV-DAG: String [[#EmptyStr:]] ""
2727
// CHECK-SPIRV-DAG: String [[k:[0-9]+]] "k"
2828
// CHECK-SPIRV-DAG: String [[#CV:]] "{{.*}}clang version [[#]].[[#]].[[#]]
29+
// CHECK-SPIRV: TypeFloat [[#FloatTy:]] 32
30+
2931
// CHECK-SPIRV: [[#CU:]] [[#]] DebugCompilationUnit
3032
// CHECK-SPIRV: [[#FuncFoo:]] [[#]] DebugFunction [[foo]] {{.*}} [[#CU]]
3133
// CHECK-SPIRV: [[#FuncK:]] [[#]] DebugFunction [[k]] {{.*}} [[#CU]]
3234
// CHECK-SPIRV: DebugEntryPoint [[#FuncK]] [[#CU]] [[#CV]] [[#EmptyStr]] {{$}}
3335
// CHECK-SPIRV-NOT: DebugEntryPoint
3436
// CHECK-SPIRV-NOT: DebugFunctionDefinition
3537

36-
// CHECK-SPIRV: Function {{[0-9]+}} [[#foo_id:]]
38+
// CHECK-SPIRV: Function [[#FloatTy]] [[#foo_id:]]
3739
// CHECK-SPIRV: DebugFunctionDefinition [[#FuncFoo]] [[#foo_id]]
3840
// CHECK-LLVM: define spir_func float @_Z3fooi(i32 %i) #{{[0-9]+}} !dbg ![[#foo_id:]] {
3941

‎llvm-spirv/test/extensions/INTEL/SPV_INTEL_inline_assembly/inline_asm_clobbers.cl‎

Lines changed: 1 addition & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -21,6 +21,7 @@ size_t __ovld __cnfn get_global_id(unsigned int dimindx);
2121

2222
// CHECK-LLVM-LABEL: define spir_kernel void @mem_clobber
2323
// CHECK-SPIRV: {{[0-9]+}} AsmINTEL {{[0-9]+}} {{[0-9]+}} {{[0-9]+}} {{[0-9]+}} "" "~{cc},~{memory}"
24+
// CHECK-LLVM-LABEL: define spir_func void @__clang_ocl_kern_imp_mem_clobber
2425
// CHECK-LLVM: [[VALUE:%[0-9]+]] = load ptr addrspace(1), ptr
2526
// CHECK-LLVM-NEXT: getelementptr inbounds i32, ptr addrspace(1) [[VALUE]], i64 0
2627
// CHECK-LLVM-NEXT: store i32 1, ptr addrspace(1)

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

Lines changed: 2 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -136,6 +136,7 @@ __kernel void intel_media_block_test(int2 edgeCoord, __read_only image2d_t src_l
136136
// CHECK-SPIRV: Capability SubgroupImageMediaBlockIOINTEL
137137
// CHECK-SPIRV: Extension "SPV_INTEL_media_block_io"
138138

139+
// CHECK-SPIRV: Name [[#TestFunc:]] "__clang_ocl_kern_imp_intel_media_block_test"
139140
// CHECK-SPIRV: TypeInt [[TypeInt:[0-9]+]] 32
140141
// CHECK-SPIRV: TypeInt [[TypeChar:[0-9]+]] 8
141142
// CHECK-SPIRV: TypeInt [[TypeShort:[0-9]+]] 16
@@ -153,6 +154,7 @@ __kernel void intel_media_block_test(int2 edgeCoord, __read_only image2d_t src_l
153154
// CHECK-SPIRV: TypeVector [[TypeInt4:[0-9]+]] [[TypeInt]] 4
154155
// CHECK-SPIRV: TypeVector [[TypeInt8:[0-9]+]] [[TypeInt]] 8
155156

157+
// CHECK-SPIRV: Function [[#]] [[#TestFunc]]
156158
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[Coord:[0-9]+]]
157159
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[SrcImage:[0-9]+]]
158160
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[DstImage:[0-9]+]]

‎llvm-spirv/test/extensions/KHR/SPV_KHR_bit_instructions/cl_khr_extended_bit_ops.cl‎

Lines changed: 9 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -9,10 +9,15 @@
99
// CHECK-SPIRV: Capability BitInstructions
1010
// CHECK-SPIRV: Extension "SPV_KHR_bit_instructions"
1111

12+
// CHECK-SPIRV: Name [[#testInsertFn:]] "testInsert"
13+
// CHECK-SPIRV: Name [[#testExtractSFn:]] "testExtractS"
14+
// CHECK-SPIRV: Name [[#testExtractUFn:]] "testExtractU"
15+
// CHECK-SPIRV: Name [[#testBitReverseFn:]] "testBitReverse"
16+
1217
// CHECK-LLVM-LABEL: @testInsert
1318
// CHECK-LLVM: call spir_func <2 x i32> @_Z15bitfield_insertDv2_iS_jj(
1419
// CHECK-SPV-IR: call spir_func <2 x i32> @_Z22__spirv_BitFieldInsertDv2_iS_jj(
15-
// CHECK-SPIRV: Function
20+
// CHECK-SPIRV: Function [[#]] [[#testInsertFn]]
1621
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[insbase:[0-9]+]]
1722
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[insins:[0-9]+]]
1823
// CHECK-SPIRV: BitFieldInsert {{[0-9]+}} {{[0-9]+}} [[insbase]] [[insins]]
@@ -25,7 +30,7 @@ kernel void testInsert(int2 b, int2 i, global int2 *res) {
2530
// CHECK-LLVM: call spir_func i16 @_Z23bitfield_extract_signedsjj(
2631
// CHECK-SPV-IR: call spir_func i16 @_Z24__spirv_BitFieldSExtractsjj(
2732
// CHECK-SPV-IR: call spir_func i16 @_Z24__spirv_BitFieldSExtractsjj(
28-
// CHECK-SPIRV: Function
33+
// CHECK-SPIRV: Function [[#]] [[#testExtractSFn]]
2934
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[sextrbase:[0-9]+]]
3035
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[sextrbaseu:[0-9]+]]
3136
// CHECK-SPIRV: BitFieldSExtract {{[0-9]+}} {{[0-9]+}} [[sextrbase]]
@@ -40,7 +45,7 @@ kernel void testExtractS(short b, ushort bu, global short *res) {
4045
// CHECK-LLVM: call spir_func <8 x i8> @_Z25bitfield_extract_unsignedDv8_cjj(
4146
// CHECK-SPV-IR: call spir_func <8 x i8> @_Z24__spirv_BitFieldUExtractDv8_hjj(
4247
// CHECK-SPV-IR: call spir_func <8 x i8> @_Z24__spirv_BitFieldUExtractDv8_hjj(
43-
// CHECK-SPIRV: Function
48+
// CHECK-SPIRV: Function [[#]] [[#testExtractUFn]]
4449
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[uextrbase:[0-9]+]]
4550
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[uextrbaseu:[0-9]+]]
4651
// CHECK-SPIRV: BitFieldUExtract {{[0-9]+}} {{[0-9]+}} [[uextrbase]]
@@ -53,7 +58,7 @@ kernel void testExtractU(char8 b, uchar8 bu, global uchar8 *res) {
5358
// CHECK-LLVM-LABEL: @testBitReverse
5459
// CHECK-LLVM: call <4 x i64> @llvm.bitreverse.v4i64(
5560
// CHECK-SPV-IR: call <4 x i64> @llvm.bitreverse.v4i64(
56-
// CHECK-SPIRV: Function
61+
// CHECK-SPIRV: Function [[#]] [[#testBitReverseFn]]
5762
// CHECK-SPIRV: FunctionParameter {{[0-9]+}} [[revbase:[0-9]+]]
5863
// CHECK-SPIRV: BitReverse {{[0-9]+}} {{[0-9]+}} [[revbase]]
5964
kernel void testBitReverse(ulong4 b, global ulong4 *res) {

‎llvm-spirv/test/extensions/KHR/SPV_KHR_subgroup_rotate/SPV_KHR_subgroup_rotate.cl‎

Lines changed: 23 additions & 11 deletions
Original file line numberDiff line numberDiff line change
@@ -14,6 +14,18 @@
1414
// CHECK-SPIRV-DAG: {{[0-9]*}} Capability GroupNonUniformRotateKHR
1515
// CHECK-SPIRV-DAG: Extension "SPV_KHR_subgroup_rotate"
1616

17+
// CHECK-SPIRV-DAG: Name [[#testRotateCharFn:]] "testRotateChar"
18+
// CHECK-SPIRV-DAG: Name [[#testRotateUCharFn:]] "testRotateUChar"
19+
// CHECK-SPIRV-DAG: Name [[#testRotateShortFn:]] "testRotateShort"
20+
// CHECK-SPIRV-DAG: Name [[#testRotateUShortFn:]] "testRotateUShort"
21+
// CHECK-SPIRV-DAG: Name [[#testRotateIntFn:]] "testRotateInt"
22+
// CHECK-SPIRV-DAG: Name [[#testRotateUIntFn:]] "testRotateUInt"
23+
// CHECK-SPIRV-DAG: Name [[#testRotateLongFn:]] "testRotateLong"
24+
// CHECK-SPIRV-DAG: Name [[#testRotateULongFn:]] "testRotateULong"
25+
// CHECK-SPIRV-DAG: Name [[#testRotateFloatFn:]] "testRotateFloat"
26+
// CHECK-SPIRV-DAG: Name [[#testRotateHalfFn:]] "testRotateHalf"
27+
// CHECK-SPIRV-DAG: Name [[#testRotateDoubleFn:]] "testRotateDouble"
28+
1729
// CHECK-SPIRV-DAG: TypeInt [[char:[0-9]+]] 8 0
1830
// CHECK-SPIRV-DAG: TypeInt [[short:[0-9]+]] 16 0
1931
// CHECK-SPIRV-DAG: TypeInt [[int:[0-9]+]] 32 0
@@ -36,7 +48,7 @@
3648
#pragma OPENCL EXTENSION cl_khr_fp16 : enable
3749
#pragma OPENCL EXTENSION cl_khr_fp64 : enable
3850

39-
// CHECK-SPIRV-LABEL: 5 Function
51+
// CHECK-SPIRV: Function [[#]] [[#testRotateCharFn]]
4052
// CHECK-SPIRV: GroupNonUniformRotateKHR [[char]] {{[0-9]+}} [[ScopeSubgroup]] [[char_0]] [[int_2]]
4153
// CHECK-SPIRV: GroupNonUniformRotateKHR [[char]] {{[0-9]+}} [[ScopeSubgroup]] [[char_0]] [[int_2]] [[int_4]]
4254
// CHECK-SPIRV: FunctionEnd
@@ -55,7 +67,7 @@ kernel void testRotateChar(global char* dst)
5567
dst[1] = sub_group_clustered_rotate(v, 2, 4);
5668
}
5769

58-
// CHECK-SPIRV-LABEL: 5 Function
70+
// CHECK-SPIRV: Function [[#]] [[#testRotateUCharFn]]
5971
// CHECK-SPIRV: GroupNonUniformRotateKHR [[char]] {{[0-9]+}} [[ScopeSubgroup]] [[char_0]] [[int_2]]
6072
// CHECK-SPIRV: GroupNonUniformRotateKHR [[char]] {{[0-9]+}} [[ScopeSubgroup]] [[char_0]] [[int_2]] [[int_4]]
6173
// CHECK-SPIRV: FunctionEnd
@@ -74,7 +86,7 @@ kernel void testRotateUChar(global uchar* dst)
7486
dst[1] = sub_group_clustered_rotate(v, 2, 4);
7587
}
7688

77-
// CHECK-SPIRV-LABEL: 5 Function
89+
// CHECK-SPIRV: Function [[#]] [[#testRotateShortFn]]
7890
// CHECK-SPIRV: GroupNonUniformRotateKHR [[short]] {{[0-9]+}} [[ScopeSubgroup]] [[short_0]] [[int_2]]
7991
// CHECK-SPIRV: GroupNonUniformRotateKHR [[short]] {{[0-9]+}} [[ScopeSubgroup]] [[short_0]] [[int_2]] [[int_4]]
8092
// CHECK-SPIRV: FunctionEnd
@@ -93,7 +105,7 @@ kernel void testRotateShort(global short* dst)
93105
dst[1] = sub_group_clustered_rotate(v, 2, 4);
94106
}
95107

96-
// CHECK-SPIRV-LABEL: 5 Function
108+
// CHECK-SPIRV: Function [[#]] [[#testRotateUShortFn]]
97109
// CHECK-SPIRV: GroupNonUniformRotateKHR [[short]] {{[0-9]+}} [[ScopeSubgroup]] [[short_0]] [[int_2]]
98110
// CHECK-SPIRV: GroupNonUniformRotateKHR [[short]] {{[0-9]+}} [[ScopeSubgroup]] [[short_0]] [[int_2]] [[int_4]]
99111
// CHECK-SPIRV: FunctionEnd
@@ -112,7 +124,7 @@ kernel void testRotateUShort(global ushort* dst)
112124
dst[1] = sub_group_clustered_rotate(v, 2, 4);
113125
}
114126

115-
// CHECK-SPIRV-LABEL: 5 Function
127+
// CHECK-SPIRV: Function [[#]] [[#testRotateIntFn]]
116128
// CHECK-SPIRV: GroupNonUniformRotateKHR [[int]] {{[0-9]+}} [[ScopeSubgroup]] [[int_0]] [[int_2]]
117129
// CHECK-SPIRV: GroupNonUniformRotateKHR [[int]] {{[0-9]+}} [[ScopeSubgroup]] [[int_0]] [[int_2]] [[int_4]]
118130
// CHECK-SPIRV: FunctionEnd
@@ -131,7 +143,7 @@ kernel void testRotateInt(global int* dst)
131143
dst[1] = sub_group_clustered_rotate(v, 2, 4);
132144
}
133145

134-
// CHECK-SPIRV-LABEL: 5 Function
146+
// CHECK-SPIRV: Function [[#]] [[#testRotateUIntFn]]
135147
// CHECK-SPIRV: GroupNonUniformRotateKHR [[int]] {{[0-9]+}} [[ScopeSubgroup]] [[int_0]] [[int_2]]
136148
// CHECK-SPIRV: GroupNonUniformRotateKHR [[int]] {{[0-9]+}} [[ScopeSubgroup]] [[int_0]] [[int_2]] [[int_4]]
137149
// CHECK-SPIRV: FunctionEnd
@@ -150,7 +162,7 @@ kernel void testRotateUInt(global uint* dst)
150162
dst[1] = sub_group_clustered_rotate(v, 2, 4);
151163
}
152164

153-
// CHECK-SPIRV-LABEL: 5 Function
165+
// CHECK-SPIRV: Function [[#]] [[#testRotateLongFn]]
154166
// CHECK-SPIRV: GroupNonUniformRotateKHR [[long]] {{[0-9]+}} [[ScopeSubgroup]] [[long_0]] [[int_2]]
155167
// CHECK-SPIRV: GroupNonUniformRotateKHR [[long]] {{[0-9]+}} [[ScopeSubgroup]] [[long_0]] [[int_2]] [[int_4]]
156168
// CHECK-SPIRV: FunctionEnd
@@ -169,7 +181,7 @@ kernel void testRotateLong(global long* dst)
169181
dst[1] = sub_group_clustered_rotate(v, 2, 4);
170182
}
171183

172-
// CHECK-SPIRV-LABEL: 5 Function
184+
// CHECK-SPIRV: Function [[#]] [[#testRotateULongFn]]
173185
// CHECK-SPIRV: GroupNonUniformRotateKHR [[long]] {{[0-9]+}} [[ScopeSubgroup]] [[long_0]] [[int_2]]
174186
// CHECK-SPIRV: GroupNonUniformRotateKHR [[long]] {{[0-9]+}} [[ScopeSubgroup]] [[long_0]] [[int_2]] [[int_4]]
175187
// CHECK-SPIRV: FunctionEnd
@@ -188,7 +200,7 @@ kernel void testRotateULong(global ulong* dst)
188200
dst[1] = sub_group_clustered_rotate(v, 2, 4);
189201
}
190202

191-
// CHECK-SPIRV-LABEL: 5 Function
203+
// CHECK-SPIRV: Function [[#]] [[#testRotateFloatFn]]
192204
// CHECK-SPIRV: GroupNonUniformRotateKHR [[float]] {{[0-9]+}} [[ScopeSubgroup]] [[float_0]] [[int_2]]
193205
// CHECK-SPIRV: GroupNonUniformRotateKHR [[float]] {{[0-9]+}} [[ScopeSubgroup]] [[float_0]] [[int_2]] [[int_4]]
194206
// CHECK-SPIRV: FunctionEnd
@@ -207,7 +219,7 @@ kernel void testRotateFloat(global float* dst)
207219
dst[1] = sub_group_clustered_rotate(v, 2, 4);
208220
}
209221

210-
// CHECK-SPIRV-LABEL: 5 Function
222+
// CHECK-SPIRV: Function [[#]] [[#testRotateHalfFn]]
211223
// CHECK-SPIRV: GroupNonUniformRotateKHR [[half]] {{[0-9]+}} [[ScopeSubgroup]] [[half_0]] [[int_2]]
212224
// CHECK-SPIRV: GroupNonUniformRotateKHR [[half]] {{[0-9]+}} [[ScopeSubgroup]] [[half_0]] [[int_2]] [[int_4]]
213225
// CHECK-SPIRV: FunctionEnd
@@ -226,7 +238,7 @@ kernel void testRotateHalf(global half* dst)
226238
dst[1] = sub_group_clustered_rotate(v, 2, 4);
227239
}
228240

229-
// CHECK-SPIRV-LABEL: 5 Function
241+
// CHECK-SPIRV: Function [[#]] [[#testRotateDoubleFn]]
230242
// CHECK-SPIRV: GroupNonUniformRotateKHR [[double]] {{[0-9]+}} [[ScopeSubgroup]] [[double_0]] [[int_2]]
231243
// CHECK-SPIRV: GroupNonUniformRotateKHR [[double]] {{[0-9]+}} [[ScopeSubgroup]] [[double_0]] [[int_2]] [[int_4]]
232244
// CHECK-SPIRV: FunctionEnd

‎llvm-spirv/test/image-unoptimized.cl‎

Lines changed: 2 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -3,11 +3,13 @@
33
// RUN: llvm-spirv %t.spv -to-text -o - | FileCheck %s
44
// RUN: spirv-val %t.spv
55

6+
// CHECK: Name [[#TestFn:]] "__clang_ocl_kern_imp_test_fn"
67
// CHECK: TypeImage [[TypeImage:[0-9]+]]
78
// CHECK: TypeSampler [[TypeSampler:[0-9]+]]
89
// CHECK: TypePointer [[TypeImagePtr:[0-9]+]] {{[0-9]+}} [[TypeImage]]
910
// CHECK: TypePointer [[TypeSamplerPtr:[0-9]+]] {{[0-9]+}} [[TypeSampler]]
1011

12+
// CHECK: Function [[#]] [[#TestFn]]
1113
// CHECK: FunctionParameter [[TypeImage]] [[srcimg:[0-9]+]]
1214
// CHECK: FunctionParameter [[TypeSampler]] [[sampler:[0-9]+]]
1315

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

Lines changed: 16 additions & 10 deletions
Original file line numberDiff line numberDiff line change
@@ -5,70 +5,76 @@
55
// RUN: llvm-spirv -r %t.spv -o %t.rev.bc
66
// RUN: llvm-dis < %t.rev.bc | FileCheck %s --check-prefix=CHECK-LLVM
77

8+
// CHECK-SPIRV-DAG: Name [[#__clang_ocl_kern_imp_testSDiv:]] "__clang_ocl_kern_imp_testSDiv"
9+
// CHECK-SPIRV-DAG: Name [[#__clang_ocl_kern_imp_testUDiv:]] "__clang_ocl_kern_imp_testUDiv"
10+
// CHECK-SPIRV-DAG: Name [[#__clang_ocl_kern_imp_testFDiv:]] "__clang_ocl_kern_imp_testFDiv"
11+
// CHECK-SPIRV-DAG: Name [[#__clang_ocl_kern_imp_testSRem:]] "__clang_ocl_kern_imp_testSRem"
12+
// CHECK-SPIRV-DAG: Name [[#__clang_ocl_kern_imp_testUMod:]] "__clang_ocl_kern_imp_testUMod"
13+
814
// CHECK-SPIRV-DAG: TypeInt [[int:[0-9]+]] 32 0
915
// CHECK-SPIRV-DAG: TypeVector [[int2:[0-9]+]] [[int]] 2
1016
// CHECK-SPIRV-DAG: TypeFloat [[float:[0-9]+]] 32
1117
// CHECK-SPIRV-DAG: TypeVector [[float2:[0-9]+]] [[float]] 2
1218

13-
// CHECK-SPIRV-LABEL: 5 Function
19+
// CHECK-SPIRV: Function [[#]] [[#__clang_ocl_kern_imp_testSDiv]]
1420
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[A:[0-9]+]]
1521
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[B:[0-9]+]]
1622
// CHECK-SPIRV: SDiv [[int2]] {{[0-9]+}} [[A]] [[B]]
1723
// CHECK-SPIRV: FunctionEnd
1824

19-
// CHECK-LLVM-LABEL: @testSDiv
25+
// CHECK-LLVM-LABEL: @__clang_ocl_kern_imp_testSDiv
2026
// CHECK-LLVM: sdiv <2 x i32> %a, %b
2127

2228
kernel void testSDiv(int2 a, int2 b, global int2 *res) {
2329
res[0] = a / b;
2430
}
2531

26-
// CHECK-SPIRV-LABEL: 5 Function
32+
// CHECK-SPIRV: Function [[#]] [[#__clang_ocl_kern_imp_testUDiv]]
2733
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[A:[0-9]+]]
2834
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[B:[0-9]+]]
2935
// CHECK-SPIRV: UDiv [[int2]] {{[0-9]+}} [[A]] [[B]]
3036
// CHECK-SPIRV: FunctionEnd
3137

32-
// CHECK-LLVM-LABEL: @testUDiv
38+
// CHECK-LLVM-LABEL: @__clang_ocl_kern_imp_testUDiv
3339
// CHECK-LLVM: udiv <2 x i32> %a, %b
3440

3541
kernel void testUDiv(uint2 a, uint2 b, global uint2 *res) {
3642
res[0] = a / b;
3743
}
3844

39-
// CHECK-SPIRV-LABEL: 5 Function
45+
// CHECK-SPIRV: Function [[#]] [[#__clang_ocl_kern_imp_testFDiv]]
4046
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[A:[0-9]+]]
4147
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[B:[0-9]+]]
4248
// CHECK-SPIRV: FDiv [[float2]] {{[0-9]+}} [[A]] [[B]]
4349
// CHECK-SPIRV: FunctionEnd
4450

45-
// CHECK-LLVM-LABEL: @testFDiv
51+
// CHECK-LLVM-LABEL: @__clang_ocl_kern_imp_testFDiv
4652
// CHECK-LLVM: fdiv <2 x float> %a, %b
4753

4854
kernel void testFDiv(float2 a, float2 b, global float2 *res) {
4955
res[0] = a / b;
5056
}
5157

52-
// CHECK-SPIRV-LABEL: 5 Function
58+
// CHECK-SPIRV: Function [[#]] [[#__clang_ocl_kern_imp_testSRem]]
5359
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[A:[0-9]+]]
5460
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[B:[0-9]+]]
5561
// CHECK-SPIRV: SRem [[int2]] {{[0-9]+}} [[A]] [[B]]
5662
// CHECK-SPIRV: FunctionEnd
5763

58-
// CHECK-LLVM-LABEL: @testSRem
64+
// CHECK-LLVM-LABEL: @__clang_ocl_kern_imp_testSRem
5965
// CHECK-LLVM: srem <2 x i32> %a, %b
6066

6167
kernel void testSRem(int2 a, int2 b, global int2 *res) {
6268
res[0] = a % b;
6369
}
6470

65-
// CHECK-SPIRV-LABEL: 5 Function
71+
// CHECK-SPIRV: Function [[#]] [[#__clang_ocl_kern_imp_testUMod]]
6672
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[A:[0-9]+]]
6773
// CHECK-SPIRV-NEXT: FunctionParameter {{[0-9]+}} [[B:[0-9]+]]
6874
// CHECK-SPIRV: UMod [[int2]] {{[0-9]+}} [[A]] [[B]]
6975
// CHECK-SPIRV: FunctionEnd
7076

71-
// CHECK-LLVM-LABEL: @testUMod
77+
// CHECK-LLVM-LABEL: @__clang_ocl_kern_imp_testUMod
7278
// CHECK-LLVM: urem <2 x i32> %a, %b
7379

7480
kernel void testUMod(uint2 a, uint2 b, global uint2 *res) {

0 commit comments

Comments
 (0)