Skip to content

Commit afe4c53

Browse files
jsjijsji
committed
Merge commit '3a353b1faa83' into llvmspirv_pulldown
 Conflicts: sycl/test/check_device_code/extensions/address_cast.cpp sycl/test/check_device_code/vector/as.cpp sycl/test/check_device_code/vector/bf16_builtins.cpp sycl/test/check_device_code/vector/bf16_builtins_preview.cpp sycl/test/check_device_code/vector/convert_bfloat.cpp sycl/test/check_device_code/vector/convert_bfloat_preview.cpp sycl/test/check_device_code/vector/math_ops.cpp sycl/test/check_device_code/vector/math_ops_preview.cpp
2 parents bd2d590 + 3a353b1 commit afe4c53

File tree

8 files changed

+54
-53
lines changed

8 files changed

+54
-53
lines changed

‎clang/test/CodeGenSYCL/sub-group-size.cpp

+2-2
Original file line numberDiff line numberDiff line change
@@ -15,15 +15,15 @@ using namespace sycl;
1515
// ALL-DAG: define {{.*}}spir_func void @{{.*}}external_10{{.*}}() #{{[0-9]+}}{{.*}} !intel_reqd_sub_group_size ![[TEN:[0-9]+]]
1616

1717
SYCL_EXTERNAL void external_default_behavior() {}
18-
// NONE-DAG: define {{.*}}spir_func void @{{.*}}external_default_behavior{{.*}}() #{{[0-9]+}} !srcloc !{{[0-9]+}} !sycl_fixed_targets !{{[0-9]+}} {
18+
// NONE-DAG: define {{.*}}spir_func void @{{.*}}external_default_behavior{{.*}}() #{{[0-9]+}} !sycl_fixed_targets !{{[0-9]+}} {
1919
// PRIM_DEF-DAG: define {{.*}}spir_func void @{{.*}}external_default_behavior{{.*}}() #{{[0-9]+}}{{.*}} !intel_reqd_sub_group_size ![[PRIMARY]]
2020
// TEN_DEF-DAG: define {{.*}}spir_func void @{{.*}}external_default_behavior{{.*}}() #{{[0-9]+}}{{.*}} !intel_reqd_sub_group_size ![[TEN]]
2121

2222
void default_behavior() {
2323
kernel_single_task<class Kernel1>([]() {
2424
});
2525
}
26-
// NONE-DAG: define {{.*}}spir_kernel void @{{.*}}Kernel1() #{{[0-9]+}} !srcloc !{{[0-9]+}} !kernel_arg_buffer_location !{{[0-9]+}} !sycl_fixed_targets !{{[0-9]+}} {
26+
// NONE-DAG: define {{.*}}spir_kernel void @{{.*}}Kernel1() #{{[0-9]+}} !kernel_arg_buffer_location !{{[0-9]+}} !sycl_fixed_targets !{{[0-9]+}} {
2727
// PRIM_DEF-DAG: define {{.*}}spir_kernel void @{{.*}}Kernel1() #{{[0-9]+}}{{.*}} !intel_reqd_sub_group_size ![[PRIMARY]]
2828
// TEN_DEF-DAG: define {{.*}}spir_kernel void @{{.*}}Kernel1() #{{[0-9]+}}{{.*}} !intel_reqd_sub_group_size ![[TEN]]
2929

‎llvm/lib/SYCLLowerIR/CleanupSYCLMetadata.cpp

+8-3
Original file line numberDiff line numberDiff line change
@@ -24,8 +24,7 @@
2424
using namespace llvm;
2525

