Skip to content

Commit b9122b3

Browse files
author
Andrew Lamzed-Short
authored
[SYCL] Updated aspects list to be SYCL 2020 compliant (#8751)
This patch updates the device aspect implementations to account for the changes made in [Section 4.6.4.3](https://registry.khronos.org/SYCL/specs/sycl-2020/html/sycl-2020.html#sec:device-aspects) of the specification. Most changed aspects have been addresses already, so this patch specifically: - Adds default implementations for the `emulated` and `host_debuggable` aspects, returning false for now. These require further device- and/or driver-specific work so are left as is for now. This fixes #8324 - Deprecates `usm_restricted_shared_allocations` aspect as the concept no longer exists, and `host` aspect as "host" device concept removed from SYCL 2020. Deprecated aspects will be removed in later releases.
1 parent 4480f8b commit b9122b3

File tree

9 files changed

+77
-66
lines changed

9 files changed

+77
-66
lines changed

‎sycl/include/sycl/device_aspect_macros.hpp

Lines changed: 10 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -208,6 +208,11 @@
208208
#define __SYCL_ALL_DEVICES_HAVE_39__ 0
209209
#endif
210210

211+
#ifndef __SYCL_ALL_DEVICES_HAVE_40__
212+
// __SYCL_ASPECT(emulated, 40)
213+
#define __SYCL_ALL_DEVICES_HAVE_40__ 0
214+
#endif
215+
211216
#ifndef __SYCL_ANY_DEVICE_HAS_0__
212217
// __SYCL_ASPECT(host, 0)
213218
#define __SYCL_ANY_DEVICE_HAS_0__ 0
@@ -407,3 +412,8 @@
407412
// __SYCL_ASPECT(ext_intel_memory_bus_width, 39)
408413
#define __SYCL_ANY_DEVICE_HAS_39__ 0
409414
#endif
415+
416+
#ifndef __SYCL_ANY_DEVICE_HAS_40__
417+
// __SYCL_ASPECT(emulated, 40)
418+
#define __SYCL_ANY_DEVICE_HAS_40__ 0
419+
#endif

‎sycl/include/sycl/device_aspect_traits.hpp

Lines changed: 6 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -132,6 +132,9 @@ struct all_devices_have<aspect::ext_intel_memory_clock_rate>
132132
template <>
133133
struct all_devices_have<aspect::ext_intel_memory_bus_width>
134134
: std::bool_constant<__SYCL_ALL_DEVICES_HAVE_39__> {};
135+
template <>
136+
struct all_devices_have<aspect::emulated>
137+
: std::bool_constant<__SYCL_ALL_DEVICES_HAVE_40__> {};
135138

136139
#ifdef __SYCL_ANY_DEVICE_HAS_ANY_ASPECT__
137140
// Special case where any_device_has is trivially true.
@@ -258,6 +261,9 @@ struct any_device_has<aspect::ext_intel_memory_clock_rate>
258261
template <>
259262
struct any_device_has<aspect::ext_intel_memory_bus_width>
260263
: std::bool_constant<__SYCL_ANY_DEVICE_HAS_39__> {};
264+
template <>
265+
struct any_device_has<aspect::emulated>
266+
: std::bool_constant<__SYCL_ANY_DEVICE_HAS_40__> {};
261267
#endif // __SYCL_ANY_DEVICE_HAS_ANY_ASPECT__
262268

263269
template <aspect Aspect>

‎sycl/include/sycl/info/aspects.def

Lines changed: 1 addition & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -1,4 +1,3 @@
1-
__SYCL_ASPECT(host, 0)
21
__SYCL_ASPECT(cpu, 1)
32
__SYCL_ASPECT(gpu, 2)
43
__SYCL_ASPECT(accelerator, 3)
@@ -12,7 +11,6 @@ __SYCL_ASPECT(queue_profiling, 12)
1211
__SYCL_ASPECT(usm_device_allocations, 13)
1312
__SYCL_ASPECT(usm_host_allocations, 14)
1413
__SYCL_ASPECT(usm_shared_allocations, 15)
15-
__SYCL_ASPECT(usm_restricted_shared_allocations, 16)
1614
__SYCL_ASPECT(usm_system_allocations, 17)
1715
__SYCL_ASPECT(ext_intel_pci_address, 18)
1816
__SYCL_ASPECT(ext_intel_gpu_eu_count, 19)
@@ -36,3 +34,4 @@ __SYCL_ASPECT(ext_intel_free_memory, 36)
3634
__SYCL_ASPECT(ext_intel_device_id, 37)
3735
__SYCL_ASPECT(ext_intel_memory_clock_rate, 38)
3836
__SYCL_ASPECT(ext_intel_memory_bus_width, 39)
37+
__SYCL_ASPECT(emulated, 40)

‎sycl/include/sycl/info/aspects_deprecated.def

Lines changed: 2 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -2,3 +2,5 @@ __SYCL_ASPECT_DEPRECATED(int64_base_atomics, 7, "use atomic64 instead")
22
__SYCL_ASPECT_DEPRECATED(int64_extended_atomics, 8, "use atomic64 instead")
33
// Special macro for aspects that don't have own token
44
__SYCL_ASPECT_DEPRECATED_ALIAS(usm_system_allocator, usm_system_allocations, "use usm_system_allocations instead")
5+
__SYCL_ASPECT_DEPRECATED(usm_restricted_shared_allocations, 16, "deprecated in SYCL 2020")
6+
__SYCL_ASPECT_DEPRECATED(host, 0, "removed in SYCL 2020, 'host' device has been removed")

‎sycl/source/detail/device_impl.cpp

Lines changed: 5 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -296,6 +296,11 @@ bool device_impl::has(aspect Aspect) const {
296296
return is_accelerator();
297297
case aspect::custom:
298298
return false;
299+
// TODO: Implement this for FPGA and ESIMD emulators.
300+
case aspect::emulated:
301+
return false;
302+
case aspect::host_debuggable:
303+
return false;
299304
case aspect::fp16:
300305
return has_extension("cl_khr_fp16");
301306
case aspect::fp64:

‎sycl/test/extensions/properties/properties_kernel.cpp

Lines changed: 43 additions & 50 deletions
Original file line numberDiff line numberDiff line change
@@ -8,14 +8,12 @@ using namespace sycl::ext::oneapi::experimental;
88

99
using device_has_all =
1010
decltype(device_has<
11-
aspect::host, aspect::cpu, aspect::gpu, aspect::accelerator,
12-
aspect::custom, aspect::fp16, aspect::fp64, aspect::image,
13-
aspect::online_compiler, aspect::online_linker,
14-
aspect::queue_profiling, aspect::usm_device_allocations,
15-
aspect::usm_host_allocations, aspect::usm_shared_allocations,
16-
aspect::usm_restricted_shared_allocations,
17-
aspect::usm_system_allocations, aspect::ext_intel_pci_address,
18-
aspect::ext_intel_gpu_eu_count,
11+
aspect::cpu, aspect::gpu, aspect::accelerator, aspect::custom,
12+
aspect::fp16, aspect::fp64, aspect::image, aspect::online_compiler,
13+
aspect::online_linker, aspect::queue_profiling,
14+
aspect::usm_device_allocations, aspect::usm_host_allocations,
15+
aspect::usm_shared_allocations, aspect::usm_system_allocations,
16+
aspect::ext_intel_pci_address, aspect::ext_intel_gpu_eu_count,
1917
aspect::ext_intel_gpu_eu_simd_width, aspect::ext_intel_gpu_slices,
2018
aspect::ext_intel_gpu_subslices_per_slice,
2119
aspect::ext_intel_gpu_eu_count_per_subslice,
@@ -87,7 +85,6 @@ int main() {
8785
static_assert(std::is_same_v<decltype(sub_group_size<28>)::value_t,
8886
std::integral_constant<uint32_t, 28>>);
8987

90-
singleAspectDeviceHasChecks<aspect::host>();
9188
singleAspectDeviceHasChecks<aspect::cpu>();
9289
singleAspectDeviceHasChecks<aspect::gpu>();
9390
singleAspectDeviceHasChecks<aspect::accelerator>();
@@ -101,7 +98,6 @@ int main() {
10198
singleAspectDeviceHasChecks<aspect::usm_device_allocations>();
10299
singleAspectDeviceHasChecks<aspect::usm_host_allocations>();
103100
singleAspectDeviceHasChecks<aspect::usm_shared_allocations>();
104-
singleAspectDeviceHasChecks<aspect::usm_restricted_shared_allocations>();
105101
singleAspectDeviceHasChecks<aspect::usm_system_allocations>();
106102
singleAspectDeviceHasChecks<aspect::ext_intel_pci_address>();
107103
singleAspectDeviceHasChecks<aspect::ext_intel_gpu_eu_count>();
@@ -132,57 +128,54 @@ int main() {
132128

133129
static_assert(is_property_value<device_has_all>::value);
134130
static_assert(std::is_same_v<device_has_key, device_has_all::key_t>);
135-
static_assert(device_has_all::value.size() == 38);
136-
static_assert(device_has_all::value[0] == aspect::host);
137-
static_assert(device_has_all::value[1] == aspect::cpu);
138-
static_assert(device_has_all::value[2] == aspect::gpu);
139-
static_assert(device_has_all::value[3] == aspect::accelerator);
140-
static_assert(device_has_all::value[4] == aspect::custom);
141-
static_assert(device_has_all::value[5] == aspect::fp16);
142-
static_assert(device_has_all::value[6] == aspect::fp64);
143-
static_assert(device_has_all::value[7] == aspect::image);
144-
static_assert(device_has_all::value[8] == aspect::online_compiler);
145-
static_assert(device_has_all::value[9] == aspect::online_linker);
146-
static_assert(device_has_all::value[10] == aspect::queue_profiling);
147-
static_assert(device_has_all::value[11] == aspect::usm_device_allocations);
148-
static_assert(device_has_all::value[12] == aspect::usm_host_allocations);
149-
static_assert(device_has_all::value[13] == aspect::usm_shared_allocations);
150-
static_assert(device_has_all::value[14] ==
151-
aspect::usm_restricted_shared_allocations);
152-
static_assert(device_has_all::value[15] == aspect::usm_system_allocations);
153-
static_assert(device_has_all::value[16] == aspect::ext_intel_pci_address);
154-
static_assert(device_has_all::value[17] == aspect::ext_intel_gpu_eu_count);
155-
static_assert(device_has_all::value[18] ==
131+
static_assert(device_has_all::value.size() == 36);
132+
static_assert(device_has_all::value[0] == aspect::cpu);
133+
static_assert(device_has_all::value[1] == aspect::gpu);
134+
static_assert(device_has_all::value[2] == aspect::accelerator);
135+
static_assert(device_has_all::value[3] == aspect::custom);
136+
static_assert(device_has_all::value[4] == aspect::fp16);
137+
static_assert(device_has_all::value[5] == aspect::fp64);
138+
static_assert(device_has_all::value[6] == aspect::image);
139+
static_assert(device_has_all::value[7] == aspect::online_compiler);
140+
static_assert(device_has_all::value[8] == aspect::online_linker);
141+
static_assert(device_has_all::value[9] == aspect::queue_profiling);
142+
static_assert(device_has_all::value[10] == aspect::usm_device_allocations);
143+
static_assert(device_has_all::value[11] == aspect::usm_host_allocations);
144+
static_assert(device_has_all::value[12] == aspect::usm_shared_allocations);
145+
static_assert(device_has_all::value[13] == aspect::usm_system_allocations);
146+
static_assert(device_has_all::value[14] == aspect::ext_intel_pci_address);
147+
static_assert(device_has_all::value[15] == aspect::ext_intel_gpu_eu_count);
148+
static_assert(device_has_all::value[16] ==
156149
aspect::ext_intel_gpu_eu_simd_width);
157-
static_assert(device_has_all::value[19] == aspect::ext_intel_gpu_slices);
158-
static_assert(device_has_all::value[20] ==
150+
static_assert(device_has_all::value[17] == aspect::ext_intel_gpu_slices);
151+
static_assert(device_has_all::value[18] ==
159152
aspect::ext_intel_gpu_subslices_per_slice);
160-
static_assert(device_has_all::value[21] ==
153+
static_assert(device_has_all::value[19] ==
161154
aspect::ext_intel_gpu_eu_count_per_subslice);
162-
static_assert(device_has_all::value[22] ==
155+
static_assert(device_has_all::value[20] ==
163156
aspect::ext_intel_max_mem_bandwidth);
164-
static_assert(device_has_all::value[23] == aspect::ext_intel_mem_channel);
165-
static_assert(device_has_all::value[24] ==
157+
static_assert(device_has_all::value[21] == aspect::ext_intel_mem_channel);
158+
static_assert(device_has_all::value[22] ==
166159
aspect::usm_atomic_host_allocations);
167-
static_assert(device_has_all::value[25] ==
160+
static_assert(device_has_all::value[23] ==
168161
aspect::usm_atomic_shared_allocations);
169-
static_assert(device_has_all::value[26] == aspect::atomic64);
170-
static_assert(device_has_all::value[27] ==
162+
static_assert(device_has_all::value[24] == aspect::atomic64);
163+
static_assert(device_has_all::value[25] ==
171164
aspect::ext_intel_device_info_uuid);
172-
static_assert(device_has_all::value[28] == aspect::ext_oneapi_srgb);
173-
static_assert(device_has_all::value[29] == aspect::ext_oneapi_native_assert);
174-
static_assert(device_has_all::value[30] == aspect::host_debuggable);
175-
static_assert(device_has_all::value[31] ==
165+
static_assert(device_has_all::value[26] == aspect::ext_oneapi_srgb);
166+
static_assert(device_has_all::value[27] == aspect::ext_oneapi_native_assert);
167+
static_assert(device_has_all::value[28] == aspect::host_debuggable);
168+
static_assert(device_has_all::value[29] ==
176169
aspect::ext_intel_gpu_hw_threads_per_eu);
177-
static_assert(device_has_all::value[32] ==
170+
static_assert(device_has_all::value[30] ==
178171
aspect::ext_oneapi_cuda_async_barrier);
179-
static_assert(device_has_all::value[33] ==
172+
static_assert(device_has_all::value[31] ==
180173
aspect::ext_oneapi_bfloat16_math_functions);
181-
static_assert(device_has_all::value[34] == aspect::ext_intel_free_memory);
182-
static_assert(device_has_all::value[35] == aspect::ext_intel_device_id);
183-
static_assert(device_has_all::value[36] ==
174+
static_assert(device_has_all::value[32] == aspect::ext_intel_free_memory);
175+
static_assert(device_has_all::value[33] == aspect::ext_intel_device_id);
176+
static_assert(device_has_all::value[34] ==
184177
aspect::ext_intel_memory_clock_rate);
185-
static_assert(device_has_all::value[37] ==
178+
static_assert(device_has_all::value[35] ==
186179
aspect::ext_intel_memory_bus_width);
187180
return 0;
188181
}

‎sycl/test/extensions/properties/properties_kernel_device_has.cpp

Lines changed: 5 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -12,9 +12,8 @@ static constexpr auto device_has_all = device_has<
1212
aspect::ext_oneapi_bfloat16_math_functions, aspect::custom, aspect::fp16,
1313
aspect::fp64, aspect::image, aspect::online_compiler, aspect::online_linker,
1414
aspect::queue_profiling, aspect::usm_device_allocations,
15-
aspect::usm_restricted_shared_allocations, aspect::usm_system_allocations,
16-
aspect::ext_intel_pci_address, aspect::host, aspect::cpu, aspect::gpu,
17-
aspect::accelerator, aspect::ext_intel_gpu_eu_count,
15+
aspect::usm_system_allocations, aspect::ext_intel_pci_address, aspect::cpu,
16+
aspect::gpu, aspect::accelerator, aspect::ext_intel_gpu_eu_count,
1817
aspect::ext_intel_gpu_subslices_per_slice,
1918
aspect::ext_intel_gpu_eu_count_per_subslice,
2019
aspect::ext_intel_max_mem_bandwidth, aspect::ext_intel_mem_channel,
@@ -141,10 +140,8 @@ int main() {
141140
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"online_linker", i32 [[online_linker_ASPECT_MD:[0-9]+]]}
142141
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"queue_profiling", i32 [[queue_profiling_ASPECT_MD:[0-9]+]]}
143142
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"usm_device_allocations", i32 [[usm_device_allocations_ASPECT_MD:[0-9]+]]}
144-
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"usm_restricted_shared_allocations", i32 [[usm_restricted_shared_allocations_ASPECT_MD:[0-9]+]]}
145143
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"usm_system_allocations", i32 [[usm_system_allocations_ASPECT_MD:[0-9]+]]}
146144
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"ext_intel_pci_address", i32 [[ext_intel_pci_address_ASPECT_MD:[0-9]+]]}
147-
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"host", i32 [[host_ASPECT_MD:[0-9]+]]}
148145
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"cpu", i32 [[cpu_ASPECT_MD:[0-9]+]]}
149146
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"gpu", i32 [[gpu_ASPECT_MD:[0-9]+]]}
150147
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"accelerator", i32 [[accelerator_ASPECT_MD:[0-9]+]]}
@@ -168,6 +165,6 @@ int main() {
168165
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"ext_intel_free_memory", i32 [[ext_intel_free_memory_ASPECT_MD:[0-9]+]]}
169166
// CHECK-IR-DAG: !{{[0-9]+}} = !{!"ext_intel_device_id", i32 [[ext_intel_device_id_ASPECT_MD:[0-9]+]]}
170167

171-
// CHECK-IR-DAG: attributes #[[DHAttr1]] = { {{.*}}"sycl-device-has"="[[ext_oneapi_cuda_async_barrier_ASPECT_MD]],[[ext_oneapi_bfloat16_math_functions_ASPECT_MD]],[[custom_ASPECT_MD]],[[fp16_ASPECT_MD]],[[fp64_ASPECT_MD]],[[image_ASPECT_MD]],[[online_compiler_ASPECT_MD]],[[online_linker_ASPECT_MD]],[[queue_profiling_ASPECT_MD]],[[usm_device_allocations_ASPECT_MD]],[[usm_restricted_shared_allocations_ASPECT_MD]],[[usm_system_allocations_ASPECT_MD]],[[ext_intel_pci_address_ASPECT_MD]],[[host_ASPECT_MD]],[[cpu_ASPECT_MD]],[[gpu_ASPECT_MD]],[[accelerator_ASPECT_MD]],[[ext_intel_gpu_eu_count_ASPECT_MD]],[[ext_intel_gpu_subslices_per_slice_ASPECT_MD]],[[ext_intel_gpu_eu_count_per_subslice_ASPECT_MD]],[[ext_intel_max_mem_bandwidth_ASPECT_MD]],[[ext_intel_mem_channel_ASPECT_MD]],[[usm_atomic_host_allocations_ASPECT_MD]],[[usm_atomic_shared_allocations_ASPECT_MD]],[[atomic64_ASPECT_MD]],[[ext_intel_device_info_uuid_ASPECT_MD]],[[ext_oneapi_srgb_ASPECT_MD]],[[ext_intel_gpu_eu_simd_width_ASPECT_MD]],[[ext_intel_gpu_slices_ASPECT_MD]],[[ext_oneapi_native_assert_ASPECT_MD]],[[host_debuggable_ASPECT_MD]],[[ext_intel_gpu_hw_threads_per_eu_ASPECT_MD]],[[usm_host_allocations_ASPECT_MD]],[[usm_shared_allocations_ASPECT_MD]],[[ext_intel_free_memory_ASPECT_MD]],[[ext_intel_device_id_ASPECT_MD]]"
172-
// CHECK-IR-DAG: attributes #[[DHAttr2]] = { {{.*}}"sycl-device-has"="[[ext_oneapi_cuda_async_barrier_ASPECT_MD]],[[ext_oneapi_bfloat16_math_functions_ASPECT_MD]],[[custom_ASPECT_MD]],[[fp16_ASPECT_MD]],[[fp64_ASPECT_MD]],[[image_ASPECT_MD]],[[online_compiler_ASPECT_MD]],[[online_linker_ASPECT_MD]],[[queue_profiling_ASPECT_MD]],[[usm_device_allocations_ASPECT_MD]],[[usm_restricted_shared_allocations_ASPECT_MD]],[[usm_system_allocations_ASPECT_MD]],[[ext_intel_pci_address_ASPECT_MD]],[[host_ASPECT_MD]],[[cpu_ASPECT_MD]],[[gpu_ASPECT_MD]],[[accelerator_ASPECT_MD]],[[ext_intel_gpu_eu_count_ASPECT_MD]],[[ext_intel_gpu_subslices_per_slice_ASPECT_MD]],[[ext_intel_gpu_eu_count_per_subslice_ASPECT_MD]],[[ext_intel_max_mem_bandwidth_ASPECT_MD]],[[ext_intel_mem_channel_ASPECT_MD]],[[usm_atomic_host_allocations_ASPECT_MD]],[[usm_atomic_shared_allocations_ASPECT_MD]],[[atomic64_ASPECT_MD]],[[ext_intel_device_info_uuid_ASPECT_MD]],[[ext_oneapi_srgb_ASPECT_MD]],[[ext_intel_gpu_eu_simd_width_ASPECT_MD]],[[ext_intel_gpu_slices_ASPECT_MD]],[[ext_oneapi_native_assert_ASPECT_MD]],[[host_debuggable_ASPECT_MD]],[[ext_intel_gpu_hw_threads_per_eu_ASPECT_MD]],[[usm_host_allocations_ASPECT_MD]],[[usm_shared_allocations_ASPECT_MD]],[[ext_intel_free_memory_ASPECT_MD]],[[ext_intel_device_id_ASPECT_MD]]"
173-
// CHECK-IR-DAG: attributes #[[DHAttr3]] = { {{.*}}"sycl-device-has"="[[ext_oneapi_cuda_async_barrier_ASPECT_MD]],[[ext_oneapi_bfloat16_math_functions_ASPECT_MD]],[[custom_ASPECT_MD]],[[fp16_ASPECT_MD]],[[fp64_ASPECT_MD]],[[image_ASPECT_MD]],[[online_compiler_ASPECT_MD]],[[online_linker_ASPECT_MD]],[[queue_profiling_ASPECT_MD]],[[usm_device_allocations_ASPECT_MD]],[[usm_restricted_shared_allocations_ASPECT_MD]],[[usm_system_allocations_ASPECT_MD]],[[ext_intel_pci_address_ASPECT_MD]],[[host_ASPECT_MD]],[[cpu_ASPECT_MD]],[[gpu_ASPECT_MD]],[[accelerator_ASPECT_MD]],[[ext_intel_gpu_eu_count_ASPECT_MD]],[[ext_intel_gpu_subslices_per_slice_ASPECT_MD]],[[ext_intel_gpu_eu_count_per_subslice_ASPECT_MD]],[[ext_intel_max_mem_bandwidth_ASPECT_MD]],[[ext_intel_mem_channel_ASPECT_MD]],[[usm_atomic_host_allocations_ASPECT_MD]],[[usm_atomic_shared_allocations_ASPECT_MD]],[[atomic64_ASPECT_MD]],[[ext_intel_device_info_uuid_ASPECT_MD]],[[ext_oneapi_srgb_ASPECT_MD]],[[ext_intel_gpu_eu_simd_width_ASPECT_MD]],[[ext_intel_gpu_slices_ASPECT_MD]],[[ext_oneapi_native_assert_ASPECT_MD]],[[host_debuggable_ASPECT_MD]],[[ext_intel_gpu_hw_threads_per_eu_ASPECT_MD]],[[usm_host_allocations_ASPECT_MD]],[[usm_shared_allocations_ASPECT_MD]],[[ext_intel_free_memory_ASPECT_MD]],[[ext_intel_device_id_ASPECT_MD]]"
168+
// CHECK-IR-DAG: attributes #[[DHAttr1]] = { {{.*}}"sycl-device-has"="[[ext_oneapi_cuda_async_barrier_ASPECT_MD]],[[ext_oneapi_bfloat16_math_functions_ASPECT_MD]],[[custom_ASPECT_MD]],[[fp16_ASPECT_MD]],[[fp64_ASPECT_MD]],[[image_ASPECT_MD]],[[online_compiler_ASPECT_MD]],[[online_linker_ASPECT_MD]],[[queue_profiling_ASPECT_MD]],[[usm_device_allocations_ASPECT_MD]],[[usm_system_allocations_ASPECT_MD]],[[ext_intel_pci_address_ASPECT_MD]],[[cpu_ASPECT_MD]],[[gpu_ASPECT_MD]],[[accelerator_ASPECT_MD]],[[ext_intel_gpu_eu_count_ASPECT_MD]],[[ext_intel_gpu_subslices_per_slice_ASPECT_MD]],[[ext_intel_gpu_eu_count_per_subslice_ASPECT_MD]],[[ext_intel_max_mem_bandwidth_ASPECT_MD]],[[ext_intel_mem_channel_ASPECT_MD]],[[usm_atomic_host_allocations_ASPECT_MD]],[[usm_atomic_shared_allocations_ASPECT_MD]],[[atomic64_ASPECT_MD]],[[ext_intel_device_info_uuid_ASPECT_MD]],[[ext_oneapi_srgb_ASPECT_MD]],[[ext_intel_gpu_eu_simd_width_ASPECT_MD]],[[ext_intel_gpu_slices_ASPECT_MD]],[[ext_oneapi_native_assert_ASPECT_MD]],[[host_debuggable_ASPECT_MD]],[[ext_intel_gpu_hw_threads_per_eu_ASPECT_MD]],[[usm_host_allocations_ASPECT_MD]],[[usm_shared_allocations_ASPECT_MD]],[[ext_intel_free_memory_ASPECT_MD]],[[ext_intel_device_id_ASPECT_MD]]"
169+
// CHECK-IR-DAG: attributes #[[DHAttr2]] = { {{.*}}"sycl-device-has"="[[ext_oneapi_cuda_async_barrier_ASPECT_MD]],[[ext_oneapi_bfloat16_math_functions_ASPECT_MD]],[[custom_ASPECT_MD]],[[fp16_ASPECT_MD]],[[fp64_ASPECT_MD]],[[image_ASPECT_MD]],[[online_compiler_ASPECT_MD]],[[online_linker_ASPECT_MD]],[[queue_profiling_ASPECT_MD]],[[usm_device_allocations_ASPECT_MD]],[[usm_system_allocations_ASPECT_MD]],[[ext_intel_pci_address_ASPECT_MD]],[[cpu_ASPECT_MD]],[[gpu_ASPECT_MD]],[[accelerator_ASPECT_MD]],[[ext_intel_gpu_eu_count_ASPECT_MD]],[[ext_intel_gpu_subslices_per_slice_ASPECT_MD]],[[ext_intel_gpu_eu_count_per_subslice_ASPECT_MD]],[[ext_intel_max_mem_bandwidth_ASPECT_MD]],[[ext_intel_mem_channel_ASPECT_MD]],[[usm_atomic_host_allocations_ASPECT_MD]],[[usm_atomic_shared_allocations_ASPECT_MD]],[[atomic64_ASPECT_MD]],[[ext_intel_device_info_uuid_ASPECT_MD]],[[ext_oneapi_srgb_ASPECT_MD]],[[ext_intel_gpu_eu_simd_width_ASPECT_MD]],[[ext_intel_gpu_slices_ASPECT_MD]],[[ext_oneapi_native_assert_ASPECT_MD]],[[host_debuggable_ASPECT_MD]],[[ext_intel_gpu_hw_threads_per_eu_ASPECT_MD]],[[usm_host_allocations_ASPECT_MD]],[[usm_shared_allocations_ASPECT_MD]],[[ext_intel_free_memory_ASPECT_MD]],[[ext_intel_device_id_ASPECT_MD]]"
170+
// CHECK-IR-DAG: attributes #[[DHAttr3]] = { {{.*}}"sycl-device-has"="[[ext_oneapi_cuda_async_barrier_ASPECT_MD]],[[ext_oneapi_bfloat16_math_functions_ASPECT_MD]],[[custom_ASPECT_MD]],[[fp16_ASPECT_MD]],[[fp64_ASPECT_MD]],[[image_ASPECT_MD]],[[online_compiler_ASPECT_MD]],[[online_linker_ASPECT_MD]],[[queue_profiling_ASPECT_MD]],[[usm_device_allocations_ASPECT_MD]],[[usm_system_allocations_ASPECT_MD]],[[ext_intel_pci_address_ASPECT_MD]],[[cpu_ASPECT_MD]],[[gpu_ASPECT_MD]],[[accelerator_ASPECT_MD]],[[ext_intel_gpu_eu_count_ASPECT_MD]],[[ext_intel_gpu_subslices_per_slice_ASPECT_MD]],[[ext_intel_gpu_eu_count_per_subslice_ASPECT_MD]],[[ext_intel_max_mem_bandwidth_ASPECT_MD]],[[ext_intel_mem_channel_ASPECT_MD]],[[usm_atomic_host_allocations_ASPECT_MD]],[[usm_atomic_shared_allocations_ASPECT_MD]],[[atomic64_ASPECT_MD]],[[ext_intel_device_info_uuid_ASPECT_MD]],[[ext_oneapi_srgb_ASPECT_MD]],[[ext_intel_gpu_eu_simd_width_ASPECT_MD]],[[ext_intel_gpu_slices_ASPECT_MD]],[[ext_oneapi_native_assert_ASPECT_MD]],[[host_debuggable_ASPECT_MD]],[[ext_intel_gpu_hw_threads_per_eu_ASPECT_MD]],[[usm_host_allocations_ASPECT_MD]],[[usm_shared_allocations_ASPECT_MD]],[[ext_intel_free_memory_ASPECT_MD]],[[ext_intel_device_id_ASPECT_MD]]"

0 commit comments

Comments
 (0)