DPC++ Runtime
Runtime libraries for oneAPI DPC++
builtins.hpp
Go to the documentation of this file.
1 //==----------- builtins.hpp - SYCL built-in functions ---------------------==//
2 //
3 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
4 // See https://llvm.org/LICENSE.txt for license information.
5 // SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
6 //
7 //===----------------------------------------------------------------------===//
8 
9 #pragma once
10 
11 #include <sycl/detail/defines_elementary.hpp> // for __SYCL_ALWAYS_INLINE
12 #include <sycl/detail/generic_type_traits.hpp> // for convertDataToType
13 
14 // TODO Decide whether to mark functions with this attribute.
15 #define __NOEXC /*noexcept*/
16 
17 #ifdef __SYCL_DEVICE_ONLY__
18 #define __FUNC_PREFIX_OCL __spirv_ocl_
19 #define __FUNC_PREFIX_CORE __spirv_
20 #define __SYCL_EXTERN_IT1(Ret, prefix, call, Arg1)
21 #define __SYCL_EXTERN_IT2(Ret, prefix, call, Arg1, Arg2)
22 #define __SYCL_EXTERN_IT2_SAME(Ret, prefix, call, Arg)
23 #define __SYCL_EXTERN_IT3(Ret, prefix, call, Arg1, Arg2, Arg3)
24 #else
25 #define __FUNC_PREFIX_OCL sycl_host_
26 #define __FUNC_PREFIX_CORE sycl_host_
27 #define __SYCL_EXTERN_IT1(Ret, prefix, call, Arg) \
28  extern Ret __SYCL_PPCAT(prefix, call)(Arg)
29 #define __SYCL_EXTERN_IT2_SAME(Ret, prefix, call, Arg) \
30  extern Ret __SYCL_PPCAT(prefix, call)(Arg, Arg)
31 #define __SYCL_EXTERN_IT2(Ret, prefix, call, Arg1, Arg2) \
32  extern Ret __SYCL_PPCAT(prefix, call)(Arg1, Arg2)
33 #define __SYCL_EXTERN_IT3(Ret, prefix, call, Arg1, Arg2, Arg3) \
34  extern Ret __SYCL_PPCAT(prefix, call)(Arg1, Arg2, Arg3)
35 #endif
36 
37 #define __SYCL_PPCAT_NX(A, B) A##B
38 #define __SYCL_PPCAT(A, B) __SYCL_PPCAT_NX(A, B)
39 
40 #define __SYCL_MAKE_CALL_ARG1(call, prefix) \
41  template <typename R, typename T1> \
42  inline __SYCL_ALWAYS_INLINE R __invoke_##call(T1 t1) __NOEXC { \
43  using Ret = sycl::detail::ConvertToOpenCLType_t<R>; \
44  using Arg1 = sycl::detail::ConvertToOpenCLType_t<T1>; \
45  __SYCL_EXTERN_IT1(Ret, prefix, call, Arg1); \
46  Arg1 arg1 = sycl::detail::convertDataToType<T1, Arg1>(t1); \
47  Ret ret = __SYCL_PPCAT(prefix, call)(arg1); \
48  return sycl::detail::convertDataToType<Ret, R>(ret); \
49  }
50 
51 #define __SYCL_MAKE_CALL_ARG2(call, prefix) \
52  template <typename R, typename T1, typename T2> \
53  inline __SYCL_ALWAYS_INLINE R __invoke_##call(T1 t1, T2 t2) __NOEXC { \
54  using Ret = sycl::detail::ConvertToOpenCLType_t<R>; \
55  using Arg1 = sycl::detail::ConvertToOpenCLType_t<T1>; \
56  using Arg2 = sycl::detail::ConvertToOpenCLType_t<T2>; \
57  __SYCL_EXTERN_IT2(Ret, prefix, call, Arg1, Arg2); \
58  Arg1 arg1 = sycl::detail::convertDataToType<T1, Arg1>(t1); \
59  Arg2 arg2 = sycl::detail::convertDataToType<T2, Arg2>(t2); \
60  Ret ret = __SYCL_PPCAT(prefix, call)(arg1, arg2); \
61  return sycl::detail::convertDataToType<Ret, R>(ret); \
62  }
63 
64 #define __SYCL_MAKE_CALL_ARG2_SAME(call, prefix) \
65  template <typename R, typename T> \
66  inline __SYCL_ALWAYS_INLINE R __invoke_##call(T t1, T t2) __NOEXC { \
67  using Ret = sycl::detail::ConvertToOpenCLType_t<R>; \
68  using Arg = sycl::detail::ConvertToOpenCLType_t<T>; \
69  __SYCL_EXTERN_IT2_SAME(Ret, prefix, call, Arg); \
70  Arg arg1 = sycl::detail::convertDataToType<T, Arg>(t1); \
71  Arg arg2 = sycl::detail::convertDataToType<T, Arg>(t2); \
72  Ret ret = __SYCL_PPCAT(prefix, call)(arg1, arg2); \
73  return sycl::detail::convertDataToType<Ret, R>(ret); \
74  }
75 
76 #define __SYCL_MAKE_CALL_ARG2_SAME_RESULT(call, prefix) \
77  template <typename T> \
78  inline __SYCL_ALWAYS_INLINE T __invoke_##call(T v1, T v2) __NOEXC { \
79  using Type = sycl::detail::ConvertToOpenCLType_t<T>; \
80  __SYCL_EXTERN_IT2_SAME(Type, prefix, call, Type); \
81  Type arg1 = sycl::detail::convertDataToType<T, Type>(v1); \
82  Type arg2 = sycl::detail::convertDataToType<T, Type>(v2); \
83  Type ret = __SYCL_PPCAT(prefix, call)(arg1, arg2); \
84  return sycl::detail::convertDataToType<Type, T>(ret); \
85  }
86 
87 #define __SYCL_MAKE_CALL_ARG3(call, prefix) \
88  template <typename R, typename T1, typename T2, typename T3> \
89  inline __SYCL_ALWAYS_INLINE R __invoke_##call(T1 t1, T2 t2, T3 t3) __NOEXC { \
90  using Ret = sycl::detail::ConvertToOpenCLType_t<R>; \
91  using Arg1 = sycl::detail::ConvertToOpenCLType_t<T1>; \
92  using Arg2 = sycl::detail::ConvertToOpenCLType_t<T2>; \
93  using Arg3 = sycl::detail::ConvertToOpenCLType_t<T3>; \
94  __SYCL_EXTERN_IT3(Ret, prefix, call, Arg1, Arg2, Arg3); \
95  Arg1 arg1 = sycl::detail::convertDataToType<T1, Arg1>(t1); \
96  Arg2 arg2 = sycl::detail::convertDataToType<T2, Arg2>(t2); \
97  Arg3 arg3 = sycl::detail::convertDataToType<T3, Arg3>(t3); \
98  Ret ret = __SYCL_PPCAT(prefix, call)(arg1, arg2, arg3); \
99  return sycl::detail::convertDataToType<Ret, R>(ret); \
100  }
101 
102 #ifndef __SYCL_DEVICE_ONLY__
103 namespace __host_std {
104 #endif // __SYCL_DEVICE_ONLY__
105 /* ----------------- 4.13.3 Math functions. ---------------------------------*/
106 __SYCL_MAKE_CALL_ARG1(acos, __FUNC_PREFIX_OCL)
107 __SYCL_MAKE_CALL_ARG1(acosh, __FUNC_PREFIX_OCL)
108 __SYCL_MAKE_CALL_ARG1(acospi, __FUNC_PREFIX_OCL)
109 __SYCL_MAKE_CALL_ARG1(asin, __FUNC_PREFIX_OCL)
110 __SYCL_MAKE_CALL_ARG1(asinh, __FUNC_PREFIX_OCL)
111 __SYCL_MAKE_CALL_ARG1(asinpi, __FUNC_PREFIX_OCL)
112 __SYCL_MAKE_CALL_ARG1(atan, __FUNC_PREFIX_OCL)
113 __SYCL_MAKE_CALL_ARG2(atan2, __FUNC_PREFIX_OCL)
114 __SYCL_MAKE_CALL_ARG1(atanh, __FUNC_PREFIX_OCL)
115 __SYCL_MAKE_CALL_ARG1(atanpi, __FUNC_PREFIX_OCL)
116 __SYCL_MAKE_CALL_ARG2(atan2pi, __FUNC_PREFIX_OCL)
117 __SYCL_MAKE_CALL_ARG1(cbrt, __FUNC_PREFIX_OCL)
118 __SYCL_MAKE_CALL_ARG1(ceil, __FUNC_PREFIX_OCL)
119 __SYCL_MAKE_CALL_ARG2(copysign, __FUNC_PREFIX_OCL)
120 __SYCL_MAKE_CALL_ARG1(cos, __FUNC_PREFIX_OCL)
121 __SYCL_MAKE_CALL_ARG1(cosh, __FUNC_PREFIX_OCL)
122 __SYCL_MAKE_CALL_ARG1(cospi, __FUNC_PREFIX_OCL)
123 __SYCL_MAKE_CALL_ARG1(erfc, __FUNC_PREFIX_OCL)
124 __SYCL_MAKE_CALL_ARG1(erf, __FUNC_PREFIX_OCL)
125 __SYCL_MAKE_CALL_ARG1(exp, __FUNC_PREFIX_OCL)
126 __SYCL_MAKE_CALL_ARG1(exp2, __FUNC_PREFIX_OCL)
127 __SYCL_MAKE_CALL_ARG1(exp10, __FUNC_PREFIX_OCL)
128 __SYCL_MAKE_CALL_ARG1(expm1, __FUNC_PREFIX_OCL)
129 __SYCL_MAKE_CALL_ARG1(fabs, __FUNC_PREFIX_OCL)
130 __SYCL_MAKE_CALL_ARG2(fdim, __FUNC_PREFIX_OCL)
131 __SYCL_MAKE_CALL_ARG1(floor, __FUNC_PREFIX_OCL)
132 __SYCL_MAKE_CALL_ARG3(fma, __FUNC_PREFIX_OCL)
133 __SYCL_MAKE_CALL_ARG2(fmax, __FUNC_PREFIX_OCL)
134 __SYCL_MAKE_CALL_ARG2(fmin, __FUNC_PREFIX_OCL)
135 __SYCL_MAKE_CALL_ARG2(fmod, __FUNC_PREFIX_OCL)
136 __SYCL_MAKE_CALL_ARG2(fract, __FUNC_PREFIX_OCL)
137 __SYCL_MAKE_CALL_ARG2(frexp, __FUNC_PREFIX_OCL)
138 __SYCL_MAKE_CALL_ARG2(hypot, __FUNC_PREFIX_OCL)
139 __SYCL_MAKE_CALL_ARG1(ilogb, __FUNC_PREFIX_OCL)
140 __SYCL_MAKE_CALL_ARG2(ldexp, __FUNC_PREFIX_OCL)
141 __SYCL_MAKE_CALL_ARG1(lgamma, __FUNC_PREFIX_OCL)
142 __SYCL_MAKE_CALL_ARG2(lgamma_r, __FUNC_PREFIX_OCL)
143 __SYCL_MAKE_CALL_ARG1(log, __FUNC_PREFIX_OCL)
144 __SYCL_MAKE_CALL_ARG1(log2, __FUNC_PREFIX_OCL)
145 __SYCL_MAKE_CALL_ARG1(log10, __FUNC_PREFIX_OCL)
146 __SYCL_MAKE_CALL_ARG1(log1p, __FUNC_PREFIX_OCL)
147 __SYCL_MAKE_CALL_ARG1(logb, __FUNC_PREFIX_OCL)
148 __SYCL_MAKE_CALL_ARG3(mad, __FUNC_PREFIX_OCL)
149 __SYCL_MAKE_CALL_ARG2(maxmag, __FUNC_PREFIX_OCL)
150 __SYCL_MAKE_CALL_ARG2(minmag, __FUNC_PREFIX_OCL)
151 __SYCL_MAKE_CALL_ARG2(modf, __FUNC_PREFIX_OCL)
152 __SYCL_MAKE_CALL_ARG1(nan, __FUNC_PREFIX_OCL)
153 __SYCL_MAKE_CALL_ARG2(nextafter, __FUNC_PREFIX_OCL)
154 __SYCL_MAKE_CALL_ARG2(pow, __FUNC_PREFIX_OCL)
155 __SYCL_MAKE_CALL_ARG2(pown, __FUNC_PREFIX_OCL)
156 __SYCL_MAKE_CALL_ARG2(powr, __FUNC_PREFIX_OCL)
157 __SYCL_MAKE_CALL_ARG2(remainder, __FUNC_PREFIX_OCL)
158 __SYCL_MAKE_CALL_ARG3(remquo, __FUNC_PREFIX_OCL)
159 __SYCL_MAKE_CALL_ARG1(rint, __FUNC_PREFIX_OCL)
160 __SYCL_MAKE_CALL_ARG2(rootn, __FUNC_PREFIX_OCL)
161 __SYCL_MAKE_CALL_ARG1(round, __FUNC_PREFIX_OCL)
162 __SYCL_MAKE_CALL_ARG1(rsqrt, __FUNC_PREFIX_OCL)
163 __SYCL_MAKE_CALL_ARG1(sin, __FUNC_PREFIX_OCL)
164 __SYCL_MAKE_CALL_ARG2(sincos, __FUNC_PREFIX_OCL)
165 __SYCL_MAKE_CALL_ARG1(sinh, __FUNC_PREFIX_OCL)
166 __SYCL_MAKE_CALL_ARG1(sinpi, __FUNC_PREFIX_OCL)
167 __SYCL_MAKE_CALL_ARG1(sqrt, __FUNC_PREFIX_OCL)
168 __SYCL_MAKE_CALL_ARG1(tan, __FUNC_PREFIX_OCL)
169 __SYCL_MAKE_CALL_ARG1(tanh, __FUNC_PREFIX_OCL)
170 __SYCL_MAKE_CALL_ARG1(tanpi, __FUNC_PREFIX_OCL)
171 __SYCL_MAKE_CALL_ARG1(tgamma, __FUNC_PREFIX_OCL)
172 __SYCL_MAKE_CALL_ARG1(trunc, __FUNC_PREFIX_OCL)
173 __SYCL_MAKE_CALL_ARG1(native_cos, __FUNC_PREFIX_OCL)
174 __SYCL_MAKE_CALL_ARG2(native_divide, __FUNC_PREFIX_OCL)
175 __SYCL_MAKE_CALL_ARG1(native_exp, __FUNC_PREFIX_OCL)
176 __SYCL_MAKE_CALL_ARG1(native_exp2, __FUNC_PREFIX_OCL)
177 __SYCL_MAKE_CALL_ARG1(native_exp10, __FUNC_PREFIX_OCL)
178 __SYCL_MAKE_CALL_ARG1(native_log, __FUNC_PREFIX_OCL)
179 __SYCL_MAKE_CALL_ARG1(native_log2, __FUNC_PREFIX_OCL)
180 __SYCL_MAKE_CALL_ARG1(native_log10, __FUNC_PREFIX_OCL)
181 __SYCL_MAKE_CALL_ARG2(native_powr, __FUNC_PREFIX_OCL)
182 __SYCL_MAKE_CALL_ARG1(native_recip, __FUNC_PREFIX_OCL)
183 __SYCL_MAKE_CALL_ARG1(native_rsqrt, __FUNC_PREFIX_OCL)
184 __SYCL_MAKE_CALL_ARG1(native_sin, __FUNC_PREFIX_OCL)
185 __SYCL_MAKE_CALL_ARG1(native_sqrt, __FUNC_PREFIX_OCL)
186 __SYCL_MAKE_CALL_ARG1(native_tan, __FUNC_PREFIX_OCL)
187 __SYCL_MAKE_CALL_ARG1(half_cos, __FUNC_PREFIX_OCL)
188 __SYCL_MAKE_CALL_ARG2(half_divide, __FUNC_PREFIX_OCL)
189 __SYCL_MAKE_CALL_ARG1(half_exp, __FUNC_PREFIX_OCL)
190 __SYCL_MAKE_CALL_ARG1(half_exp2, __FUNC_PREFIX_OCL)
191 __SYCL_MAKE_CALL_ARG1(half_exp10, __FUNC_PREFIX_OCL)
192 __SYCL_MAKE_CALL_ARG1(half_log, __FUNC_PREFIX_OCL)
193 __SYCL_MAKE_CALL_ARG1(half_log2, __FUNC_PREFIX_OCL)
194 __SYCL_MAKE_CALL_ARG1(half_log10, __FUNC_PREFIX_OCL)
195 __SYCL_MAKE_CALL_ARG2(half_powr, __FUNC_PREFIX_OCL)
196 __SYCL_MAKE_CALL_ARG1(half_recip, __FUNC_PREFIX_OCL)
197 __SYCL_MAKE_CALL_ARG1(half_rsqrt, __FUNC_PREFIX_OCL)
198 __SYCL_MAKE_CALL_ARG1(half_sin, __FUNC_PREFIX_OCL)
199 __SYCL_MAKE_CALL_ARG1(half_sqrt, __FUNC_PREFIX_OCL)
200 __SYCL_MAKE_CALL_ARG1(half_tan, __FUNC_PREFIX_OCL)
201 /* --------------- 4.13.4 Integer functions. --------------------------------*/
202 __SYCL_MAKE_CALL_ARG1(s_abs, __FUNC_PREFIX_OCL)
203 __SYCL_MAKE_CALL_ARG1(u_abs, __FUNC_PREFIX_OCL)
204 __SYCL_MAKE_CALL_ARG2(s_abs_diff, __FUNC_PREFIX_OCL)
205 __SYCL_MAKE_CALL_ARG2(u_abs_diff, __FUNC_PREFIX_OCL)
206 __SYCL_MAKE_CALL_ARG2(s_add_sat, __FUNC_PREFIX_OCL)
207 __SYCL_MAKE_CALL_ARG2(u_add_sat, __FUNC_PREFIX_OCL)
208 __SYCL_MAKE_CALL_ARG2(s_hadd, __FUNC_PREFIX_OCL)
209 __SYCL_MAKE_CALL_ARG2(u_hadd, __FUNC_PREFIX_OCL)
210 __SYCL_MAKE_CALL_ARG2(s_rhadd, __FUNC_PREFIX_OCL)
211 __SYCL_MAKE_CALL_ARG2(u_rhadd, __FUNC_PREFIX_OCL)
212 __SYCL_MAKE_CALL_ARG3(s_clamp, __FUNC_PREFIX_OCL)
213 __SYCL_MAKE_CALL_ARG3(u_clamp, __FUNC_PREFIX_OCL)
214 __SYCL_MAKE_CALL_ARG1(clz, __FUNC_PREFIX_OCL)
215 __SYCL_MAKE_CALL_ARG1(ctz, __FUNC_PREFIX_OCL)
216 __SYCL_MAKE_CALL_ARG3(s_mad_hi, __FUNC_PREFIX_OCL)
217 __SYCL_MAKE_CALL_ARG3(u_mad_hi, __FUNC_PREFIX_OCL)
218 __SYCL_MAKE_CALL_ARG3(u_mad_sat, __FUNC_PREFIX_OCL)
219 __SYCL_MAKE_CALL_ARG3(s_mad_sat, __FUNC_PREFIX_OCL)
220 __SYCL_MAKE_CALL_ARG2(s_max, __FUNC_PREFIX_OCL)
221 __SYCL_MAKE_CALL_ARG2(u_max, __FUNC_PREFIX_OCL)
222 __SYCL_MAKE_CALL_ARG2(s_min, __FUNC_PREFIX_OCL)
223 __SYCL_MAKE_CALL_ARG2(u_min, __FUNC_PREFIX_OCL)
224 __SYCL_MAKE_CALL_ARG2(s_mul_hi, __FUNC_PREFIX_OCL)
225 __SYCL_MAKE_CALL_ARG2(u_mul_hi, __FUNC_PREFIX_OCL)
226 __SYCL_MAKE_CALL_ARG2(rotate, __FUNC_PREFIX_OCL)
227 __SYCL_MAKE_CALL_ARG2(s_sub_sat, __FUNC_PREFIX_OCL)
228 __SYCL_MAKE_CALL_ARG2(u_sub_sat, __FUNC_PREFIX_OCL)
229 __SYCL_MAKE_CALL_ARG2(u_upsample, __FUNC_PREFIX_OCL)
230 __SYCL_MAKE_CALL_ARG2(s_upsample, __FUNC_PREFIX_OCL)
231 __SYCL_MAKE_CALL_ARG1(popcount, __FUNC_PREFIX_OCL)
232 __SYCL_MAKE_CALL_ARG3(s_mad24, __FUNC_PREFIX_OCL)
233 __SYCL_MAKE_CALL_ARG3(u_mad24, __FUNC_PREFIX_OCL)
234 __SYCL_MAKE_CALL_ARG2(s_mul24, __FUNC_PREFIX_OCL)
235 __SYCL_MAKE_CALL_ARG2(u_mul24, __FUNC_PREFIX_OCL)
236 /* --------------- 4.13.5 Common functions. ---------------------------------*/
237 __SYCL_MAKE_CALL_ARG3(fclamp, __FUNC_PREFIX_OCL)
238 __SYCL_MAKE_CALL_ARG1(degrees, __FUNC_PREFIX_OCL)
239 __SYCL_MAKE_CALL_ARG2(fmax_common, __FUNC_PREFIX_OCL)
240 __SYCL_MAKE_CALL_ARG2(fmin_common, __FUNC_PREFIX_OCL)
241 __SYCL_MAKE_CALL_ARG3(mix, __FUNC_PREFIX_OCL)
242 __SYCL_MAKE_CALL_ARG1(radians, __FUNC_PREFIX_OCL)
243 __SYCL_MAKE_CALL_ARG2(step, __FUNC_PREFIX_OCL)
244 __SYCL_MAKE_CALL_ARG3(smoothstep, __FUNC_PREFIX_OCL)
245 __SYCL_MAKE_CALL_ARG1(sign, __FUNC_PREFIX_OCL)
246 /* --------------- 4.13.6 Geometric Functions. ------------------------------*/
247 __SYCL_MAKE_CALL_ARG2(cross, __FUNC_PREFIX_OCL)
248 __SYCL_MAKE_CALL_ARG2_SAME(Dot, __FUNC_PREFIX_CORE) // dot
249 __SYCL_MAKE_CALL_ARG2_SAME_RESULT(FMul, __FUNC_PREFIX_CORE) // dot
250 __SYCL_MAKE_CALL_ARG2(distance, __FUNC_PREFIX_OCL)
251 __SYCL_MAKE_CALL_ARG1(length, __FUNC_PREFIX_OCL)
252 __SYCL_MAKE_CALL_ARG1(normalize, __FUNC_PREFIX_OCL)
253 __SYCL_MAKE_CALL_ARG2(fast_distance, __FUNC_PREFIX_OCL)
254 __SYCL_MAKE_CALL_ARG1(fast_length, __FUNC_PREFIX_OCL)
255 __SYCL_MAKE_CALL_ARG1(fast_normalize, __FUNC_PREFIX_OCL)
256 /* --------------- 4.13.7 Relational functions. -----------------------------*/
257 __SYCL_MAKE_CALL_ARG2_SAME(FOrdEqual, __FUNC_PREFIX_CORE) // isequal
258 __SYCL_MAKE_CALL_ARG2_SAME(FUnordNotEqual, __FUNC_PREFIX_CORE) // isnotequal
259 __SYCL_MAKE_CALL_ARG2_SAME(FOrdGreaterThan, __FUNC_PREFIX_CORE) // isgreater
260 __SYCL_MAKE_CALL_ARG2_SAME(FOrdGreaterThanEqual,
261  __FUNC_PREFIX_CORE) // isgreaterequal
262 __SYCL_MAKE_CALL_ARG2_SAME(FOrdLessThan, __FUNC_PREFIX_CORE) // isless
263 __SYCL_MAKE_CALL_ARG2_SAME(FOrdLessThanEqual, __FUNC_PREFIX_CORE) // islessequal
264 __SYCL_MAKE_CALL_ARG2_SAME(FOrdNotEqual, __FUNC_PREFIX_CORE) // islessgreater
265 __SYCL_MAKE_CALL_ARG2_SAME(LessOrGreater, __FUNC_PREFIX_CORE) // islessgreater
266 __SYCL_MAKE_CALL_ARG1(IsFinite, __FUNC_PREFIX_CORE) // isfinite
267 __SYCL_MAKE_CALL_ARG1(IsInf, __FUNC_PREFIX_CORE) // isinf
268 __SYCL_MAKE_CALL_ARG1(IsNan, __FUNC_PREFIX_CORE) // isnan
269 __SYCL_MAKE_CALL_ARG1(IsNormal, __FUNC_PREFIX_CORE) // isnormal
270 __SYCL_MAKE_CALL_ARG2_SAME(Ordered, __FUNC_PREFIX_CORE) // isordered
271 __SYCL_MAKE_CALL_ARG2_SAME(Unordered, __FUNC_PREFIX_CORE) // isunordered
272 __SYCL_MAKE_CALL_ARG1(SignBitSet, __FUNC_PREFIX_CORE) // signbit
273 __SYCL_MAKE_CALL_ARG1(Any, __FUNC_PREFIX_CORE) // any
274 __SYCL_MAKE_CALL_ARG1(All, __FUNC_PREFIX_CORE) // all
275 __SYCL_MAKE_CALL_ARG3(bitselect, __FUNC_PREFIX_OCL)
276 __SYCL_MAKE_CALL_ARG3(select, __FUNC_PREFIX_OCL) // select
277 #ifndef __SYCL_DEVICE_ONLY__
278 } // namespace __host_std
279 #endif
280 
281 #undef __NOEXC
282 #undef __SYCL_MAKE_CALL_ARG1
283 #undef __SYCL_MAKE_CALL_ARG2
284 #undef __SYCL_MAKE_CALL_ARG2_SAME
285 #undef __SYCL_MAKE_CALL_ARG2_SAME_RESULT
286 #undef __SYCL_MAKE_CALL_ARG3
287 #undef __SYCL_PPCAT_NX
288 #undef __SYCL_PPCAT
289 #undef __FUNC_PREFIX_OCL
290 #undef __FUNC_PREFIX_CORE
291 #undef __SYCL_EXTERN_IT1
292 #undef __SYCL_EXTERN_IT2
293 #undef __SYCL_EXTERN_IT2_SAME
294 #undef __SYCL_EXTERN_IT3
__SYCL_MAKE_CALL_ARG3
#define __SYCL_MAKE_CALL_ARG3(call, prefix)
Definition: builtins.hpp:87
__SYCL_MAKE_CALL_ARG2
#define __SYCL_MAKE_CALL_ARG2(call, prefix)
Definition: builtins.hpp:51
sycl::_V1::ext::oneapi::fabs
std::enable_if_t< detail::is_bf16_storage_type< T >::value, T > fabs(T x)
Definition: bf16_storage_builtins.hpp:47
sycl::_V1::ext::intel::experimental::esimd::acos
__ESIMD_API std::enable_if_t< std::is_floating_point< T >::value, sycl::ext::intel::esimd::simd< T, SZ > > acos(sycl::ext::intel::esimd::simd< T, SZ > src0)
Definition: math.hpp:1298
__FUNC_PREFIX_CORE
#define __FUNC_PREFIX_CORE
Definition: builtins.hpp:26
sycl::_V1::ext::intel::experimental::esimd::atan2
sycl::ext::intel::esimd::simd< float, N > atan2(sycl::ext::intel::esimd::simd< float, N > y, sycl::ext::intel::esimd::simd< float, N > x)
Definition: math.hpp:1446
__host_std
Definition: builtins.hpp:103
sycl::_V1::ext::oneapi::experimental::native::tanh
__SYCL_ALWAYS_INLINE std::enable_if_t< std::is_same_v< T, half >||std::is_same_v< T, float >, sycl::marray< T, N > > tanh(sycl::marray< T, N > x) __NOEXC
Definition: builtins.hpp:117
sycl::_V1::cos
ESIMD_NODEBUG ESIMD_INLINE sycl::ext::intel::esimd::simd< float, SZ > cos(sycl::ext::intel::esimd::simd< float, SZ > x) __NOEXC
Definition: builtins_esimd.hpp:27
sycl::_V1::exp
ESIMD_NODEBUG ESIMD_INLINE sycl::ext::intel::esimd::simd< float, SZ > exp(sycl::ext::intel::esimd::simd< float, SZ > x) __NOEXC
Definition: builtins_esimd.hpp:49
__host_std::__SYCL_MAKE_CALL_ARG2_SAME
__SYCL_MAKE_CALL_ARG2_SAME(Dot, __FUNC_PREFIX_CORE) __SYCL_MAKE_CALL_ARG2_SAME_RESULT(FMul
sycl::_V1::ext::intel::experimental::esimd::asin
__ESIMD_API std::enable_if_t< std::is_floating_point< T >::value, sycl::ext::intel::esimd::simd< T, SZ > > asin(sycl::ext::intel::esimd::simd< T, SZ > src0)
Definition: math.hpp:1336
sycl::_V1::ext::intel::esimd::sqrt
__ESIMD_API simd< T, N > sqrt(simd< T, N > src, Sat sat={})
Square root.
Definition: math.hpp:389
sycl::_V1::sin
ESIMD_NODEBUG ESIMD_INLINE sycl::ext::intel::esimd::simd< float, SZ > sin(sycl::ext::intel::esimd::simd< float, SZ > x) __NOEXC
Definition: builtins_esimd.hpp:38
sycl::_V1::ext::intel::experimental::esimd::atan
ESIMD_DETAIL __ESIMD_API sycl::ext::intel::esimd::simd< T, SZ > atan(sycl::ext::intel::esimd::simd< T, SZ > src0)
Definition: math.hpp:1254
defines_elementary.hpp
sycl::_V1::ext::intel::experimental::esimd::sincos
__ESIMD_API sycl::ext::intel::esimd::simd< float, SZ > sincos(sycl::ext::intel::esimd::simd< float, SZ > &dstcos, U src0, Sat sat={})
Definition: math.hpp:1240
generic_type_traits.hpp
sycl::_V1::ext::intel::esimd::rsqrt
__ESIMD_API simd< T, N > rsqrt(simd< T, N > src, Sat sat={})
Square root reciprocal - calculates 1/sqrt(x).
Definition: math.hpp:397
sycl::_V1::ext::intel::esimd::ceil
ESIMD_INLINE sycl::ext::intel::esimd::simd< RT, SZ > ceil(const sycl::ext::intel::esimd::simd< float, SZ > src0, Sat sat={})
"Ceiling" operation, vector version - alias of rndu.
Definition: math.hpp:594
popcount
int popcount(const simd_mask< _Tp, _Abi > &) noexcept
sycl::_V1::ext::intel::experimental::esimd::fmod
sycl::ext::intel::esimd::simd< float, N > fmod(sycl::ext::intel::esimd::simd< float, N > y, sycl::ext::intel::esimd::simd< float, N > x)
Definition: math.hpp:1479
sycl::_V1::ext::intel::esimd::log2
__ESIMD_API simd< T, N > log2(simd< T, N > src, Sat sat={})
Logarithm base 2.
Definition: math.hpp:381
__SYCL_MAKE_CALL_ARG2_SAME_RESULT
#define __SYCL_MAKE_CALL_ARG2_SAME_RESULT(call, prefix)
Definition: builtins.hpp:76
sycl::_V1::ext::intel::math::copysign
std::enable_if_t< std::is_same_v< Tp, float >, float > copysign(Tp x, Tp y)
Definition: math.hpp:71
sycl::_V1::ext::oneapi::experimental::native::exp2
__SYCL_ALWAYS_INLINE sycl::marray< half, N > exp2(sycl::marray< half, N > x) __NOEXC
Definition: builtins.hpp:160
sycl::_V1::log
ESIMD_NODEBUG ESIMD_INLINE sycl::ext::intel::esimd::simd< float, SZ > log(sycl::ext::intel::esimd::simd< float, SZ > x) __NOEXC
Definition: builtins_esimd.hpp:60
sycl::_V1::ext::intel::math::rint
std::enable_if_t< std::is_same_v< Tp, float >, float > rint(Tp x)
Definition: math.hpp:152
sycl::_V1::ext::intel::esimd::pow
__ESIMD_API simd< T, N > pow(simd< T, N > src0, simd< U, N > src1, Sat sat={})
Power - calculates src0 in power of src1.
Definition: math.hpp:442
__FUNC_PREFIX_OCL
#define __FUNC_PREFIX_OCL
Definition: builtins.hpp:25
syclcompat::fast_length
float fast_length(const float *a, int len)
Compute fast_length for variable-length array.
Definition: util.hpp:126
sycl::_V1::detail::Ordered
@ Ordered
Definition: queue_impl.hpp:68
sycl::_V1::ext::intel::esimd::floor
ESIMD_INLINE sycl::ext::intel::esimd::simd< RT, SZ > floor(const sycl::ext::intel::esimd::simd< float, SZ > src0, Sat sat={})
"Floor" operation, vector version - alias of rndd.
Definition: math.hpp:581
sycl::_V1::ext::intel::esimd::trunc
__ESIMD_API sycl::ext::intel::esimd::simd< RT, SZ > trunc(const sycl::ext::intel::esimd::simd< float, SZ > &src0, Sat sat={})
Round to integral value using the round to zero rounding mode (vector version).
Definition: math.hpp:614
__host_std::__SYCL_MAKE_CALL_ARG1
__FUNC_PREFIX_CORE __FUNC_PREFIX_CORE __FUNC_PREFIX_CORE __FUNC_PREFIX_CORE __FUNC_PREFIX_CORE __SYCL_MAKE_CALL_ARG1(IsFinite, __FUNC_PREFIX_CORE) __SYCL_MAKE_CALL_ARG1(IsInf