2626
namespace {
27-
28-
void cleanupSYCLCompilerMetadata(const Module &M, llvm::StringRef MD) {
27+
void cleanupSYCLCompilerModuleMetadata(const Module &M, llvm::StringRef MD) {
2928
NamedMDNode *Node = M.getNamedMetadata(MD);
3029
if (!Node)
3130
return;
@@ -65,7 +64,13 @@ PreservedAnalyses CleanupSYCLMetadataPass::run(Module &M,
6564
SmallVector<StringRef, 2> ModuleMDToRemove = {"sycl_aspects",
6665
"sycl_types_that_use_aspects"};
6766
for (const auto &MD : ModuleMDToRemove)
68-
cleanupSYCLCompilerMetadata(M, MD);
67+
cleanupSYCLCompilerModuleMetadata(M, MD);
68+
69+
// Cleanup no longer needed function metadata.
70+
for (auto &F : M) {
71+
if (F.getMetadata("srcloc"))
72+
F.setMetadata("srcloc", nullptr);
73+
}
6974

7075
return PreservedAnalyses::all();
7176
}

‎llvm/test/SYCLLowerIR/CleanupSYCLCompilerInternalMetadata/sycl-function-metadata.ll

+30
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,30 @@
1+
; RUN: opt -passes=cleanup-sycl-metadata -S < %s | FileCheck %s
2+
;
3+
; Test checks that the pass is able to cleanup srcloc metadata
4+
; function metadata
5+
6+
; CHECK-NOT: srcloc
7+
8+
; ModuleID = 'test.cpp'
9+
source_filename = "test.cpp"
10+
target datalayout = "e-i64:64-v16:16-v24:32-v32:32-v48:64-v96:128-v192:256-v256:256-v512:512-v1024:1024-n8:16:32:64-G1"
11+
target triple = "spir64-unknown-unknown"
12+
13+
$_ZNK13KernelFunctorclEv = comdat any
14+
15+
define dso_local spir_func void @_Z6func10v() !sycl_declared_aspects !1 !srcloc !2 {
16+
entry:
17+
ret void
18+
}
19+
20+
21+
define linkonce_odr spir_func void @_ZNK13KernelFunctorclEv() !sycl_declared_aspects !3 !srcloc !4 {
22+
entry:
23+
call spir_func void @_Z6func10v()
24+
ret void
25+
}
26+
27+
!1 = !{i32 5}
28+
!2 = !{i32 2457}
29+
!3 = !{i32 1}
30+
!4 = !{i32 2547}

‎sycl/test/check_device_code/atomic_ref.cpp

+1-1
Original file line numberDiff line numberDiff line change
@@ -4,7 +4,7 @@
44
#include <sycl/sycl.hpp>
55

66
// CHECK-LABEL: define dso_local spir_func noundef i32 @_Z17atomic_ref_globalRi(
7-
// CHECK-SAME: ptr addrspace(4) noundef align 4 dereferenceable(4) [[I:%.*]]) local_unnamed_addr #[[ATTR0:[0-9]+]] !srcloc [[META6:![0-9]+]] !sycl_fixed_targets [[META7:![0-9]+]] {
7+
// CHECK-SAME: ptr addrspace(4) noundef align 4 dereferenceable(4) [[I:%.*]]) local_unnamed_addr #[[ATTR0:[0-9]+]] !sycl_fixed_targets [[META6:![0-9]+]] {
88
// CHECK-NEXT: [[ENTRY:.*:]]
99
// CHECK-NEXT: [[TMP:%.*]] = addrspacecast ptr addrspace(4) [[I]] to ptr addrspace(1)
1010
// CHECK-NEXT: [[CALL3_I_I:%.*]] = tail call spir_func noundef i32 @_Z18__spirv_AtomicLoadPU3AS1KiN5__spv5Scope4FlagENS1_19MemorySemanticsMask4FlagE(ptr addrspace(1) noundef [[TMP]], i32 noundef 1, i32 noundef 898) #[[ATTR4:[0-9]+]]

‎sycl/test/check_device_code/bf16_vector_conversion.cpp

+12-12
Original file line numberDiff line numberDiff line change
@@ -10,7 +10,7 @@ using namespace sycl;
1010
using bfloat16 = sycl::ext::oneapi::bfloat16;
1111

1212
// CHECK-LABEL: define dso_local spir_func void @_Z10TestBFtoF1PN4sycl3_V13ext6oneapi8bfloat16EPf(
13-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0:[0-9]+]] !srcloc [[META5:![0-9]+]] !sycl_fixed_targets [[META6:![0-9]+]] {
13+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0:[0-9]+]] !sycl_fixed_targets [[META6:![0-9]+]] {
1414
// CHECK-NEXT: entry:
1515
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertBF16ToFINTELVec1(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2:[0-9]+]]
1616
// CHECK-NEXT: ret void
@@ -20,7 +20,7 @@ SYCL_EXTERNAL auto TestBFtoF1(bfloat16 *a, float *b) {
2020
}
2121

