Skip to content

Commit 9668871

Browse files
elizabethandrewselizabethandrews
authored
[SYCL][NFC] Make tests insensitive to dso_local (#3037)
These tests fail after a recent open-source clang change done to set dso_local in frontend. Signed-off-by: Elizabeth Andrews <[email protected]>
1 parent 9c13694 commit 9668871

Some content is hidden

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

46 files changed

+143
-145
lines changed

‎clang/test/CodeGenSYCL/accessor_inheritance.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -23,7 +23,7 @@ int main() {
2323
// Check kernel parameters
2424
// CHECK: %[[RANGE_TYPE:"struct.*cl::sycl::range"]]
2525
// CHECK: %[[ID_TYPE:"struct.*cl::sycl::id"]]
26-
// CHECK: define spir_kernel void @_ZTSZ4mainE6kernel
26+
// CHECK: define {{.*}}spir_kernel void @_ZTSZ4mainE6kernel
2727
// CHECK-SAME: i32 [[ARG_A:%[a-zA-Z0-9_]+]],
2828
// CHECK-SAME: i32 [[ARG_B:%[a-zA-Z0-9_]+]],
2929
// CHECK-SAME: i8 addrspace(1)* [[ACC1_DATA:%[a-zA-Z0-9_]+]],

‎clang/test/CodeGenSYCL/address-space-new.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -103,7 +103,7 @@ void test() {
103103
//
104104
Y yy;
105105
baz(yy);
106-
// CHECK: define spir_func void @{{.*}}baz{{.*}}
106+
// CHECK: define {{.*}}spir_func void @{{.*}}baz{{.*}}
107107
// CHECK: %[[FIRST:[a-zA-Z0-9]+]] = bitcast %struct.{{.*}}.Y addrspace(4)* %{{.*}} to i8 addrspace(4)*
108108
// CHECK: %[[OFFSET:[a-zA-Z0-9]+]].ptr = getelementptr inbounds i8, i8 addrspace(4)* %[[FIRST]], i64 8
109109
// CHECK: %[[SECOND:[a-zA-Z0-9]+]] = bitcast i8 addrspace(4)* %[[OFFSET]].ptr to %struct.{{.*}}.HasX addrspace(4)*

‎clang/test/CodeGenSYCL/address-space-of-returns.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -26,7 +26,7 @@ A ret_agg() {
2626
A a;
2727
return a;
2828
}
29-
// CHECK: define spir_func void @{{.*}}ret_agg{{.*}}(%struct.{{.*}}.A addrspace(4)* {{.*}} %agg.result)
29+
// CHECK: define {{.*}}spir_func void @{{.*}}ret_agg{{.*}}(%struct.{{.*}}.A addrspace(4)* {{.*}} %agg.result)
3030

3131
template <typename name, typename Func>
3232
__attribute__((sycl_kernel)) void kernel_single_task(const Func &kernelFunc) {

‎clang/test/CodeGenSYCL/address-space-parameter-conversions.cpp

Lines changed: 8 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -1,20 +1,20 @@
11
// RUN: %clang_cc1 -fsycl -fsycl-is-device -triple spir64-unknown-unknown-sycldevice -disable-llvm-passes -emit-llvm %s -o - | FileCheck %s
22
void bar(int & Data) {}
3-
// CHECK-DAG: define spir_func void @[[RAW_REF:[a-zA-Z0-9_]+]](i32 addrspace(4)* align 4 dereferenceable(4) %
3+
// CHECK-DAG: define {{.*}}spir_func void @[[RAW_REF:[a-zA-Z0-9_]+]](i32 addrspace(4)* align 4 dereferenceable(4) %
44
void bar2(int & Data) {}
5-
// CHECK-DAG: define spir_func void @[[RAW_REF2:[a-zA-Z0-9_]+]](i32 addrspace(4)* align 4 dereferenceable(4) %
5+
// CHECK-DAG: define {{.*}}spir_func void @[[RAW_REF2:[a-zA-Z0-9_]+]](i32 addrspace(4)* align 4 dereferenceable(4) %
66
void bar(__attribute__((opencl_local)) int &Data) {}
7-
// CHECK-DAG: define spir_func void [[LOC_REF:@[a-zA-Z0-9_]+]](i32 addrspace(3)* align 4 dereferenceable(4) %
7+
// CHECK-DAG: define {{.*}}spir_func void [[LOC_REF:@[a-zA-Z0-9_]+]](i32 addrspace(3)* align 4 dereferenceable(4) %
88
void bar3(__attribute__((opencl_global)) int &Data) {}
9-
// CHECK-DAG: define spir_func void @[[GLOB_REF:[a-zA-Z0-9_]+]](i32 addrspace(1)* align 4 dereferenceable(4) %
9+
// CHECK-DAG: define {{.*}}spir_func void @[[GLOB_REF:[a-zA-Z0-9_]+]](i32 addrspace(1)* align 4 dereferenceable(4) %
1010
void foo(int * Data) {}
11-
// CHECK-DAG: define spir_func void @[[RAW_PTR:[a-zA-Z0-9_]+]](i32 addrspace(4)* %
11+
// CHECK-DAG: define {{.*}}spir_func void @[[RAW_PTR:[a-zA-Z0-9_]+]](i32 addrspace(4)* %
1212
void foo2(int * Data) {}
13-
// CHECK-DAG: define spir_func void @[[RAW_PTR2:[a-zA-Z0-9_]+]](i32 addrspace(4)* %
13+
// CHECK-DAG: define {{.*}}spir_func void @[[RAW_PTR2:[a-zA-Z0-9_]+]](i32 addrspace(4)* %
1414
void foo(__attribute__((opencl_local)) int *Data) {}
15-
// CHECK-DAG: define spir_func void [[LOC_PTR:@[a-zA-Z0-9_]+]](i32 addrspace(3)* %
15+
// CHECK-DAG: define {{.*}}spir_func void [[LOC_PTR:@[a-zA-Z0-9_]+]](i32 addrspace(3)* %
1616
void foo3(__attribute__((opencl_global)) int *Data) {}
17-
// CHECK-DAG: define spir_func void @[[GLOB_PTR:[a-zA-Z0-9_]+]](i32 addrspace(1)* %
17+
// CHECK-DAG: define {{.*}}spir_func void @[[GLOB_PTR:[a-zA-Z0-9_]+]](i32 addrspace(1)* %
1818

1919
template<typename T>
2020
void tmpl(T t){}

‎clang/test/CodeGenSYCL/basic-kernel-wrapper.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -19,7 +19,7 @@ int main() {
1919
return 0;
2020
}
2121

22-
// CHECK: define spir_kernel void @{{.*}}kernel_function
22+
// CHECK: define {{.*}}spir_kernel void @{{.*}}kernel_function
2323
// CHECK-SAME: i32 addrspace(1)* [[MEM_ARG:%[a-zA-Z0-9_]+]],
2424
// CHECK-SAME: %"struct.{{.*}}.cl::sycl::range"* byval{{.*}}align 4 [[ACC_RANGE:%[a-zA-Z0-9_]+_1]],
2525
// CHECK-SAME: %"struct.{{.*}}.cl::sycl::range"* byval{{.*}}align 4 [[MEM_RANGE:%[a-zA-Z0-9_]+_2]],

‎clang/test/CodeGenSYCL/device-functions.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -21,7 +21,7 @@ int main() {
2121
kernel_single_task<class fake_kernel>([]() { foo(); });
2222
return 0;
2323
}
24-
// CHECK: define spir_kernel void @_ZTSZ4mainE11fake_kernel()
24+
// CHECK: define {{.*}}spir_kernel void @_ZTSZ4mainE11fake_kernel()
2525
// CHECK: define internal spir_func void @"_ZZ4mainENK3$_0clEv"(%"class.{{.*}}.anon" addrspace(4)* {{[^,]*}} %this)
26-
// CHECK: define spir_func void @_Z3foov()
26+
// CHECK: define {{.*}}spir_func void @_Z3foov()
2727
// CHECK: define linkonce_odr spir_func i32 @_Z3barIiET_S0_(i32 %arg)

‎clang/test/CodeGenSYCL/device-indirectly-callable-attr.cpp

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -7,18 +7,18 @@ void foo() {
77
helper();
88
}
99

10-
// CHECK: define spir_func void @{{.*foo.*}}() #[[ATTRS_INDIR_CALL:[0-9]+]]
10+
// CHECK: define {{.*}}spir_func void @{{.*foo.*}}() #[[ATTRS_INDIR_CALL:[0-9]+]]
1111
// CHECK: call spir_func void @{{.*helper.*}}()
1212
//
13-
// CHECK: define spir_func void @{{.*helper.*}}() #[[ATTRS_NOT_INDIR_CALL:[0-9]+]]
13+
// CHECK: define {{.*}}spir_func void @{{.*helper.*}}() #[[ATTRS_NOT_INDIR_CALL:[0-9]+]]
1414
//
1515

1616
int bar20(int a) { return a + 20; }
1717

1818
class A {
1919
public:
2020
// CHECK-DAG: define linkonce_odr spir_func void @_ZN1A3fooEv{{.*}}#[[ATTRS_INDIR_CALL]]
21-
// CHECK-DAG: define spir_func i32 @_Z5bar20{{.*}}#[[ATTRS_NOT_INDIR_CALL]]
21+
// CHECK-DAG: define {{.*}}spir_func i32 @_Z5bar20{{.*}}#[[ATTRS_NOT_INDIR_CALL]]
2222
[[intel::device_indirectly_callable]] void foo() { bar20(10); }
2323

2424
// CHECK-DAG: define linkonce_odr spir_func void @_ZN1AC1Ev{{.*}}#[[ATTRS_INDIR_CALL_1:[0-9]+]]

‎clang/test/CodeGenSYCL/emit-kernel-in-virtual-func.cpp

Lines changed: 1 addition & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -26,5 +26,4 @@ int main() {
2626
}
2727

2828
// Ensure that the SPIR-Kernel function is actually emitted.
29-
// CHECK: define spir_kernel void @_ZTSZN7DERIVEDIiE10initializeEvE2FF
30-
29+
// CHECK: define {{.*}}spir_kernel void @_ZTSZN7DERIVEDIiE10initializeEvE2FF

‎clang/test/CodeGenSYCL/emit-kernel-in-virtual-func2.cpp

Lines changed: 1 addition & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -31,5 +31,4 @@ int main() {
3131
}
3232

3333
// Ensure that the SPIR-Kernel function is actually emitted.
34-
// CHECK: define spir_kernel void @_ZTSZ2TTIiEvvE2PP
35-
34+
// CHECK: define {{.*}}spir_kernel void @_ZTSZ2TTIiEvvE2PP

‎clang/test/CodeGenSYCL/esimd-accessor-ptr-md.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -30,7 +30,7 @@ void test(int val) {
3030
});
3131

3232
// --- Name
33-
// CHECK-LABEL: define spir_kernel void @"_ZTSZZ4testiENK3$_0clERN2cl4sycl7handlerEE12esimd_kernel"(
33+
// CHECK-LABEL: define {{.*}}spir_kernel void @"_ZTSZZ4testiENK3$_0clERN2cl4sycl7handlerEE12esimd_kernel"(
3434
// --- Signature
3535
// CHECK: i32 addrspace(1)* "VCArgumentDesc"="buffer_t" "VCArgumentIOKind"="0" "VCArgumentKind"="2" %_arg_,
3636
// CHECK: i32 "VCArgumentDesc" "VCArgumentIOKind"="0" "VCArgumentKind"="0" %_arg_1,

‎clang/test/CodeGenSYCL/esimd_metadata1.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -15,7 +15,7 @@ void kernel(const Func &f) __attribute__((sycl_kernel)) {
1515

1616
void bar() {
1717
kernel<class MyKernel>([=]() __attribute__((sycl_explicit_simd)){});
18-
// CHECK: define spir_kernel void @_ZTSZ3barvE8MyKernel() {{.*}} !sycl_explicit_simd ![[EMPTY:[0-9]+]] !intel_reqd_sub_group_size ![[REQD_SIZE:[0-9]+]]
18+
// CHECK: define {{.*}}spir_kernel void @_ZTSZ3barvE8MyKernel() {{.*}} !sycl_explicit_simd ![[EMPTY:[0-9]+]] !intel_reqd_sub_group_size ![[REQD_SIZE:[0-9]+]]
1919
}
2020

2121
// CHECK: !spirv.Source = !{[[LANG:![0-9]+]]}

‎clang/test/CodeGenSYCL/esimd_metadata2.cpp

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -11,9 +11,9 @@ __attribute__((sycl_device)) void shared_func() { shared_func_decl(); }
1111

1212
__attribute__((sycl_device)) __attribute__((sycl_explicit_simd)) void esimd_func() { shared_func(); }
1313

14-
// CHECK-ESIMD-DAG: define spir_kernel void @{{.*}}kernel_cm() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {{.*}} !intel_reqd_sub_group_size ![[SGSIZE1:[0-9]+]] {{.*}}{
15-
// CHECK-ESIMD-DAG: define spir_func void @{{.*}}esimd_funcv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {
16-
// CHECK-ESIMD-DAG: define spir_func void @{{.*}}shared_funcv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {
14+
// CHECK-ESIMD-DAG: define {{.*}}spir_kernel void @{{.*}}kernel_cm() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {{.*}} !intel_reqd_sub_group_size ![[SGSIZE1:[0-9]+]] {{.*}}{
15+
// CHECK-ESIMD-DAG: define {{.*}}spir_func void @{{.*}}esimd_funcv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {
16+
// CHECK-ESIMD-DAG: define {{.*}}spir_func void @{{.*}}shared_funcv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {
1717
// CHECK-ESIMD-DAG: define linkonce_odr spir_func void @_ZN12ESIMDFunctorclEv({{.*}}) #{{[0-9]+}} {{.*}} !sycl_explicit_simd !{{[0-9]+}} {
1818
// CHECK-ESIMD-DAG: declare spir_func void @{{.*}}shared_func_declv() #{{[0-9]+}}
1919

‎clang/test/CodeGenSYCL/esimd_metadata3.cpp

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -3,5 +3,5 @@
33
__attribute__((sycl_device)) void funcWithSpirvIntrin() {}
44
__attribute__((sycl_device)) __attribute__((sycl_explicit_simd)) void standaloneCmFunc() { funcWithSpirvIntrin(); }
55

6-
// CHECK-ESIMD-DAG: define spir_func void @{{.*}}funcWithSpirvIntrinv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {
7-
// CHECK-ESIMD-DAG: define spir_func void @{{.*}}standaloneCmFuncv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {
6+
// CHECK-ESIMD-DAG: define {{.*}}spir_func void @{{.*}}funcWithSpirvIntrinv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {
7+
// CHECK-ESIMD-DAG: define {{.*}}spir_func void @{{.*}}standaloneCmFuncv() #{{[0-9]+}} !sycl_explicit_simd !{{[0-9]+}} {

‎clang/test/CodeGenSYCL/image_accessor.cpp

Lines changed: 6 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -7,27 +7,27 @@
77
// RUN: FileCheck < %t.ll --enable-var-scope %s --check-prefix=CHECK-3DWO
88
//
99
// CHECK-1DRO: %opencl.image1d_ro_t = type opaque
10-
// CHECK-1DRO: define spir_kernel void @{{.*}}(%opencl.image1d_ro_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
10+
// CHECK-1DRO: define {{.*}}spir_kernel void @{{.*}}(%opencl.image1d_ro_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
1111
// CHECK-1DRO: call spir_func void @{{.*}}__init{{.*}}(%{{.*}}cl::sycl::accessor{{.*}} %{{[0-9]+}}, %opencl.image1d_ro_t addrspace(1)* %{{[0-9]+}})
1212
//
1313
// CHECK-2DRO: %opencl.image2d_ro_t = type opaque
14-
// CHECK-2DRO: define spir_kernel void @{{.*}}(%opencl.image2d_ro_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
14+
// CHECK-2DRO: define {{.*}}spir_kernel void @{{.*}}(%opencl.image2d_ro_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
1515
// CHECK-2DRO: call spir_func void @{{.*}}__init{{.*}}(%{{.*}}cl::sycl::accessor{{.*}} %{{[0-9]+}}, %opencl.image2d_ro_t addrspace(1)* %{{[0-9]+}})
1616
//
1717
// CHECK-3DRO: %opencl.image3d_ro_t = type opaque
18-
// CHECK-3DRO: define spir_kernel void @{{.*}}(%opencl.image3d_ro_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
18+
// CHECK-3DRO: define {{.*}}spir_kernel void @{{.*}}(%opencl.image3d_ro_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
1919
// CHECK-3DRO: call spir_func void @{{.*}}__init{{.*}}(%{{.*}}cl::sycl::accessor{{.*}} %{{[0-9]+}}, %opencl.image3d_ro_t addrspace(1)* %{{[0-9]+}})
2020
//
2121
// CHECK-1DWO: %opencl.image1d_wo_t = type opaque
22-
// CHECK-1DWO: define spir_kernel void @{{.*}}(%opencl.image1d_wo_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
22+
// CHECK-1DWO: define {{.*}}spir_kernel void @{{.*}}(%opencl.image1d_wo_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
2323
// CHECK-1DWO: call spir_func void @{{.*}}__init{{.*}}(%{{.*}}cl::sycl::accessor{{.*}} %{{[0-9]+}}, %opencl.image1d_wo_t addrspace(1)* %{{[0-9]+}})
2424
//
2525
// CHECK-2DWO: %opencl.image2d_wo_t = type opaque
26-
// CHECK-2DWO: define spir_kernel void @{{.*}}(%opencl.image2d_wo_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
26+
// CHECK-2DWO: define {{.*}}spir_kernel void @{{.*}}(%opencl.image2d_wo_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
2727
// CHECK-2DWO: call spir_func void @{{.*}}__init{{.*}}(%{{.*}}cl::sycl::accessor{{.*}} %{{[0-9]+}}, %opencl.image2d_wo_t addrspace(1)* %{{[0-9]+}})
2828
//
2929
// CHECK-3DWO: %opencl.image3d_wo_t = type opaque
30-
// CHECK-3DWO: define spir_kernel void @{{.*}}(%opencl.image3d_wo_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
30+
// CHECK-3DWO: define {{.*}}spir_kernel void @{{.*}}(%opencl.image3d_wo_t addrspace(1)* [[IMAGE_ARG:%[a-zA-Z0-9_]+]])
3131
// CHECK-3DWO: call spir_func void @{{.*}}__init{{.*}}(%{{.*}}cl::sycl::accessor{{.*}} %{{[0-9]+}}, %opencl.image3d_wo_t addrspace(1)* %{{[0-9]+}})
3232
//
3333
// TODO: Add tests for the image_array opencl datatype support.

‎clang/test/CodeGenSYCL/inheritance.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -40,7 +40,7 @@ int main() {
4040
}
4141

4242
// Check kernel paramters
43-
// CHECK: define spir_kernel void @{{.*}}derived(%struct.{{.*}}.base* byval(%struct.{{.*}}.base) align 4 %_arg__base, %struct.{{.*}}.__wrapper_class* byval(%struct.{{.*}}.__wrapper_class) align 8 %_arg_e, i32 %_arg_a)
43+
// CHECK: define {{.*}}spir_kernel void @{{.*}}derived(%struct.{{.*}}.base* byval(%struct.{{.*}}.base) align 4 %_arg__base, %struct.{{.*}}.__wrapper_class* byval(%struct.{{.*}}.__wrapper_class) align 8 %_arg_e, i32 %_arg_a)
4444

4545
// Check alloca for kernel paramters
4646
// CHECK: %[[ARG_A:[a-zA-Z0-9_.]+]] = alloca i32, align 4

‎clang/test/CodeGenSYCL/intel-fpga-ivdep-array.cpp

Lines changed: 9 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22

33
// Array-specific ivdep - annotate the correspondent GEPs only
44
//
5-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_array_no_safelenv()
5+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_array_no_safelenv()
66
void ivdep_array_no_safelen() {
77
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
88
int a[10];
@@ -18,7 +18,7 @@ void ivdep_array_no_safelen() {
1818
}
1919

2020
// Array-specific ivdep w/ safelen - annotate the correspondent GEPs only
21-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_array_with_safelenv()
21+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_array_with_safelenv()
2222
void ivdep_array_with_safelen() {
2323
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
2424
int a[10];
@@ -35,7 +35,7 @@ void ivdep_array_with_safelen() {
3535

3636
// Multiple array-specific ivdeps - annotate the correspondent GEPs
3737
//
38-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_multiple_arraysv()
38+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_multiple_arraysv()
3939
void ivdep_multiple_arrays() {
4040
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
4141
int a[10];
@@ -63,7 +63,7 @@ void ivdep_multiple_arrays() {
6363

6464
// Global ivdep with INF safelen & array-specific ivdep with the same safelen
6565
//
66-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_array_and_globalv()
66+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_array_and_globalv()
6767
void ivdep_array_and_global() {
6868
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
6969
int a[10];
@@ -81,7 +81,7 @@ void ivdep_array_and_global() {
8181

8282
// Global ivdep with INF safelen & array-specific ivdep with lesser safelen
8383
//
84-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_array_and_inf_globalv()
84+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_array_and_inf_globalv()
8585
void ivdep_array_and_inf_global() {
8686
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
8787
int a[10];
@@ -99,7 +99,7 @@ void ivdep_array_and_inf_global() {
9999

100100
// Global ivdep with specified safelen & array-specific ivdep with lesser safelen
101101
//
102-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_array_and_greater_globalv()
102+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_array_and_greater_globalv()
103103
void ivdep_array_and_greater_global() {
104104
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
105105
int a[10];
@@ -117,7 +117,7 @@ void ivdep_array_and_greater_global() {
117117

118118
// Global safelen, array-specific safelens
119119
//
120-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_mul_arrays_and_globalv()
120+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_mul_arrays_and_globalv()
121121
void ivdep_mul_arrays_and_global() {
122122
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
123123
int a[10];
@@ -138,7 +138,7 @@ void ivdep_mul_arrays_and_global() {
138138
}
139139
}
140140

141-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_ptrv()
141+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_ptrv()
142142
void ivdep_ptr() {
143143
int *ptr;
144144
// CHECK: %[[PTR:[0-9a-z]+]] = alloca i32 addrspace(4)*
@@ -149,7 +149,7 @@ void ivdep_ptr() {
149149
// CHECK: br label %for.cond, !llvm.loop ![[MD_LOOP_PTR:[0-9]+]]
150150
}
151151

152-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_structv()
152+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_structv()
153153
void ivdep_struct() {
154154
struct S {
155155
int *ptr;

‎clang/test/CodeGenSYCL/intel-fpga-ivdep-embedded-loops.cpp

Lines changed: 6 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22

33
// Accesses from the inner loop only, various global safelens for the outer and the inner loops.
44
//
5-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_inner_loop_accessv()
5+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_inner_loop_accessv()
66
void ivdep_inner_loop_access() {
77
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
88
int a[10];
@@ -19,7 +19,7 @@ void ivdep_inner_loop_access() {
1919

2020
// Accesses from both inner and outer loop, same global (INF) safelen for both.
2121
//
22-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_embedded_global_safelenv()
22+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_embedded_global_safelenv()
2323
void ivdep_embedded_global_safelen() {
2424
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
2525
int a[10];
@@ -39,7 +39,7 @@ void ivdep_embedded_global_safelen() {
3939

4040
// Accesses from both inner and outer loop, with various safelens per loop.
4141
//
42-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_embedded_various_safelensv()
42+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_embedded_various_safelensv()
4343
void ivdep_embedded_various_safelens() {
4444
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
4545
int a[10];
@@ -61,7 +61,7 @@ void ivdep_embedded_various_safelens() {
6161
// Outer loop: array-specific ivdeps for all arrays with various safelens
6262
// Inner loop: global ivdep with its own safelen
6363
//
64-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_embedded_multiple_arraysv()
64+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_embedded_multiple_arraysv()
6565
void ivdep_embedded_multiple_arrays() {
6666
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
6767
int a[10];
@@ -90,7 +90,7 @@ void ivdep_embedded_multiple_arrays() {
9090
// As the outer loop's ivdep applies to a particular, other array(s) shouldn't be marked
9191
// into any index group at the outer loop level
9292
//
93-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_embedded_multiple_arrays_globalv()
93+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_embedded_multiple_arrays_globalv()
9494
void ivdep_embedded_multiple_arrays_global() {
9595
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
9696
int a[10];
@@ -114,7 +114,7 @@ void ivdep_embedded_multiple_arrays_global() {
114114
}
115115

116116
// Accesses within each dimension of a multi-dimensional (n > 2) loop
117-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_embedded_multiple_dimensionsv()
117+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_embedded_multiple_dimensionsv()
118118
void ivdep_embedded_multiple_dimensions() {
119119
int a[10];
120120
[[intel::ivdep]] for (int i = 0; i != 10; ++i) {

‎clang/test/CodeGenSYCL/intel-fpga-ivdep-global.cpp

Lines changed: 4 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -2,7 +2,7 @@
22

33
// Global ivdep - annotate all GEPs
44
//
5-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_no_paramv()
5+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_no_paramv()
66
void ivdep_no_param() {
77
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
88
int a[10];
@@ -20,7 +20,7 @@ void ivdep_no_param() {
2020
// Global ivdep - annotate all GEPs
2121
// Make sure that ALL of the relevant GEPs for an array are marked into the array's index groups
2222
//
23-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_no_param_multiple_gepsv()
23+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_no_param_multiple_gepsv()
2424
void ivdep_no_param_multiple_geps() {
2525
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
2626
int a[10];
@@ -42,7 +42,7 @@ void ivdep_no_param_multiple_geps() {
4242

4343
// Global ivdep w/ safelen specified - annotate all GEPs
4444
//
45-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_safelenv()
45+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_safelenv()
4646
void ivdep_safelen() {
4747
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
4848
int a[10];
@@ -59,7 +59,7 @@ void ivdep_safelen() {
5959

6060
// Global ivdep, albeit conflicting safelens - annotate all GEPs
6161
//
62-
// CHECK: define spir_func void @_Z{{[0-9]+}}ivdep_conflicting_safelenv()
62+
// CHECK: define {{.*}}spir_func void @_Z{{[0-9]+}}ivdep_conflicting_safelenv()
6363
void ivdep_conflicting_safelen() {
6464
// CHECK: %[[ARRAY_A:[0-9a-z]+]] = alloca [10 x i32]
6565
int a[10];

‎clang/test/CodeGenSYCL/intel-fpga-mem-builtin.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -12,7 +12,7 @@ struct State {
1212
// CHECK: [[ANN1:@.str[\.]*[0-9]*]] = {{.*}}{params:384}{cache-size:0}
1313
// CHECK: [[ANN2:@.str[\.]*[0-9]*]] = {{.*}}{params:384}{cache-size:127}
1414

15-
// CHECK: define spir_func void @{{.*}}(float addrspace(4)* %A, i32 addrspace(4)* %B, [[STRUCT]] addrspace(4)* %C, [[STRUCT]] addrspace(4)*{{.*}}%D)
15+
// CHECK: define {{.*}}spir_func void @{{.*}}(float addrspace(4)* %A, i32 addrspace(4)* %B, [[STRUCT]] addrspace(4)* %C, [[STRUCT]] addrspace(4)*{{.*}}%D)
1616
void foo(float *A, int *B, State *C, State &D) {
1717
float *x;
1818
int *y;

0 commit comments

Comments
 (0)