DPC++ Runtime
Runtime libraries for oneAPI DPC++
device_architecture.hpp
Go to the documentation of this file.
1 #pragma once
2 
3 #include <sycl/detail/defines_elementary.hpp>
4 
5 namespace sycl {
6 __SYCL_INLINE_VER_NAMESPACE(_V1) {
7 namespace ext::oneapi::experimental {
8 
9 enum class architecture {
10  x86_64,
11  intel_gpu_bdw,
12  intel_gpu_skl,
13  intel_gpu_kbl,
14  intel_gpu_cfl,
15  intel_gpu_apl,
16  intel_gpu_glk,
17  intel_gpu_whl,
18  intel_gpu_aml,
19  intel_gpu_cml,
20  intel_gpu_icllp,
21  intel_gpu_ehl,
22  intel_gpu_tgllp,
23  intel_gpu_rkl,
24  intel_gpu_adl_s,
25  intel_gpu_rpl_s,
26  intel_gpu_adl_p,
27  intel_gpu_adl_n,
28  intel_gpu_dg1,
29  intel_gpu_acm_g10,
30  intel_gpu_acm_g11,
31  intel_gpu_acm_g12,
32  intel_gpu_pvc,
33  // NVIDIA architectures
34  nvidia_gpu_sm_50,
35  nvidia_gpu_sm_52,
36  nvidia_gpu_sm_53,
37  nvidia_gpu_sm_60,
38  nvidia_gpu_sm_61,
39  nvidia_gpu_sm_62,
40  nvidia_gpu_sm_70,
41  nvidia_gpu_sm_72,
42  nvidia_gpu_sm_75,
43  nvidia_gpu_sm_80,
44  nvidia_gpu_sm_86,
45  nvidia_gpu_sm_87,
46  nvidia_gpu_sm_89,
47  nvidia_gpu_sm_90,
48  // AMD architectures
49  amd_gpu_gfx700,
50  amd_gpu_gfx701,
51  amd_gpu_gfx702,
52  amd_gpu_gfx801,
53  amd_gpu_gfx802,
54  amd_gpu_gfx803,
55  amd_gpu_gfx805,
56  amd_gpu_gfx810,
57  amd_gpu_gfx900,
58  amd_gpu_gfx902,
59  amd_gpu_gfx904,
60  amd_gpu_gfx906,
61  amd_gpu_gfx908,
62  amd_gpu_gfx90a,
63  amd_gpu_gfx1010,
64  amd_gpu_gfx1011,
65  amd_gpu_gfx1012,
66  amd_gpu_gfx1013,
67  amd_gpu_gfx1030,
68  amd_gpu_gfx1031,
69  amd_gpu_gfx1032,
70  amd_gpu_gfx1034,
71  // Update "detail::max_architecture" below if you add new elements here!
72  intel_gpu_8_0_0 = intel_gpu_bdw,
73  intel_gpu_9_0_9 = intel_gpu_skl,
74  intel_gpu_9_1_9 = intel_gpu_kbl,
75  intel_gpu_9_2_9 = intel_gpu_cfl,
76  intel_gpu_9_3_0 = intel_gpu_apl,
77  intel_gpu_9_4_0 = intel_gpu_glk,
78  intel_gpu_9_5_0 = intel_gpu_whl,
79  intel_gpu_9_6_0 = intel_gpu_aml,
80  intel_gpu_9_7_0 = intel_gpu_cml,
81  intel_gpu_11_0_0 = intel_gpu_icllp,
82  intel_gpu_11_2_0 = intel_gpu_ehl,
83  intel_gpu_12_0_0 = intel_gpu_tgllp,
84  intel_gpu_12_10_0 = intel_gpu_dg1,
85 };
86 
87 } // namespace ext::oneapi::experimental
88 
89 namespace detail {
90 
91 static constexpr ext::oneapi::experimental::architecture max_architecture =
92  ext::oneapi::experimental::architecture::amd_gpu_gfx1034;
93 
94 #ifndef __SYCL_TARGET_INTEL_X86_64__
95 #define __SYCL_TARGET_INTEL_X86_64__ 0
96 #endif
97 #ifndef __SYCL_TARGET_INTEL_GPU_BDW__
98 #define __SYCL_TARGET_INTEL_GPU_BDW__ 0
99 #endif
100 #ifndef __SYCL_TARGET_INTEL_GPU_SKL__
101 #define __SYCL_TARGET_INTEL_GPU_SKL__ 0
102 #endif
103 #ifndef __SYCL_TARGET_INTEL_GPU_KBL__
104 #define __SYCL_TARGET_INTEL_GPU_KBL__ 0
105 #endif
106 #ifndef __SYCL_TARGET_INTEL_GPU_CFL__
107 #define __SYCL_TARGET_INTEL_GPU_CFL__ 0
108 #endif
109 #ifndef __SYCL_TARGET_INTEL_GPU_APL__
110 #define __SYCL_TARGET_INTEL_GPU_APL__ 0
111 #endif
112 #ifndef __SYCL_TARGET_INTEL_GPU_GLK__
113 #define __SYCL_TARGET_INTEL_GPU_GLK__ 0
114 #endif
115 #ifndef __SYCL_TARGET_INTEL_GPU_WHL__
116 #define __SYCL_TARGET_INTEL_GPU_WHL__ 0
117 #endif
118 #ifndef __SYCL_TARGET_INTEL_GPU_AML__
119 #define __SYCL_TARGET_INTEL_GPU_AML__ 0
120 #endif
121 #ifndef __SYCL_TARGET_INTEL_GPU_CML__
122 #define __SYCL_TARGET_INTEL_GPU_CML__ 0
123 #endif
124 #ifndef __SYCL_TARGET_INTEL_GPU_ICLLP__
125 #define __SYCL_TARGET_INTEL_GPU_ICLLP__ 0
126 #endif
127 #ifndef __SYCL_TARGET_INTEL_GPU_EHL__
128 #define __SYCL_TARGET_INTEL_GPU_EHL__ 0
129 #endif
130 #ifndef __SYCL_TARGET_INTEL_GPU_TGLLP__
131 #define __SYCL_TARGET_INTEL_GPU_TGLLP__ 0
132 #endif
133 #ifndef __SYCL_TARGET_INTEL_GPU_RKL__
134 #define __SYCL_TARGET_INTEL_GPU_RKL__ 0
135 #endif
136 #ifndef __SYCL_TARGET_INTEL_GPU_ADL_S__
137 #define __SYCL_TARGET_INTEL_GPU_ADL_S__ 0
138 #endif
139 #ifndef __SYCL_TARGET_INTEL_GPU_RPL_S__
140 #define __SYCL_TARGET_INTEL_GPU_RPL_S__ 0
141 #endif
142 #ifndef __SYCL_TARGET_INTEL_GPU_ADL_P__
143 #define __SYCL_TARGET_INTEL_GPU_ADL_P__ 0
144 #endif
145 #ifndef __SYCL_TARGET_INTEL_GPU_ADL_N__
146 #define __SYCL_TARGET_INTEL_GPU_ADL_N__ 0
147 #endif
148 #ifndef __SYCL_TARGET_INTEL_GPU_DG1__
149 #define __SYCL_TARGET_INTEL_GPU_DG1__ 0
150 #endif
151 #ifndef __SYCL_TARGET_INTEL_GPU_ACM_G10__
152 #define __SYCL_TARGET_INTEL_GPU_ACM_G10__ 0
153 #endif
154 #ifndef __SYCL_TARGET_INTEL_GPU_ACM_G11__
155 #define __SYCL_TARGET_INTEL_GPU_ACM_G11__ 0
156 #endif
157 #ifndef __SYCL_TARGET_INTEL_GPU_ACM_G12__
158 #define __SYCL_TARGET_INTEL_GPU_ACM_G12__ 0
159 #endif
160 #ifndef __SYCL_TARGET_INTEL_GPU_PVC__
161 #define __SYCL_TARGET_INTEL_GPU_PVC__ 0
162 #endif
163 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM50__
164 #define __SYCL_TARGET_NVIDIA_GPU_SM50__ 0
165 #endif
166 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM52__
167 #define __SYCL_TARGET_NVIDIA_GPU_SM52__ 0
168 #endif
169 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM53__
170 #define __SYCL_TARGET_NVIDIA_GPU_SM53__ 0
171 #endif
172 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM60__
173 #define __SYCL_TARGET_NVIDIA_GPU_SM60__ 0
174 #endif
175 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM61__
176 #define __SYCL_TARGET_NVIDIA_GPU_SM61__ 0
177 #endif
178 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM62__
179 #define __SYCL_TARGET_NVIDIA_GPU_SM62__ 0
180 #endif
181 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM70__
182 #define __SYCL_TARGET_NVIDIA_GPU_SM70__ 0
183 #endif
184 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM72__
185 #define __SYCL_TARGET_NVIDIA_GPU_SM72__ 0
186 #endif
187 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM75__
188 #define __SYCL_TARGET_NVIDIA_GPU_SM75__ 0
189 #endif
190 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM80__
191 #define __SYCL_TARGET_NVIDIA_GPU_SM80__ 0
192 #endif
193 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM86__
194 #define __SYCL_TARGET_NVIDIA_GPU_SM86__ 0
195 #endif
196 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM87__
197 #define __SYCL_TARGET_NVIDIA_GPU_SM87__ 0
198 #endif
199 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM89__
200 #define __SYCL_TARGET_NVIDIA_GPU_SM89__ 0
201 #endif
202 #ifndef __SYCL_TARGET_NVIDIA_GPU_SM90__
203 #define __SYCL_TARGET_NVIDIA_GPU_SM90__ 0
204 #endif
205 #ifndef __SYCL_TARGET_AMD_GPU_GFX700__
206 #define __SYCL_TARGET_AMD_GPU_GFX700__ 0
207 #endif
208 #ifndef __SYCL_TARGET_AMD_GPU_GFX701__
209 #define __SYCL_TARGET_AMD_GPU_GFX701__ 0
210 #endif
211 #ifndef __SYCL_TARGET_AMD_GPU_GFX702__
212 #define __SYCL_TARGET_AMD_GPU_GFX702__ 0
213 #endif
214 #ifndef __SYCL_TARGET_AMD_GPU_GFX801__
215 #define __SYCL_TARGET_AMD_GPU_GFX801__ 0
216 #endif
217 #ifndef __SYCL_TARGET_AMD_GPU_GFX802__
218 #define __SYCL_TARGET_AMD_GPU_GFX802__ 0
219 #endif
220 #ifndef __SYCL_TARGET_AMD_GPU_GFX803__
221 #define __SYCL_TARGET_AMD_GPU_GFX803__ 0
222 #endif
223 #ifndef __SYCL_TARGET_AMD_GPU_GFX805__
224 #define __SYCL_TARGET_AMD_GPU_GFX805__ 0
225 #endif
226 #ifndef __SYCL_TARGET_AMD_GPU_GFX810__
227 #define __SYCL_TARGET_AMD_GPU_GFX810__ 0
228 #endif
229 #ifndef __SYCL_TARGET_AMD_GPU_GFX900__
230 #define __SYCL_TARGET_AMD_GPU_GFX900__ 0
231 #endif
232 #ifndef __SYCL_TARGET_AMD_GPU_GFX902__
233 #define __SYCL_TARGET_AMD_GPU_GFX902__ 0
234 #endif
235 #ifndef __SYCL_TARGET_AMD_GPU_GFX904__
236 #define __SYCL_TARGET_AMD_GPU_GFX904__ 0
237 #endif
238 #ifndef __SYCL_TARGET_AMD_GPU_GFX906__
239 #define __SYCL_TARGET_AMD_GPU_GFX906__ 0
240 #endif
241 #ifndef __SYCL_TARGET_AMD_GPU_GFX908__
242 #define __SYCL_TARGET_AMD_GPU_GFX908__ 0
243 #endif
244 #ifndef __SYCL_TARGET_AMD_GPU_GFX90A__
245 #define __SYCL_TARGET_AMD_GPU_GFX90A__ 0
246 #endif
247 #ifndef __SYCL_TARGET_AMD_GPU_GFX1010__
248 #define __SYCL_TARGET_AMD_GPU_GFX1010__ 0
249 #endif
250 #ifndef __SYCL_TARGET_AMD_GPU_GFX1011__
251 #define __SYCL_TARGET_AMD_GPU_GFX1011__ 0
252 #endif
253 #ifndef __SYCL_TARGET_AMD_GPU_GFX1012__
254 #define __SYCL_TARGET_AMD_GPU_GFX1012__ 0
255 #endif
256 #ifndef __SYCL_TARGET_AMD_GPU_GFX1013__
257 #define __SYCL_TARGET_AMD_GPU_GFX1013__ 0
258 #endif
259 #ifndef __SYCL_TARGET_AMD_GPU_GFX1030__
260 #define __SYCL_TARGET_AMD_GPU_GFX1030__ 0
261 #endif
262 #ifndef __SYCL_TARGET_AMD_GPU_GFX1031__
263 #define __SYCL_TARGET_AMD_GPU_GFX1031__ 0
264 #endif
265 #ifndef __SYCL_TARGET_AMD_GPU_GFX1032__
266 #define __SYCL_TARGET_AMD_GPU_GFX1032__ 0
267 #endif
268 #ifndef __SYCL_TARGET_AMD_GPU_GFX1034__
269 #define __SYCL_TARGET_AMD_GPU_GFX1034__ 0
270 #endif
271 
272 // This is true when the translation unit is compiled in AOT mode with target
273 // names that supports the "if_architecture_is" features. If an unsupported
274 // target name is specified via "-fsycl-targets", the associated invocation of
275 // the device compiler will set this variable to false, and that will trigger
276 // an error for code that uses "if_architecture_is".
277 static constexpr bool is_allowable_aot_mode =
278  (__SYCL_TARGET_INTEL_X86_64__ == 1) ||
279  (__SYCL_TARGET_INTEL_GPU_BDW__ == 1) ||
280  (__SYCL_TARGET_INTEL_GPU_SKL__ == 1) ||
281  (__SYCL_TARGET_INTEL_GPU_KBL__ == 1) ||
282  (__SYCL_TARGET_INTEL_GPU_CFL__ == 1) ||
283  (__SYCL_TARGET_INTEL_GPU_APL__ == 1) ||
284  (__SYCL_TARGET_INTEL_GPU_GLK__ == 1) ||
285  (__SYCL_TARGET_INTEL_GPU_WHL__ == 1) ||
286  (__SYCL_TARGET_INTEL_GPU_AML__ == 1) ||
287  (__SYCL_TARGET_INTEL_GPU_CML__ == 1) ||
288  (__SYCL_TARGET_INTEL_GPU_ICLLP__ == 1) ||
289  (__SYCL_TARGET_INTEL_GPU_EHL__ == 1) ||
290  (__SYCL_TARGET_INTEL_GPU_TGLLP__ == 1) ||
291  (__SYCL_TARGET_INTEL_GPU_RKL__ == 1) ||
292  (__SYCL_TARGET_INTEL_GPU_ADL_S__ == 1) ||
293  (__SYCL_TARGET_INTEL_GPU_RPL_S__ == 1) ||
294  (__SYCL_TARGET_INTEL_GPU_ADL_P__ == 1) ||
295  (__SYCL_TARGET_INTEL_GPU_ADL_N__ == 1) ||
296  (__SYCL_TARGET_INTEL_GPU_DG1__ == 1) ||
297  (__SYCL_TARGET_INTEL_GPU_ACM_G10__ == 1) ||
298  (__SYCL_TARGET_INTEL_GPU_ACM_G11__ == 1) ||
299  (__SYCL_TARGET_INTEL_GPU_ACM_G12__ == 1) ||
300  (__SYCL_TARGET_INTEL_GPU_PVC__ == 1) ||
301  (__SYCL_TARGET_NVIDIA_GPU_SM50__ == 1) ||
302  (__SYCL_TARGET_NVIDIA_GPU_SM52__ == 1) ||
303  (__SYCL_TARGET_NVIDIA_GPU_SM53__ == 1) ||
304  (__SYCL_TARGET_NVIDIA_GPU_SM60__ == 1) ||
305  (__SYCL_TARGET_NVIDIA_GPU_SM61__ == 1) ||
306  (__SYCL_TARGET_NVIDIA_GPU_SM62__ == 1) ||
307  (__SYCL_TARGET_NVIDIA_GPU_SM70__ == 1) ||
308  (__SYCL_TARGET_NVIDIA_GPU_SM72__ == 1) ||
309  (__SYCL_TARGET_NVIDIA_GPU_SM75__ == 1) ||
310  (__SYCL_TARGET_NVIDIA_GPU_SM80__ == 1) ||
311  (__SYCL_TARGET_NVIDIA_GPU_SM86__ == 1) ||
312  (__SYCL_TARGET_NVIDIA_GPU_SM87__ == 1) ||
313  (__SYCL_TARGET_NVIDIA_GPU_SM89__ == 1) ||
314  (__SYCL_TARGET_NVIDIA_GPU_SM90__ == 1) ||
315  (__SYCL_TARGET_AMD_GPU_GFX700__ == 1) ||
316  (__SYCL_TARGET_AMD_GPU_GFX701__ == 1) ||
317  (__SYCL_TARGET_AMD_GPU_GFX702__ == 1) ||
318  (__SYCL_TARGET_AMD_GPU_GFX801__ == 1) ||
319  (__SYCL_TARGET_AMD_GPU_GFX802__ == 1) ||
320  (__SYCL_TARGET_AMD_GPU_GFX803__ == 1) ||
321  (__SYCL_TARGET_AMD_GPU_GFX805__ == 1) ||
322  (__SYCL_TARGET_AMD_GPU_GFX810__ == 1) ||
323  (__SYCL_TARGET_AMD_GPU_GFX900__ == 1) ||
324  (__SYCL_TARGET_AMD_GPU_GFX902__ == 1) ||
325  (__SYCL_TARGET_AMD_GPU_GFX904__ == 1) ||
326  (__SYCL_TARGET_AMD_GPU_GFX906__ == 1) ||
327  (__SYCL_TARGET_AMD_GPU_GFX908__ == 1) ||
328  (__SYCL_TARGET_AMD_GPU_GFX90A__ == 1) ||
329  (__SYCL_TARGET_AMD_GPU_GFX1010__ == 1) ||
330  (__SYCL_TARGET_AMD_GPU_GFX1011__ == 1) ||
331  (__SYCL_TARGET_AMD_GPU_GFX1012__ == 1) ||
332  (__SYCL_TARGET_AMD_GPU_GFX1013__ == 1) ||
333  (__SYCL_TARGET_AMD_GPU_GFX1030__ == 1) ||
334  (__SYCL_TARGET_AMD_GPU_GFX1031__ == 1) ||
335  (__SYCL_TARGET_AMD_GPU_GFX1032__ == 1) ||
336  (__SYCL_TARGET_AMD_GPU_GFX1034__ == 1);
337 
338 struct IsAOTForArchitectureClass {
339  // Allocate an array of size == size of
340  // ext::oneapi::experimental::architecture enum.
341  bool arr[static_cast<int>(max_architecture) + 1];
342 
343  using arch = ext::oneapi::experimental::architecture;
344 
345  constexpr IsAOTForArchitectureClass() : arr() {
346  arr[static_cast<int>(arch::x86_64)] = __SYCL_TARGET_INTEL_X86_64__ == 1;
347  arr[static_cast<int>(arch::intel_gpu_bdw)] =
348  __SYCL_TARGET_INTEL_GPU_BDW__ == 1;
349  arr[static_cast<int>(arch::intel_gpu_skl)] =
350  __SYCL_TARGET_INTEL_GPU_SKL__ == 1;
351  arr[static_cast<int>(arch::intel_gpu_kbl)] =
352  __SYCL_TARGET_INTEL_GPU_KBL__ == 1;
353  arr[static_cast<int>(arch::intel_gpu_cfl)] =
354  __SYCL_TARGET_INTEL_GPU_CFL__ == 1;
355  arr[static_cast<int>(arch::intel_gpu_apl)] =
356  __SYCL_TARGET_INTEL_GPU_APL__ == 1;
357  arr[static_cast<int>(arch::intel_gpu_glk)] =
358  __SYCL_TARGET_INTEL_GPU_GLK__ == 1;
359  arr[static_cast<int>(arch::intel_gpu_whl)] =
360  __SYCL_TARGET_INTEL_GPU_WHL__ == 1;
361  arr[static_cast<int>(arch::intel_gpu_aml)] =
362  __SYCL_TARGET_INTEL_GPU_AML__ == 1;
363  arr[static_cast<int>(arch::intel_gpu_cml)] =
364  __SYCL_TARGET_INTEL_GPU_CML__ == 1;
365  arr[static_cast<int>(arch::intel_gpu_icllp)] =
366  __SYCL_TARGET_INTEL_GPU_ICLLP__ == 1;
367  arr[static_cast<int>(arch::intel_gpu_ehl)] =
368  __SYCL_TARGET_INTEL_GPU_EHL__ == 1;
369  arr[static_cast<int>(arch::intel_gpu_tgllp)] =
370  __SYCL_TARGET_INTEL_GPU_TGLLP__ == 1;
371  arr[static_cast<int>(arch::intel_gpu_rkl)] =
372  __SYCL_TARGET_INTEL_GPU_RKL__ == 1;
373  arr[static_cast<int>(arch::intel_gpu_adl_s)] =
374  __SYCL_TARGET_INTEL_GPU_ADL_S__ == 1;
375  arr[static_cast<int>(arch::intel_gpu_rpl_s)] =
376  __SYCL_TARGET_INTEL_GPU_RPL_S__ == 1;
377  arr[static_cast<int>(arch::intel_gpu_adl_p)] =
378  __SYCL_TARGET_INTEL_GPU_ADL_P__ == 1;
379  arr[static_cast<int>(arch::intel_gpu_adl_n)] =
380  __SYCL_TARGET_INTEL_GPU_ADL_N__ == 1;
381  arr[static_cast<int>(arch::intel_gpu_dg1)] =
382  __SYCL_TARGET_INTEL_GPU_DG1__ == 1;
383  arr[static_cast<int>(arch::intel_gpu_acm_g10)] =
384  __SYCL_TARGET_INTEL_GPU_ACM_G10__ == 1;
385  arr[static_cast<int>(arch::intel_gpu_acm_g11)] =
386  __SYCL_TARGET_INTEL_GPU_ACM_G11__ == 1;
387  arr[static_cast<int>(arch::intel_gpu_acm_g12)] =
388  __SYCL_TARGET_INTEL_GPU_ACM_G12__ == 1;
389  arr[static_cast<int>(arch::intel_gpu_pvc)] =
390  __SYCL_TARGET_INTEL_GPU_PVC__ == 1;
391  arr[static_cast<int>(arch::nvidia_gpu_sm_50)] =
392  __SYCL_TARGET_NVIDIA_GPU_SM50__ == 1;
393  arr[static_cast<int>(arch::nvidia_gpu_sm_52)] =
394  __SYCL_TARGET_NVIDIA_GPU_SM52__ == 1;
395  arr[static_cast<int>(arch::nvidia_gpu_sm_53)] =
396  __SYCL_TARGET_NVIDIA_GPU_SM53__ == 1;
397  arr[static_cast<int>(arch::nvidia_gpu_sm_60)] =
398  __SYCL_TARGET_NVIDIA_GPU_SM60__ == 1;
399  arr[static_cast<int>(arch::nvidia_gpu_sm_61)] =
400  __SYCL_TARGET_NVIDIA_GPU_SM61__ == 1;
401  arr[static_cast<int>(arch::nvidia_gpu_sm_62)] =
402  __SYCL_TARGET_NVIDIA_GPU_SM62__ == 1;
403  arr[static_cast<int>(arch::nvidia_gpu_sm_70)] =
404  __SYCL_TARGET_NVIDIA_GPU_SM70__ == 1;
405  arr[static_cast<int>(arch::nvidia_gpu_sm_72)] =
406  __SYCL_TARGET_NVIDIA_GPU_SM72__ == 1;
407  arr[static_cast<int>(arch::nvidia_gpu_sm_75)] =
408  __SYCL_TARGET_NVIDIA_GPU_SM75__ == 1;
409  arr[static_cast<int>(arch::nvidia_gpu_sm_80)] =
410  __SYCL_TARGET_NVIDIA_GPU_SM80__ == 1;
411  arr[static_cast<int>(arch::nvidia_gpu_sm_86)] =
412  __SYCL_TARGET_NVIDIA_GPU_SM86__ == 1;
413  arr[static_cast<int>(arch::nvidia_gpu_sm_87)] =
414  __SYCL_TARGET_NVIDIA_GPU_SM87__ == 1;
415  arr[static_cast<int>(arch::nvidia_gpu_sm_89)] =
416  __SYCL_TARGET_NVIDIA_GPU_SM89__ == 1;
417  arr[static_cast<int>(arch::nvidia_gpu_sm_90)] =
418  __SYCL_TARGET_NVIDIA_GPU_SM90__ == 1;
419  arr[static_cast<int>(arch::amd_gpu_gfx700)] =
420  __SYCL_TARGET_AMD_GPU_GFX700__ == 1;
421  arr[static_cast<int>(arch::amd_gpu_gfx701)] =
422  __SYCL_TARGET_AMD_GPU_GFX701__ == 1;
423  arr[static_cast<int>(arch::amd_gpu_gfx702)] =
424  __SYCL_TARGET_AMD_GPU_GFX702__ == 1;
425  arr[static_cast<int>(arch::amd_gpu_gfx801)] =
426  __SYCL_TARGET_AMD_GPU_GFX801__ == 1;
427  arr[static_cast<int>(arch::amd_gpu_gfx802)] =
428  __SYCL_TARGET_AMD_GPU_GFX802__ == 1;
429  arr[static_cast<int>(arch::amd_gpu_gfx803)] =
430  __SYCL_TARGET_AMD_GPU_GFX803__ == 1;
431  arr[static_cast<int>(arch::amd_gpu_gfx805)] =
432  __SYCL_TARGET_AMD_GPU_GFX805__ == 1;
433  arr[static_cast<int>(arch::amd_gpu_gfx810)] =
434  __SYCL_TARGET_AMD_GPU_GFX810__ == 1;
435  arr[static_cast<int>(arch::amd_gpu_gfx900)] =
436  __SYCL_TARGET_AMD_GPU_GFX900__ == 1;
437  arr[static_cast<int>(arch::amd_gpu_gfx902)] =
438  __SYCL_TARGET_AMD_GPU_GFX902__ == 1;
439  arr[static_cast<int>(arch::amd_gpu_gfx904)] =
440  __SYCL_TARGET_AMD_GPU_GFX904__ == 1;
441  arr[static_cast<int>(arch::amd_gpu_gfx906)] =
442  __SYCL_TARGET_AMD_GPU_GFX906__ == 1;
443  arr[static_cast<int>(arch::amd_gpu_gfx908)] =
444  __SYCL_TARGET_AMD_GPU_GFX908__ == 1;
445  arr[static_cast<int>(arch::amd_gpu_gfx90a)] =
446  __SYCL_TARGET_AMD_GPU_GFX90A__ == 1;
447  arr[static_cast<int>(arch::amd_gpu_gfx1010)] =
448  __SYCL_TARGET_AMD_GPU_GFX1010__ == 1;
449  arr[static_cast<int>(arch::amd_gpu_gfx1011)] =
450  __SYCL_TARGET_AMD_GPU_GFX1011__ == 1;
451  arr[static_cast<int>(arch::amd_gpu_gfx1012)] =
452  __SYCL_TARGET_AMD_GPU_GFX1012__ == 1;
453  arr[static_cast<int>(arch::amd_gpu_gfx1030)] =
454  __SYCL_TARGET_AMD_GPU_GFX1030__ == 1;
455  arr[static_cast<int>(arch::amd_gpu_gfx1031)] =
456  __SYCL_TARGET_AMD_GPU_GFX1031__ == 1;
457  arr[static_cast<int>(arch::amd_gpu_gfx1032)] =
458  __SYCL_TARGET_AMD_GPU_GFX1032__ == 1;
459  arr[static_cast<int>(arch::amd_gpu_gfx1034)] =
460  __SYCL_TARGET_AMD_GPU_GFX1034__ == 1;
461  }
462 };
463 
464 // One entry for each enumerator in "architecture" telling whether the AOT
465 // target matches that architecture.
466 static constexpr IsAOTForArchitectureClass is_aot_for_architecture;
467 
468 // Reads the value of "is_allowable_aot_mode" via a template to defer triggering
469 // static_assert() until template instantiation time.
470 template <ext::oneapi::experimental::architecture... Archs>
471 constexpr static bool allowable_aot_mode() {
472  return is_allowable_aot_mode;
473 }
474 
475 // Tells if the current device has one of the architectures in the parameter
476 // pack.
477 template <ext::oneapi::experimental::architecture... Archs>
478 constexpr static bool device_architecture_is() {
479  return (is_aot_for_architecture.arr[static_cast<int>(Archs)] || ...);
480 }
481 
482 // Helper object used to implement "else_if_architecture_is" and "otherwise".
483 // The "MakeCall" template parameter tells whether a previous clause in the
484 // "if-elseif-elseif ..." chain was true. When "MakeCall" is false, some
485 // previous clause was true, so none of the subsequent
486 // "else_if_architecture_is" or "otherwise" member functions should call the
487 // user's function.
488 template <bool MakeCall> class if_architecture_helper {
489 public:
490  template <ext::oneapi::experimental::architecture... Archs, typename T,
491  typename... Args>
492  constexpr auto else_if_architecture_is(T fnTrue, Args... args) {
493  if constexpr (MakeCall && device_architecture_is<Archs...>()) {
494  fnTrue(args...);
495  return if_architecture_helper<false>{};
496  } else {
497  (void)fnTrue;
498  return if_architecture_helper<MakeCall>{};
499  }
500  }
501 
502  template <typename T, typename... Args>
503  constexpr void otherwise(T fn, Args... args) {
504  if constexpr (MakeCall) {
505  fn(args...);
506  }
507  }
508 };
509 } // namespace detail
510 
511 namespace ext::oneapi::experimental {
512 
513 template <architecture... Archs, typename T, typename... Args>
514 constexpr static auto if_architecture_is(T fnTrue, Args... args) {
515  static_assert(sycl::detail::allowable_aot_mode<Archs...>(),
516  "The if_architecture_is function may only be used when AOT "
517  "compiling with '-fsycl-targets=spir64_x86_64' or "
518  "'-fsycl-targets=*_gpu_*'");
519  if constexpr (sycl::detail::device_architecture_is<Archs...>()) {
520  fnTrue(args...);
521  return sycl::detail::if_architecture_helper<false>{};
522  } else {
523  (void)fnTrue;
524  return sycl::detail::if_architecture_helper<true>{};
525  }
526 }
527 
528 } // namespace ext::oneapi::experimental
529 } // __SYCL_INLINE_VER_NAMESPACE(_V1)
530 } // namespace sycl
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1031
@ amd_gpu_gfx1031
__SYCL_TARGET_AMD_GPU_GFX902__
#define __SYCL_TARGET_AMD_GPU_GFX902__
Definition: device_architecture.hpp:233
__SYCL_TARGET_NVIDIA_GPU_SM52__
#define __SYCL_TARGET_NVIDIA_GPU_SM52__
Definition: device_architecture.hpp:167
__SYCL_TARGET_NVIDIA_GPU_SM70__
#define __SYCL_TARGET_NVIDIA_GPU_SM70__
Definition: device_architecture.hpp:182
__SYCL_TARGET_INTEL_GPU_AML__
#define __SYCL_TARGET_INTEL_GPU_AML__
Definition: device_architecture.hpp:119
sycl::_V1::ext::oneapi::experimental::if_architecture_is
constexpr static auto if_architecture_is(T fnTrue, Args... args)
Definition: device_architecture.hpp:514
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx801
@ amd_gpu_gfx801
__SYCL_TARGET_AMD_GPU_GFX1011__
#define __SYCL_TARGET_AMD_GPU_GFX1011__
Definition: device_architecture.hpp:251
__SYCL_TARGET_NVIDIA_GPU_SM72__
#define __SYCL_TARGET_NVIDIA_GPU_SM72__
Definition: device_architecture.hpp:185
__SYCL_TARGET_INTEL_GPU_GLK__
#define __SYCL_TARGET_INTEL_GPU_GLK__
Definition: device_architecture.hpp:113
__SYCL_TARGET_INTEL_GPU_ADL_S__
#define __SYCL_TARGET_INTEL_GPU_ADL_S__
Definition: device_architecture.hpp:137
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx906
@ amd_gpu_gfx906
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_6_0
@ intel_gpu_9_6_0
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_70
@ nvidia_gpu_sm_70
sycl::_V1::detail::device_architecture_is
constexpr static bool device_architecture_is()
Definition: device_architecture.hpp:478
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_kbl
@ intel_gpu_kbl
__SYCL_TARGET_NVIDIA_GPU_SM62__
#define __SYCL_TARGET_NVIDIA_GPU_SM62__
Definition: device_architecture.hpp:179
__SYCL_TARGET_INTEL_X86_64__
#define __SYCL_TARGET_INTEL_X86_64__
Definition: device_architecture.hpp:95
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_rpl_s
@ intel_gpu_rpl_s
__SYCL_TARGET_AMD_GPU_GFX1030__
#define __SYCL_TARGET_AMD_GPU_GFX1030__
Definition: device_architecture.hpp:260
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx701
@ amd_gpu_gfx701
__SYCL_INLINE_VER_NAMESPACE
#define __SYCL_INLINE_VER_NAMESPACE(X)
Definition: defines_elementary.hpp:11
__SYCL_TARGET_AMD_GPU_GFX1034__
#define __SYCL_TARGET_AMD_GPU_GFX1034__
Definition: device_architecture.hpp:269
__SYCL_TARGET_NVIDIA_GPU_SM75__
#define __SYCL_TARGET_NVIDIA_GPU_SM75__
Definition: device_architecture.hpp:188
__SYCL_TARGET_NVIDIA_GPU_SM60__
#define __SYCL_TARGET_NVIDIA_GPU_SM60__
Definition: device_architecture.hpp:173
__SYCL_TARGET_AMD_GPU_GFX810__
#define __SYCL_TARGET_AMD_GPU_GFX810__
Definition: device_architecture.hpp:227
__SYCL_TARGET_INTEL_GPU_EHL__
#define __SYCL_TARGET_INTEL_GPU_EHL__
Definition: device_architecture.hpp:128
sycl::_V1::detail::IsAOTForArchitectureClass::IsAOTForArchitectureClass
constexpr IsAOTForArchitectureClass()
Definition: device_architecture.hpp:345
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_cfl
@ intel_gpu_cfl
__SYCL_TARGET_INTEL_GPU_RKL__
#define __SYCL_TARGET_INTEL_GPU_RKL__
Definition: device_architecture.hpp:134
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_acm_g11
@ intel_gpu_acm_g11
__SYCL_TARGET_INTEL_GPU_ICLLP__
#define __SYCL_TARGET_INTEL_GPU_ICLLP__
Definition: device_architecture.hpp:125
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1013
@ amd_gpu_gfx1013
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1010
@ amd_gpu_gfx1010
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_0_9
@ intel_gpu_9_0_9
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1011
@ amd_gpu_gfx1011
__SYCL_TARGET_NVIDIA_GPU_SM90__
#define __SYCL_TARGET_NVIDIA_GPU_SM90__
Definition: device_architecture.hpp:203
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_whl
@ intel_gpu_whl
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1032
@ amd_gpu_gfx1032
__SYCL_TARGET_INTEL_GPU_ADL_P__
#define __SYCL_TARGET_INTEL_GPU_ADL_P__
Definition: device_architecture.hpp:143
__SYCL_TARGET_AMD_GPU_GFX1032__
#define __SYCL_TARGET_AMD_GPU_GFX1032__
Definition: device_architecture.hpp:266
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx805
@ amd_gpu_gfx805
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_2_9
@ intel_gpu_9_2_9
sycl
---— Error handling, matching OpenCL plugin semantics.
Definition: access.hpp:14
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_53
@ nvidia_gpu_sm_53
__SYCL_TARGET_INTEL_GPU_DG1__
#define __SYCL_TARGET_INTEL_GPU_DG1__
Definition: device_architecture.hpp:149
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_acm_g10
@ intel_gpu_acm_g10
__SYCL_TARGET_NVIDIA_GPU_SM80__
#define __SYCL_TARGET_NVIDIA_GPU_SM80__
Definition: device_architecture.hpp:191
__SYCL_TARGET_INTEL_GPU_KBL__
#define __SYCL_TARGET_INTEL_GPU_KBL__
Definition: device_architecture.hpp:104
__SYCL_TARGET_AMD_GPU_GFX1012__
#define __SYCL_TARGET_AMD_GPU_GFX1012__
Definition: device_architecture.hpp:254
sycl::_V1::ext::oneapi::experimental::architecture
architecture
Definition: device_architecture.hpp:9
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_icllp
@ intel_gpu_icllp
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_adl_n
@ intel_gpu_adl_n
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_3_0
@ intel_gpu_9_3_0
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_aml
@ intel_gpu_aml
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_86
@ nvidia_gpu_sm_86
__SYCL_TARGET_NVIDIA_GPU_SM61__
#define __SYCL_TARGET_NVIDIA_GPU_SM61__
Definition: device_architecture.hpp:176
__SYCL_TARGET_INTEL_GPU_BDW__
#define __SYCL_TARGET_INTEL_GPU_BDW__
Definition: device_architecture.hpp:98
__SYCL_TARGET_INTEL_GPU_TGLLP__
#define __SYCL_TARGET_INTEL_GPU_TGLLP__
Definition: device_architecture.hpp:131
__SYCL_TARGET_NVIDIA_GPU_SM89__
#define __SYCL_TARGET_NVIDIA_GPU_SM89__
Definition: device_architecture.hpp:200
__SYCL_TARGET_INTEL_GPU_CFL__
#define __SYCL_TARGET_INTEL_GPU_CFL__
Definition: device_architecture.hpp:107
__SYCL_TARGET_INTEL_GPU_APL__
#define __SYCL_TARGET_INTEL_GPU_APL__
Definition: device_architecture.hpp:110
__SYCL_TARGET_INTEL_GPU_ACM_G11__
#define __SYCL_TARGET_INTEL_GPU_ACM_G11__
Definition: device_architecture.hpp:155
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_8_0_0
@ intel_gpu_8_0_0
defines_elementary.hpp
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_apl
@ intel_gpu_apl
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx90a
@ amd_gpu_gfx90a
__SYCL_TARGET_AMD_GPU_GFX801__
#define __SYCL_TARGET_AMD_GPU_GFX801__
Definition: device_architecture.hpp:215
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_52
@ nvidia_gpu_sm_52
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_tgllp
@ intel_gpu_tgllp
__SYCL_TARGET_AMD_GPU_GFX900__
#define __SYCL_TARGET_AMD_GPU_GFX900__
Definition: device_architecture.hpp:230
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_rkl
@ intel_gpu_rkl
__SYCL_TARGET_AMD_GPU_GFX908__
#define __SYCL_TARGET_AMD_GPU_GFX908__
Definition: device_architecture.hpp:242
sycl::_V1::detail::if_architecture_helper
Definition: device_architecture.hpp:488
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_4_0
@ intel_gpu_9_4_0
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx900
@ amd_gpu_gfx900
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_50
@ nvidia_gpu_sm_50
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx702
@ amd_gpu_gfx702
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_5_0
@ intel_gpu_9_5_0
__SYCL_TARGET_INTEL_GPU_ADL_N__
#define __SYCL_TARGET_INTEL_GPU_ADL_N__
Definition: device_architecture.hpp:146
sycl::_V1::detail::if_architecture_helper::otherwise
constexpr void otherwise(T fn, Args... args)
Definition: device_architecture.hpp:503
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_72
@ nvidia_gpu_sm_72
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_11_2_0
@ intel_gpu_11_2_0
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_adl_p
@ intel_gpu_adl_p
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1034
@ amd_gpu_gfx1034
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_ehl
@ intel_gpu_ehl
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_skl
@ intel_gpu_skl
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_bdw
@ intel_gpu_bdw
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_12_0_0
@ intel_gpu_12_0_0
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_61
@ nvidia_gpu_sm_61
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1030
@ amd_gpu_gfx1030
__SYCL_TARGET_INTEL_GPU_ACM_G10__
#define __SYCL_TARGET_INTEL_GPU_ACM_G10__
Definition: device_architecture.hpp:152
sycl::_V1::ext::oneapi::experimental::architecture::x86_64
@ x86_64
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx902
@ amd_gpu_gfx902
__SYCL_TARGET_AMD_GPU_GFX1010__
#define __SYCL_TARGET_AMD_GPU_GFX1010__
Definition: device_architecture.hpp:248
__SYCL_TARGET_INTEL_GPU_PVC__
#define __SYCL_TARGET_INTEL_GPU_PVC__
Definition: device_architecture.hpp:161
__SYCL_TARGET_AMD_GPU_GFX802__
#define __SYCL_TARGET_AMD_GPU_GFX802__
Definition: device_architecture.hpp:218
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_87
@ nvidia_gpu_sm_87
__SYCL_TARGET_INTEL_GPU_WHL__
#define __SYCL_TARGET_INTEL_GPU_WHL__
Definition: device_architecture.hpp:116
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_adl_s
@ intel_gpu_adl_s
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx803
@ amd_gpu_gfx803
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_60
@ nvidia_gpu_sm_60
__SYCL_TARGET_AMD_GPU_GFX805__
#define __SYCL_TARGET_AMD_GPU_GFX805__
Definition: device_architecture.hpp:224
__SYCL_TARGET_AMD_GPU_GFX90A__
#define __SYCL_TARGET_AMD_GPU_GFX90A__
Definition: device_architecture.hpp:245
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_7_0
@ intel_gpu_9_7_0
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_dg1
@ intel_gpu_dg1
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_75
@ nvidia_gpu_sm_75
__SYCL_TARGET_NVIDIA_GPU_SM87__
#define __SYCL_TARGET_NVIDIA_GPU_SM87__
Definition: device_architecture.hpp:197
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_62
@ nvidia_gpu_sm_62
sycl::_V1::detail::if_architecture_helper::else_if_architecture_is
constexpr auto else_if_architecture_is(T fnTrue, Args... args)
Definition: device_architecture.hpp:492
sycl::_V1::detail::IsAOTForArchitectureClass::arr
bool arr[static_cast< int >(max_architecture)+1]
Definition: device_architecture.hpp:341
__SYCL_TARGET_AMD_GPU_GFX1031__
#define __SYCL_TARGET_AMD_GPU_GFX1031__
Definition: device_architecture.hpp:263
sycl::_V1::detail::is_aot_for_architecture
static constexpr IsAOTForArchitectureClass is_aot_for_architecture
Definition: device_architecture.hpp:466
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_89
@ nvidia_gpu_sm_89
__SYCL_TARGET_NVIDIA_GPU_SM86__
#define __SYCL_TARGET_NVIDIA_GPU_SM86__
Definition: device_architecture.hpp:194
__SYCL_TARGET_AMD_GPU_GFX906__
#define __SYCL_TARGET_AMD_GPU_GFX906__
Definition: device_architecture.hpp:239
__SYCL_TARGET_AMD_GPU_GFX803__
#define __SYCL_TARGET_AMD_GPU_GFX803__
Definition: device_architecture.hpp:221
sycl::_V1::detail::max_architecture
static constexpr ext::oneapi::experimental::architecture max_architecture
Definition: device_architecture.hpp:91
__SYCL_TARGET_AMD_GPU_GFX904__
#define __SYCL_TARGET_AMD_GPU_GFX904__
Definition: device_architecture.hpp:236
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx810
@ amd_gpu_gfx810
__SYCL_TARGET_INTEL_GPU_SKL__
#define __SYCL_TARGET_INTEL_GPU_SKL__
Definition: device_architecture.hpp:101
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_9_1_9
@ intel_gpu_9_1_9
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx904
@ amd_gpu_gfx904
__SYCL_TARGET_NVIDIA_GPU_SM50__
#define __SYCL_TARGET_NVIDIA_GPU_SM50__
Definition: device_architecture.hpp:164
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_glk
@ intel_gpu_glk
sycl::_V1::detail::IsAOTForArchitectureClass
Definition: device_architecture.hpp:338
sycl::_V1::detail::is_allowable_aot_mode
static constexpr bool is_allowable_aot_mode
Definition: device_architecture.hpp:277
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_11_0_0
@ intel_gpu_11_0_0
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_80
@ nvidia_gpu_sm_80
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_cml
@ intel_gpu_cml
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_12_10_0
@ intel_gpu_12_10_0
__SYCL_TARGET_AMD_GPU_GFX701__
#define __SYCL_TARGET_AMD_GPU_GFX701__
Definition: device_architecture.hpp:209
__SYCL_TARGET_AMD_GPU_GFX700__
#define __SYCL_TARGET_AMD_GPU_GFX700__
Definition: device_architecture.hpp:206
__SYCL_TARGET_INTEL_GPU_RPL_S__
#define __SYCL_TARGET_INTEL_GPU_RPL_S__
Definition: device_architecture.hpp:140
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_acm_g12
@ intel_gpu_acm_g12
__SYCL_TARGET_INTEL_GPU_ACM_G12__
#define __SYCL_TARGET_INTEL_GPU_ACM_G12__
Definition: device_architecture.hpp:158
sycl::_V1::ext::oneapi::experimental::architecture::nvidia_gpu_sm_90
@ nvidia_gpu_sm_90
__SYCL_TARGET_NVIDIA_GPU_SM53__
#define __SYCL_TARGET_NVIDIA_GPU_SM53__
Definition: device_architecture.hpp:170
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx700
@ amd_gpu_gfx700
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx1012
@ amd_gpu_gfx1012
__SYCL_TARGET_INTEL_GPU_CML__
#define __SYCL_TARGET_INTEL_GPU_CML__
Definition: device_architecture.hpp:122
sycl::_V1::detail::allowable_aot_mode
constexpr static bool allowable_aot_mode()
Definition: device_architecture.hpp:471
__SYCL_TARGET_AMD_GPU_GFX702__
#define __SYCL_TARGET_AMD_GPU_GFX702__
Definition: device_architecture.hpp:212
__SYCL_TARGET_AMD_GPU_GFX1013__
#define __SYCL_TARGET_AMD_GPU_GFX1013__
Definition: device_architecture.hpp:257
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx802
@ amd_gpu_gfx802
sycl::_V1::ext::oneapi::experimental::architecture::intel_gpu_pvc
@ intel_gpu_pvc
sycl::_V1::ext::oneapi::experimental::architecture::amd_gpu_gfx908
@ amd_gpu_gfx908