2222
// CHECK-LABEL: define dso_local spir_func void @_Z10TestFtoBF1PfPN4sycl3_V13ext6oneapi8bfloat16Ei(
23-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META7:![0-9]+]] !sycl_fixed_targets [[META6]] {
23+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
2424
// CHECK-NEXT: entry:
2525
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertFToBF16INTELVec1(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
2626
// CHECK-NEXT: ret void
@@ -30,7 +30,7 @@ SYCL_EXTERNAL auto TestFtoBF1(float *a, bfloat16 *b, int size) {
3030
}
3131

3232
// CHECK-LABEL: define dso_local spir_func void @_Z10TestBFtoF2PN4sycl3_V13ext6oneapi8bfloat16EPf(
33-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META8:![0-9]+]] !sycl_fixed_targets [[META6]] {
33+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
3434
// CHECK-NEXT: entry:
3535
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertBF16ToFINTELVec2(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
3636
// CHECK-NEXT: ret void
@@ -40,7 +40,7 @@ SYCL_EXTERNAL auto TestBFtoF2(bfloat16 *a, float *b) {
4040
}
4141

4242
// CHECK-LABEL: define dso_local spir_func void @_Z10TestFtoBF2PfPN4sycl3_V13ext6oneapi8bfloat16Ei(
43-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META9:![0-9]+]] !sycl_fixed_targets [[META6]] {
43+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
4444
// CHECK-NEXT: entry:
4545
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertFToBF16INTELVec2(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
4646
// CHECK-NEXT: ret void
@@ -50,7 +50,7 @@ SYCL_EXTERNAL auto TestFtoBF2(float *a, bfloat16 *b, int size) {
5050
}
5151

5252
// CHECK-LABEL: define dso_local spir_func void @_Z10TestBFtoF3PN4sycl3_V13ext6oneapi8bfloat16EPf(
53-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META10:![0-9]+]] !sycl_fixed_targets [[META6]] {
53+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
5454
// CHECK-NEXT: entry:
5555
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertBF16ToFINTELVec3(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
5656
// CHECK-NEXT: ret void
@@ -60,7 +60,7 @@ SYCL_EXTERNAL auto TestBFtoF3(bfloat16 *a, float *b) {
6060
}
6161

6262
// CHECK-LABEL: define dso_local spir_func void @_Z10TestFtoBF3PfPN4sycl3_V13ext6oneapi8bfloat16Ei(
63-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META11:![0-9]+]] !sycl_fixed_targets [[META6]] {
63+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
6464
// CHECK-NEXT: entry:
6565
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertFToBF16INTELVec3(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
6666
// CHECK-NEXT: ret void
@@ -70,7 +70,7 @@ SYCL_EXTERNAL auto TestFtoBF3(float *a, bfloat16 *b, int size) {
7070
}
7171

7272
// CHECK-LABEL: define dso_local spir_func void @_Z10TestBFtoF4PN4sycl3_V13ext6oneapi8bfloat16EPf(
73-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META12:![0-9]+]] !sycl_fixed_targets [[META6]] {
73+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
7474
// CHECK-NEXT: entry:
7575
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertBF16ToFINTELVec4(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
7676
// CHECK-NEXT: ret void
@@ -80,7 +80,7 @@ SYCL_EXTERNAL auto TestBFtoF4(bfloat16 *a, float *b) {
8080
}
8181

8282
// CHECK-LABEL: define dso_local spir_func void @_Z10TestFtoBF4PfPN4sycl3_V13ext6oneapi8bfloat16Ei(
83-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META13:![0-9]+]] !sycl_fixed_targets [[META6]] {
83+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
8484
// CHECK-NEXT: entry:
8585
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertFToBF16INTELVec4(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
8686
// CHECK-NEXT: ret void
@@ -90,7 +90,7 @@ SYCL_EXTERNAL auto TestFtoBF4(float *a, bfloat16 *b, int size) {
9090
}
9191

9292
// CHECK-LABEL: define dso_local spir_func void @_Z10TestBFtoF8PN4sycl3_V13ext6oneapi8bfloat16EPf(
93-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META14:![0-9]+]] !sycl_fixed_targets [[META6]] {
93+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
9494
// CHECK-NEXT: entry:
9595
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertBF16ToFINTELVec8(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
9696
// CHECK-NEXT: ret void
@@ -100,7 +100,7 @@ SYCL_EXTERNAL auto TestBFtoF8(bfloat16 *a, float *b) {
100100
}
101101

102102
// CHECK-LABEL: define dso_local spir_func void @_Z10TestFtoBF8PfPN4sycl3_V13ext6oneapi8bfloat16Ei(
103-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META15:![0-9]+]] !sycl_fixed_targets [[META6]] {
103+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
104104
// CHECK-NEXT: entry:
105105
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertFToBF16INTELVec8(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
106106
// CHECK-NEXT: ret void
@@ -110,7 +110,7 @@ SYCL_EXTERNAL auto TestFtoBF8(float *a, bfloat16 *b, int size) {
110110
}
111111

112112
// CHECK-LABEL: define dso_local spir_func void @_Z11TestBFtoF16PN4sycl3_V13ext6oneapi8bfloat16EPf(
113-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META16:![0-9]+]] !sycl_fixed_targets [[META6]] {
113+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
114114
// CHECK-NEXT: entry:
115115
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertBF16ToFINTELVec16(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
116116
// CHECK-NEXT: ret void
@@ -120,7 +120,7 @@ SYCL_EXTERNAL auto TestBFtoF16(bfloat16 *a, float *b) {
120120
}
121121

122122
// CHECK-LABEL: define dso_local spir_func void @_Z11TestFtoBF16PfPN4sycl3_V13ext6oneapi8bfloat16Ei(
123-
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !srcloc [[META17:![0-9]+]] !sycl_fixed_targets [[META6]] {
123+
// CHECK-SAME: ptr addrspace(4) noundef [[A:%.*]], ptr addrspace(4) noundef [[B:%.*]], i32 noundef [[SIZE:%.*]]) local_unnamed_addr #[[ATTR0]] !sycl_fixed_targets [[META6]] {
124124
// CHECK-NEXT: entry:
125125
// CHECK-NEXT: tail call spir_func void @__devicelib_ConvertFToBF16INTELVec16(ptr addrspace(4) noundef [[A]], ptr addrspace(4) noundef [[B]]) #[[ATTR2]]
126126
// CHECK-NEXT: ret void

‎sycl/test/check_device_code/device_has_func.cpp

-17
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,5 @@
11
// RUN: %clangxx -fsycl -Xclang -fsycl-is-device -fsycl-device-only -Xclang -fno-sycl-early-optimizations -S -emit-llvm %s -o %t.ll
22
// RUN: FileCheck %s --input-file %t.ll --check-prefix=CHECK-ASPECTS
3-
// RUN: FileCheck %s --input-file %t.ll --check-prefix=CHECK-SRCLOC
43

54
// Tests for IR of device_has(aspect, ...) attribute and
65
// !sycl_used_aspects metadata.
@@ -11,37 +10,30 @@
1110
using namespace sycl;
1211

1312
// CHECK-ASPECTS: define dso_local spir_func void @{{.*}}kernel_name_1{{.*}} !sycl_declared_aspects ![[ASPECTS1:[0-9]+]] {{.*}}
14-
// CHECK-SRCLOC: define dso_local spir_func void @{{.*}}kernel_name_1{{.*}} !srcloc ![[SRCLOC1:[0-9]+]] {{.*}}
1513

1614
// CHECK-ASPECTS: define {{.*}}spir_func void @{{.*}}func1{{.*}} !sycl_declared_aspects ![[ASPECTS1]]
1715
// CHECK-ASPECTS-SAME: !sycl_used_aspects ![[ASPECTS1]]
18-
// CHECK-SRCLOC: define {{.*}}spir_func void @{{.*}}func1{{.*}} !srcloc ![[SRCLOC2:[0-9]+]]
1916
[[sycl::device_has(sycl::aspect::cpu)]] void func1() {}
2017

2118
// CHECK-ASPECTS: define {{.*}}spir_func void @{{.*}}func2{{.*}} !sycl_declared_aspects ![[ASPECTS2:[0-9]+]]
2219
// CHECK-ASPECTS-SAME: !sycl_used_aspects ![[ASPECTS2]]
23-
// CHECK-SRCLOC: define {{.*}}spir_func void @{{.*}}func2{{.*}} !srcloc ![[SRCLOC3:[0-9]+]]
2420
[[sycl::device_has(sycl::aspect::fp16, sycl::aspect::gpu)]] void func2() {}
2521

2622
// CHECK-ASPECTS: define {{.*}}spir_func void @{{.*}}func3{{.*}} !sycl_declared_aspects ![[EMPTYASPECTS:[0-9]+]]
27-
// CHECK-SRCLOC: define {{.*}}spir_func void @{{.*}}func3{{.*}} !srcloc ![[SRCLOC4:[0-9]+]]
2823
[[sycl::device_has()]] void func3() {}
2924

3025
// CHECK-ASPECTS: define {{.*}}spir_func void @{{.*}}func4{{.*}} !sycl_declared_aspects ![[ASPECTS3:[0-9]+]]
3126
// CHECK-ASPECTS-SAME: !sycl_used_aspects ![[ASPECTS3]]
32-
// CHECK-SRCLOC: define {{.*}}spir_func void @{{.*}}func4{{.*}} !srcloc ![[SRCLOC5:[0-9]+]]
3327
template <sycl::aspect Aspect> [[sycl::device_has(Aspect)]] void func4() {}
3428

3529
// CHECK-ASPECTS: define {{.*}}spir_func void @{{.*}}func5{{.*}} !sycl_declared_aspects ![[ASPECTS1]]
3630
// CHECK-ASPECTS-SAME: !sycl_used_aspects ![[ASPECTS1]]
37-
// CHECK-SRCLOC: define {{.*}}spir_func void @{{.*}}func5{{.*}} !srcloc ![[SRCLOC6:[0-9]+]]
3831
[[sycl::device_has(sycl::aspect::cpu)]] void func5();
3932
void func5() {}
4033

4134
constexpr sycl::aspect getAspect() { return sycl::aspect::cpu; }
4235
// CHECK-ASPECTS: define {{.*}}spir_func void @{{.*}}func6{{.*}} !sycl_declared_aspects ![[ASPECTS1]]
4336
// CHECK-ASPECTS-SAME: !sycl_used_aspects ![[ASPECTS1]]
44-
// CHECK-SRCLOC: define {{.*}}spir_func void @{{.*}}func6{{.*}} !srcloc ![[SRCLOC7:[0-9]+]]
4537
[[sycl::device_has(getAspect())]] void func6() {}
4638

4739
SYCL_EXTERNAL [[sycl::device_has(sycl::aspect::cpu)]] void kernel_name_1() {
@@ -54,23 +46,14 @@ SYCL_EXTERNAL [[sycl::device_has(sycl::aspect::cpu)]] void kernel_name_1() {
5446
}
5547

5648
// CHECK-ASPECTS: define dso_local spir_func void @{{.*}}kernel_name_2{{.*}} !sycl_declared_aspects ![[ASPECTS4:[0-9]+]]
57-
// CHECK-SRCLOC: define dso_local spir_func void @{{.*}}kernel_name_2{{.*}} !srcloc ![[SRCLOC8:[0-9]+]] {{.*}}
5849
SYCL_EXTERNAL [[sycl::device_has(sycl::aspect::gpu)]] void kernel_name_2() {}
5950

6051
// CHECK-ASPECTS-DAG: [[ASPECTS1]] = !{![[ASPECTCPU:[0-9]+]]}
6152
// CHECK-ASPECTS-DAG: [[ASPECTCPU]] = !{!"cpu", i32 1}
62-
// CHECK-SRCLOC-DAG: [[SRCLOC1]] = !{i32 {{[0-9]+}}}
6353
// CHECK-ASPECTS-DAG: [[EMPTYASPECTS]] = !{}
64-
// CHECK-SRCLOC-DAG: [[SRCLOC2]] = !{i32 {{[0-9]+}}}
6554
// CHECK-ASPECTS-DAG: [[ASPECTS2]] = !{![[ASPECTFP16:[0-9]+]], ![[ASPECTGPU:[0-9]+]]}
6655
// CHECK-ASPECTS-DAG: [[ASPECTFP16]] = !{!"fp16", i32 5}
6756
// CHECK-ASPECTS-DAG: [[ASPECTGPU]] = !{!"gpu", i32 2}
68-
// CHECK-SRCLOC-DAG: [[SRCLOC3]] = !{i32 {{[0-9]+}}}
69-
// CHECK-SRCLOC-DAG: [[SRCLOC4]] = !{i32 {{[0-9]+}}}
7057
// CHECK-ASPECTS-DAG: [[ASPECTS3]] = !{![[ASPECTHOST:[0-9]+]]}
7158
// CHECK-ASPECTS-DAG: [[ASPECTHOST]] = !{!"host", i32 0}
72-
// CHECK-SRCLOC-DAG: [[SRCLOC5]] = !{i32 {{[0-9]+}}}
73-
// CHECK-SRCLOC-DAG: [[SRCLOC6]] = !{i32 {{[0-9]+}}}
74-
// CHECK-SRCLOC-DAG: [[SRCLOC7]] = !{i32 {{[0-9]+}}}
7559
// CHECK-ASPECTS-DAG: [[ASPECTS4]] = !{![[ASPECTGPU]]}
76-
// CHECK-SRCLOC-DAG: [[SRCLOC8]] = !{i32 {{[0-9]+}}}

0 commit comments

Comments
 (0)