10 #ifndef __CLANG_HIP_LIBDEVICE_DECLARES_H__
11 #define __CLANG_HIP_LIBDEVICE_DECLARES_H__
18 __device__
__attribute__((const))
float __ocml_asin_f32(
float);
19 __device__
__attribute__((pure))
float __ocml_asinh_f32(
float);
21 __device__
__attribute__((const))
float __ocml_atan_f32(
float);
22 __device__
__attribute__((pure))
float __ocml_atanh_f32(
float);
23 __device__
__attribute__((pure))
float __ocml_cbrt_f32(
float);
24 __device__
__attribute__((const))
float __ocml_ceil_f32(
float);
25 __device__
__attribute__((const)) __device__
float __ocml_copysign_f32(
float,
29 __device__
__attribute__((pure)) __device__
float __ocml_cosh_f32(
float);
33 __device__
__attribute__((pure))
float __ocml_erfc_f32(
float);
34 __device__
__attribute__((pure))
float __ocml_erfcinv_f32(
float);
35 __device__
__attribute__((pure))
float __ocml_erfcx_f32(
float);
37 __device__
__attribute__((pure))
float __ocml_erfinv_f32(
float);
38 __device__
__attribute__((pure))
float __ocml_exp10_f32(
float);
39 __device__
__attribute__((pure))
float __ocml_native_exp10_f32(
float);
40 __device__
__attribute__((pure))
float __ocml_exp2_f32(
float);
42 __device__
__attribute__((pure))
float __ocml_native_exp_f32(
float);
43 __device__
__attribute__((pure))
float __ocml_expm1_f32(
float);
44 __device__
__attribute__((const))
float __ocml_fabs_f32(
float);
45 __device__
__attribute__((const))
float __ocml_fdim_f32(
float,
float);
46 __device__
__attribute__((const))
float __ocml_floor_f32(
float);
47 __device__
__attribute__((const))
float __ocml_fma_f32(
float,
float,
float);
48 __device__
__attribute__((const))
float __ocml_fmax_f32(
float,
float);
49 __device__
__attribute__((const))
float __ocml_fmin_f32(
float,
float);
50 __device__
__attribute__((const)) __device__
float __ocml_fmod_f32(
float,
54 __device__
__attribute__((const))
float __ocml_hypot_f32(
float,
float);
55 __device__
__attribute__((const))
int __ocml_ilogb_f32(
float);
56 __device__
__attribute__((const))
int __ocml_isfinite_f32(
float);
57 __device__
__attribute__((const))
int __ocml_isinf_f32(
float);
58 __device__
__attribute__((const))
int __ocml_isnan_f32(
float);
63 __device__
__attribute__((pure))
float __ocml_log10_f32(
float);
64 __device__
__attribute__((pure))
float __ocml_native_log10_f32(
float);
65 __device__
__attribute__((pure))
float __ocml_log1p_f32(
float);
66 __device__
__attribute__((pure))
float __ocml_log2_f32(
float);
67 __device__
__attribute__((pure))
float __ocml_native_log2_f32(
float);
68 __device__
__attribute__((const))
float __ocml_logb_f32(
float);
70 __device__
__attribute__((pure))
float __ocml_native_log_f32(
float);
73 __device__
__attribute__((const))
float __ocml_nearbyint_f32(
float);
74 __device__
__attribute__((const))
float __ocml_nextafter_f32(
float,
float);
75 __device__
__attribute__((const))
float __ocml_len3_f32(
float,
float,
float);
76 __device__
__attribute__((const))
float __ocml_len4_f32(
float,
float,
float,
78 __device__
__attribute__((pure))
float __ocml_ncdf_f32(
float);
79 __device__
__attribute__((pure))
float __ocml_ncdfinv_f32(
float);
80 __device__
__attribute__((pure))
float __ocml_pow_f32(
float,
float);
81 __device__
__attribute__((pure))
float __ocml_rcbrt_f32(
float);
82 __device__
__attribute__((const))
float __ocml_remainder_f32(
float,
float);
85 __device__
__attribute__((const))
float __ocml_rhypot_f32(
float,
float);
86 __device__
__attribute__((const))
float __ocml_rint_f32(
float);
87 __device__
__attribute__((const))
float __ocml_rlen3_f32(
float,
float,
float);
88 __device__
__attribute__((const))
float __ocml_rlen4_f32(
float,
float,
float,
90 __device__
__attribute__((const))
float __ocml_round_f32(
float);
91 __device__
__attribute__((pure))
float __ocml_rsqrt_f32(
float);
92 __device__
__attribute__((const))
float __ocml_scalb_f32(
float,
float);
93 __device__
__attribute__((const))
float __ocml_scalbn_f32(
float,
int);
94 __device__
__attribute__((const))
int __ocml_signbit_f32(
float);
101 __device__
__attribute__((pure))
float __ocml_sinh_f32(
float);
103 __device__
__attribute__((const))
float __ocml_sqrt_f32(
float);
104 __device__
__attribute__((const))
float __ocml_native_sqrt_f32(
float);
106 __device__
__attribute__((pure))
float __ocml_tanh_f32(
float);
108 __device__
__attribute__((const))
float __ocml_trunc_f32(
float);
113 __device__
__attribute__((const))
float __ocml_add_rte_f32(
float,
float);
114 __device__
__attribute__((const))
float __ocml_add_rtn_f32(
float,
float);
115 __device__
__attribute__((const))
float __ocml_add_rtp_f32(
float,
float);
116 __device__
__attribute__((const))
float __ocml_add_rtz_f32(
float,
float);
117 __device__
__attribute__((const))
float __ocml_sub_rte_f32(
float,
float);
118 __device__
__attribute__((const))
float __ocml_sub_rtn_f32(
float,
float);
119 __device__
__attribute__((const))
float __ocml_sub_rtp_f32(
float,
float);
120 __device__
__attribute__((const))
float __ocml_sub_rtz_f32(
float,
float);
121 __device__
__attribute__((const))
float __ocml_mul_rte_f32(
float,
float);
122 __device__
__attribute__((const))
float __ocml_mul_rtn_f32(
float,
float);
123 __device__
__attribute__((const))
float __ocml_mul_rtp_f32(
float,
float);
124 __device__
__attribute__((const))
float __ocml_mul_rtz_f32(
float,
float);
125 __device__
__attribute__((const))
float __ocml_div_rte_f32(
float,
float);
126 __device__
__attribute__((const))
float __ocml_div_rtn_f32(
float,
float);
127 __device__
__attribute__((const))
float __ocml_div_rtp_f32(
float,
float);
128 __device__
__attribute__((const))
float __ocml_div_rtz_f32(
float,
float);
129 __device__
__attribute__((const))
float __ocml_sqrt_rte_f32(
float,
float);
130 __device__
__attribute__((const))
float __ocml_sqrt_rtn_f32(
float,
float);
131 __device__
__attribute__((const))
float __ocml_sqrt_rtp_f32(
float,
float);
132 __device__
__attribute__((const))
float __ocml_sqrt_rtz_f32(
float,
float);
133 __device__
__attribute__((const))
float __ocml_fma_rte_f32(
float,
float,
float);
134 __device__
__attribute__((const))
float __ocml_fma_rtn_f32(
float,
float,
float);
135 __device__
__attribute__((const))
float __ocml_fma_rtp_f32(
float,
float,
float);
136 __device__
__attribute__((const))
float __ocml_fma_rtz_f32(
float,
float,
float);
139 __llvm_amdgcn_cos_f32(
float) __asm("llvm.amdgcn.
cos.f32");
141 __llvm_amdgcn_rcp_f32(
float) __asm("llvm.amdgcn.rcp.f32");
143 __llvm_amdgcn_rsq_f32(
float) __asm("llvm.amdgcn.rsq.f32");
145 __llvm_amdgcn_sin_f32(
float) __asm("llvm.amdgcn.
sin.f32");
150 __device__
__attribute__((const))
double __ocml_acos_f64(
double);
151 __device__
__attribute__((pure))
double __ocml_acosh_f64(
double);
152 __device__
__attribute__((const))
double __ocml_asin_f64(
double);
153 __device__
__attribute__((pure))
double __ocml_asinh_f64(
double);
155 __device__
__attribute__((const))
double __ocml_atan_f64(
double);
156 __device__
__attribute__((pure))
double __ocml_atanh_f64(
double);
157 __device__
__attribute__((pure))
double __ocml_cbrt_f64(
double);
158 __device__
__attribute__((const))
double __ocml_ceil_f64(
double);
159 __device__
__attribute__((const))
double __ocml_copysign_f64(
double,
double);
161 __device__
__attribute__((pure))
double __ocml_cosh_f64(
double);
165 __device__
__attribute__((pure))
double __ocml_erfc_f64(
double);
166 __device__
__attribute__((pure))
double __ocml_erfcinv_f64(
double);
167 __device__
__attribute__((pure))
double __ocml_erfcx_f64(
double);
168 __device__
__attribute__((pure))
double __ocml_erf_f64(
double);
169 __device__
__attribute__((pure))
double __ocml_erfinv_f64(
double);
170 __device__
__attribute__((pure))
double __ocml_exp10_f64(
double);
171 __device__
__attribute__((pure))
double __ocml_exp2_f64(
double);
172 __device__
__attribute__((pure))
double __ocml_exp_f64(
double);
173 __device__
__attribute__((pure))
double __ocml_expm1_f64(
double);
174 __device__
__attribute__((const))
double __ocml_fabs_f64(
double);
175 __device__
__attribute__((const))
double __ocml_fdim_f64(
double,
double);
176 __device__
__attribute__((const))
double __ocml_floor_f64(
double);
177 __device__
__attribute__((const))
double __ocml_fma_f64(
double,
double,
double);
178 __device__
__attribute__((const))
double __ocml_fmax_f64(
double,
double);
179 __device__
__attribute__((const))
double __ocml_fmin_f64(
double,
double);
180 __device__
__attribute__((const))
double __ocml_fmod_f64(
double,
double);
183 __device__
__attribute__((const))
double __ocml_hypot_f64(
double,
double);
184 __device__
__attribute__((const))
int __ocml_ilogb_f64(
double);
185 __device__
__attribute__((const))
int __ocml_isfinite_f64(
double);
186 __device__
__attribute__((const))
int __ocml_isinf_f64(
double);
187 __device__
__attribute__((const))
int __ocml_isnan_f64(
double);
190 __device__
__attribute__((const))
double __ocml_ldexp_f64(
double,
int);
192 __device__
__attribute__((pure))
double __ocml_log10_f64(
double);
193 __device__
__attribute__((pure))
double __ocml_log1p_f64(
double);
194 __device__
__attribute__((pure))
double __ocml_log2_f64(
double);
195 __device__
__attribute__((const))
double __ocml_logb_f64(
double);
196 __device__
__attribute__((pure))
double __ocml_log_f64(
double);
199 __device__
__attribute__((const))
double __ocml_nearbyint_f64(
double);
200 __device__
__attribute__((const))
double __ocml_nextafter_f64(
double,
double);
201 __device__
__attribute__((const))
double __ocml_len3_f64(
double,
double,
203 __device__
__attribute__((const))
double __ocml_len4_f64(
double,
double,
double,
205 __device__
__attribute__((pure))
double __ocml_ncdf_f64(
double);
206 __device__
__attribute__((pure))
double __ocml_ncdfinv_f64(
double);
207 __device__
__attribute__((pure))
double __ocml_pow_f64(
double,
double);
208 __device__
__attribute__((pure))
double __ocml_rcbrt_f64(
double);
209 __device__
__attribute__((const))
double __ocml_remainder_f64(
double,
double);
212 __device__
__attribute__((const))
double __ocml_rhypot_f64(
double,
double);
213 __device__
__attribute__((const))
double __ocml_rint_f64(
double);
214 __device__
__attribute__((const))
double __ocml_rlen3_f64(
double,
double,
216 __device__
__attribute__((const))
double __ocml_rlen4_f64(
double,
double,
218 __device__
__attribute__((const))
double __ocml_round_f64(
double);
219 __device__
__attribute__((pure))
double __ocml_rsqrt_f64(
double);
220 __device__
__attribute__((const))
double __ocml_scalb_f64(
double,
double);
221 __device__
__attribute__((const))
double __ocml_scalbn_f64(
double,
int);
222 __device__
__attribute__((const))
int __ocml_signbit_f64(
double);
228 __device__
__attribute__((pure))
double __ocml_sinh_f64(
double);
230 __device__
__attribute__((const))
double __ocml_sqrt_f64(
double);
232 __device__
__attribute__((pure))
double __ocml_tanh_f64(
double);
234 __device__
__attribute__((const))
double __ocml_trunc_f64(
double);
239 __device__
__attribute__((const))
double __ocml_add_rte_f64(
double,
double);
240 __device__
__attribute__((const))
double __ocml_add_rtn_f64(
double,
double);
241 __device__
__attribute__((const))
double __ocml_add_rtp_f64(
double,
double);
242 __device__
__attribute__((const))
double __ocml_add_rtz_f64(
double,
double);
243 __device__
__attribute__((const))
double __ocml_sub_rte_f64(
double,
double);
244 __device__
__attribute__((const))
double __ocml_sub_rtn_f64(
double,
double);
245 __device__
__attribute__((const))
double __ocml_sub_rtp_f64(
double,
double);
246 __device__
__attribute__((const))
double __ocml_sub_rtz_f64(
double,
double);
247 __device__
__attribute__((const))
double __ocml_mul_rte_f64(
double,
double);
248 __device__
__attribute__((const))
double __ocml_mul_rtn_f64(
double,
double);
249 __device__
__attribute__((const))
double __ocml_mul_rtp_f64(
double,
double);
250 __device__
__attribute__((const))
double __ocml_mul_rtz_f64(
double,
double);
251 __device__
__attribute__((const))
double __ocml_div_rte_f64(
double,
double);
252 __device__
__attribute__((const))
double __ocml_div_rtn_f64(
double,
double);
253 __device__
__attribute__((const))
double __ocml_div_rtp_f64(
double,
double);
254 __device__
__attribute__((const))
double __ocml_div_rtz_f64(
double,
double);
255 __device__
__attribute__((const))
double __ocml_sqrt_rte_f64(
double,
double);
256 __device__
__attribute__((const))
double __ocml_sqrt_rtn_f64(
double,
double);
257 __device__
__attribute__((const))
double __ocml_sqrt_rtp_f64(
double,
double);
258 __device__
__attribute__((const))
double __ocml_sqrt_rtz_f64(
double,
double);
259 __device__
__attribute__((const))
double __ocml_fma_rte_f64(
double,
double,
261 __device__
__attribute__((const))
double __ocml_fma_rtn_f64(
double,
double,
263 __device__
__attribute__((const))
double __ocml_fma_rtp_f64(
double,
double,
265 __device__
__attribute__((const))
double __ocml_fma_rtz_f64(
double,
double,
269 __llvm_amdgcn_rcp_f64(
double) __asm("llvm.amdgcn.rcp.f64");
271 __llvm_amdgcn_rsq_f64(
double) __asm("llvm.amdgcn.rsq.f64");
316 return __2f16{__llvm_amdgcn_rcp_f16(
__x.x), __llvm_amdgcn_rcp_f16(
__x.y)};
__device__ double __ocml_i0_f64(double)
__device__ float __ocml_j1_f32(float)
__device__ double __ocml_remquo_f64(double, double, __attribute__((address_space(5))) int *)
__device__ double __ocml_modf_f64(double, __attribute__((address_space(5))) double *)
__device__ float __ocml_cospi_f32(float)
__device__ float __ocml_i0_f32(float)
__device__ double __ocml_lgamma_f64(double)
__device__ float __ocml_sincos_f32(float, __attribute__((address_space(5))) float *)
__device__ float __ocml_remquo_f32(float, float, __attribute__((address_space(5))) int *)
_Float16 __2f16 __attribute__((ext_vector_type(2)))
Zeroes the upper 128 bits (bits 255:128) of all YMM registers.
__device__ _Float16 __ocml_sin_f16(_Float16)
__device__ float __ocml_y0_f32(float)
__device__ float __ocml_modf_f32(float, __attribute__((address_space(5))) float *)
__device__ float __ocml_i1_f32(float)
__device__ __2f16 __ocml_cos_2f16(__2f16)
__device__ float __ocml_lgamma_f32(float)
__device__ float __ocml_frexp_f32(float, __attribute__((address_space(5))) int *)
__device__ double __ocml_sinpi_f64(double)
__device__ double __ocml_cospi_f64(double)
__device__ __2f16 __ocml_sin_2f16(__2f16)
__device__ double __ocml_frexp_f64(double, __attribute__((address_space(5))) int *)
__device__ double __ocml_tgamma_f64(double)
__device__ float __ocml_tan_f32(float)
__device__ float __ocml_tgamma_f32(float)
__device__ double __ocml_sincos_f64(double, __attribute__((address_space(5))) double *)
__device__ float __ocml_sinpi_f32(float)
__device__ double __ocml_j1_f64(double)
__device__ double __ocml_y1_f64(double)
__device__ double __ocml_j0_f64(double)
__device__ float __ocml_cos_f32(float)
__device__ float __ocml_y1_f32(float)
__device__ _Float16 __ocml_cos_f16(_Float16)
__device__ float __ocml_j0_f32(float)
__device__ double __ocml_cos_f64(double)
__device__ double __ocml_i1_f64(double)
__device__ double __ocml_sin_f64(double)
__device__ __2f16 float c
__device__ double __ocml_sincospi_f64(double, __attribute__((address_space(5))) double *)
__device__ float __ocml_sin_f32(float)
__device__ float __ocml_sincospi_f32(float, __attribute__((address_space(5))) float *)
__device__ __2f16 __llvm_amdgcn_rcp_2f16(__2f16 __x)
__device__ float __ocml_native_sin_f32(float)
__device__ float __ocml_native_cos_f32(float)
__device__ __2f16 float bool s
__device__ double __ocml_y0_f64(double)
__device__ double __ocml_tan_f64(double)
static __inline unsigned char unsigned int __x