14#if defined(__opencl_c_images)
15#ifndef cl_khr_depth_images
16#define cl_khr_depth_images
20#if __OPENCL_C_VERSION__ < CL_VERSION_2_0
21#ifdef cl_khr_3d_image_writes
22#pragma OPENCL EXTENSION cl_khr_3d_image_writes : enable
26#if (defined(__OPENCL_CPP_VERSION__) || \
27 (__OPENCL_C_VERSION__ >= CL_VERSION_1_2)) && \
28 (defined(__SPIR__) || defined(__SPIRV__))
29#pragma OPENCL EXTENSION cl_intel_planar_yuv : begin
30#pragma OPENCL EXTENSION cl_intel_planar_yuv : end
35#define __ovld __attribute__((overloadable))
36#define __conv __attribute__((convergent))
39#define __purefn __attribute__((pure))
40#define __cnfn __attribute__((const))
4640#pragma OPENCL EXTENSION cl_khr_fp64 : enable
5463#pragma OPENCL EXTENSION cl_khr_fp16 : enable
6430#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
7265#if defined(__opencl_c_generic_address_space)
7290#if defined(__opencl_c_named_address_space_builtins)
7315double16
__ovld fract(double16, __global double16 *);
7321double16
__ovld fract(double16, __local double16 *);
7323double2
__ovld fract(double2, __private double2 *);
7324double3
__ovld fract(double3, __private double3 *);
7325double4
__ovld fract(double4, __private double4 *);
7326double8
__ovld fract(double8, __private double8 *);
7327double16
__ovld fract(double16, __private double16 *);
7357#if defined(__opencl_c_generic_address_space)
7382#if defined(__opencl_c_named_address_space_builtins)
7419double16
__ovld frexp(double16, __private int16 *);
7566#if defined(__opencl_c_generic_address_space)
7591#if defined(__opencl_c_named_address_space_builtins)
7874#if defined(__opencl_c_generic_address_space)
7899#if defined(__opencl_c_named_address_space_builtins)
7919double __ovld modf(
double, __global
double *);
7920double2
__ovld modf(double2, __global double2 *);
7921double3
__ovld modf(double3, __global double3 *);
7922double4
__ovld modf(double4, __global double4 *);
7923double8
__ovld modf(double8, __global double8 *);
7924double16
__ovld modf(double16, __global double16 *);
7926double2
__ovld modf(double2, __local double2 *);
7927double3
__ovld modf(double3, __local double3 *);
7928double4
__ovld modf(double4, __local double4 *);
7929double8
__ovld modf(double8, __local double8 *);
7930double16
__ovld modf(double16, __local double16 *);
7931double __ovld modf(
double, __private
double *);
7932double2
__ovld modf(double2, __private double2 *);
7933double3
__ovld modf(double3, __private double3 *);
7934double4
__ovld modf(double4, __private double4 *);
7935double8
__ovld modf(double8, __private double8 *);
7936double16
__ovld modf(double16, __private double16 *);
7944half16
__ovld modf(half16, __global half16 *);
7956half16
__ovld modf(half16, __private half16 *);
8136#if defined(__opencl_c_generic_address_space)
8161#if defined(__opencl_c_named_address_space_builtins)
8182double2
__ovld remquo(double2, double2, __global int2 *);
8183double3
__ovld remquo(double3, double3, __global int3 *);
8184double4
__ovld remquo(double4, double4, __global int4 *);
8185double8
__ovld remquo(double8, double8, __global int8 *);
8186double16
__ovld remquo(double16, double16, __global int16 *);
8188double2
__ovld remquo(double2, double2, __local int2 *);
8189double3
__ovld remquo(double3, double3, __local int3 *);
8190double4
__ovld remquo(double4, double4, __local int4 *);
8191double8
__ovld remquo(double8, double8, __local int8 *);
8192double16
__ovld remquo(double16, double16, __local int16 *);
8194double2
__ovld remquo(double2, double2, __private int2 *);
8195double3
__ovld remquo(double3, double3, __private int3 *);
8196double4
__ovld remquo(double4, double4, __private int4 *);
8197double8
__ovld remquo(double8, double8, __private int8 *);
8198double16
__ovld remquo(double16, double16, __private int16 *);
8218half16
__ovld remquo(half16, half16, __private int16 *);
8361#if defined(__opencl_c_generic_address_space)
8386#if defined(__opencl_c_named_address_space_builtins)
9370#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
9924#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_1_2)
11247#if defined(__opencl_c_generic_address_space)
11311#if defined(__opencl_c_named_address_space_builtins)
11485#if defined(__opencl_c_generic_address_space)
11547#if defined(__opencl_c_named_address_space_builtins)
11728#if defined(__opencl_c_generic_address_space)
11732#if defined(__opencl_c_named_address_space_builtins)
11751#if defined(__opencl_c_generic_address_space)
11759#if defined(__opencl_c_named_address_space_builtins)
11788#if defined(__opencl_c_generic_address_space)
11803#if defined(__opencl_c_named_address_space_builtins)
11849#if defined(__opencl_c_generic_address_space)
11904#if defined(__opencl_c_named_address_space_builtins)
12077#if defined(__opencl_c_generic_address_space)
12085#if defined(__opencl_c_named_address_space_builtins)
12119#if defined(__opencl_c_generic_address_space)
12183#if defined(__opencl_c_named_address_space_builtins)
12401#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
12449#if defined(__opencl_c_generic_address_space)
12884#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
12885#pragma OPENCL EXTENSION cl_khr_int64_base_atomics : enable
12886#pragma OPENCL EXTENSION cl_khr_int64_extended_atomics : enable
12898#ifdef __OPENCL_CPP_VERSION__
12903#if defined(cl_khr_global_int32_base_atomics)
12904int __ovld atom_add(
volatile __global
int *,
int);
12907#if defined(cl_khr_local_int32_base_atomics)
12908int __ovld atom_add(
volatile __local
int *,
int);
12912#if defined(cl_khr_int64_base_atomics)
12913long __ovld atom_add(
volatile __global
long *,
long);
12915long __ovld atom_add(
volatile __local
long *,
long);
12928#ifdef __OPENCL_CPP_VERSION__
12933#if defined(cl_khr_global_int32_base_atomics)
12934int __ovld atom_sub(
volatile __global
int *,
int);
12937#if defined(cl_khr_local_int32_base_atomics)
12938int __ovld atom_sub(
volatile __local
int *,
int);
12942#if defined(cl_khr_int64_base_atomics)
12943long __ovld atom_sub(
volatile __global
long *,
long);
12945long __ovld atom_sub(
volatile __local
long *,
long);
12960#ifdef __OPENCL_CPP_VERSION__
12966#if defined(cl_khr_global_int32_base_atomics)
12967int __ovld atom_xchg(
volatile __global
int *,
int);
12970#if defined(cl_khr_local_int32_base_atomics)
12971int __ovld atom_xchg(
volatile __local
int *,
int);
12975#if defined(cl_khr_int64_base_atomics)
12976long __ovld atom_xchg(
volatile __global
long *,
long);
12977long __ovld atom_xchg(
volatile __local
long *,
long);
12992#ifdef __OPENCL_CPP_VERSION__
12997#if defined(cl_khr_global_int32_base_atomics)
12998int __ovld atom_inc(
volatile __global
int *);
13001#if defined(cl_khr_local_int32_base_atomics)
13002int __ovld atom_inc(
volatile __local
int *);
13006#if defined(cl_khr_int64_base_atomics)
13007long __ovld atom_inc(
volatile __global
long *);
13009long __ovld atom_inc(
volatile __local
long *);
13023#ifdef __OPENCL_CPP_VERSION__
13028#if defined(cl_khr_global_int32_base_atomics)
13029int __ovld atom_dec(
volatile __global
int *);
13032#if defined(cl_khr_local_int32_base_atomics)
13033int __ovld atom_dec(
volatile __local
int *);
13037#if defined(cl_khr_int64_base_atomics)
13038long __ovld atom_dec(
volatile __global
long *);
13040long __ovld atom_dec(
volatile __local
long *);
13055#ifdef __OPENCL_CPP_VERSION__
13060#if defined(cl_khr_global_int32_base_atomics)
13061int __ovld atom_cmpxchg(
volatile __global
int *,
int,
int);
13064#if defined(cl_khr_local_int32_base_atomics)
13065int __ovld atom_cmpxchg(
volatile __local
int *,
int,
int);
13069#if defined(cl_khr_int64_base_atomics)
13070long __ovld atom_cmpxchg(
volatile __global
long *,
long,
long);
13072long __ovld atom_cmpxchg(
volatile __local
long *,
long,
long);
13087#ifdef __OPENCL_CPP_VERSION__
13092#if defined(cl_khr_global_int32_extended_atomics)
13093int __ovld atom_min(
volatile __global
int *,
int);
13096#if defined(cl_khr_local_int32_extended_atomics)
13097int __ovld atom_min(
volatile __local
int *,
int);
13101#if defined(cl_khr_int64_extended_atomics)
13102long __ovld atom_min(
volatile __global
long *,
long);
13104long __ovld atom_min(
volatile __local
long *,
long);
13119#ifdef __OPENCL_CPP_VERSION__
13124#if defined(cl_khr_global_int32_extended_atomics)
13125int __ovld atom_max(
volatile __global
int *,
int);
13128#if defined(cl_khr_local_int32_extended_atomics)
13129int __ovld atom_max(
volatile __local
int *,
int);
13133#if defined(cl_khr_int64_extended_atomics)
13134long __ovld atom_max(
volatile __global
long *,
long);
13136long __ovld atom_max(
volatile __local
long *,
long);
13150#ifdef __OPENCL_CPP_VERSION__
13155#if defined(cl_khr_global_int32_extended_atomics)
13156int __ovld atom_and(
volatile __global
int *,
int);
13159#if defined(cl_khr_local_int32_extended_atomics)
13160int __ovld atom_and(
volatile __local
int *,
int);
13164#if defined(cl_khr_int64_extended_atomics)
13165long __ovld atom_and(
volatile __global
long *,
long);
13167long __ovld atom_and(
volatile __local
long *,
long);
13181#ifdef __OPENCL_CPP_VERSION__
13186#if defined(cl_khr_global_int32_extended_atomics)
13187int __ovld atom_or(
volatile __global
int *,
int);
13190#if defined(cl_khr_local_int32_extended_atomics)
13191int __ovld atom_or(
volatile __local
int *,
int);
13195#if defined(cl_khr_int64_extended_atomics)
13196long __ovld atom_or(
volatile __global
long *,
long);
13198long __ovld atom_or(
volatile __local
long *,
long);
13212#ifdef __OPENCL_CPP_VERSION__
13217#if defined(cl_khr_global_int32_extended_atomics)
13218int __ovld atom_xor(
volatile __global
int *,
int);
13221#if defined(cl_khr_local_int32_extended_atomics)
13222int __ovld atom_xor(
volatile __local
int *,
int);
13226#if defined(cl_khr_int64_extended_atomics)
13227long __ovld atom_xor(
volatile __global
long *,
long);
13229long __ovld atom_xor(
volatile __local
long *,
long);
13233#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13234#pragma OPENCL EXTENSION cl_khr_int64_base_atomics : disable
13235#pragma OPENCL EXTENSION cl_khr_int64_extended_atomics : disable
13240#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
13243#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13244#pragma OPENCL EXTENSION cl_khr_int64_base_atomics : enable
13245#pragma OPENCL EXTENSION cl_khr_int64_extended_atomics : enable
13249#if defined(__opencl_c_generic_address_space)
13253#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13261#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
13268#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13287#if defined(__opencl_c_atomic_order_seq_cst) && defined(__opencl_c_atomic_scope_device)
13288#if defined(__opencl_c_generic_address_space)
13299int __ovld atomic_fetch_min(
volatile atomic_int *,
int);
13301int __ovld atomic_fetch_max(
volatile atomic_int *,
int);
13303#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13314long __ovld atomic_fetch_min(
volatile atomic_long *,
long);
13316long __ovld atomic_fetch_max(
volatile atomic_long *,
long);
13322#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
13343int __ovld atomic_fetch_min(
volatile __global atomic_int *,
int);
13344int __ovld atomic_fetch_min(
volatile __local atomic_int *,
int);
13345uint __ovld atomic_fetch_min(
volatile __global atomic_uint *,
uint);
13346uint __ovld atomic_fetch_min(
volatile __local atomic_uint *,
uint);
13347int __ovld atomic_fetch_max(
volatile __global atomic_int *,
int);
13348int __ovld atomic_fetch_max(
volatile __local atomic_int *,
int);
13349uint __ovld atomic_fetch_max(
volatile __global atomic_uint *,
uint);
13350uint __ovld atomic_fetch_max(
volatile __local atomic_uint *,
uint);
13351#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13388long __ovld atomic_fetch_min(
volatile __global atomic_long *,
long);
13389long __ovld atomic_fetch_min(
volatile __local atomic_long *,
long);
13396long __ovld atomic_fetch_max(
volatile __global atomic_long *,
long);
13397long __ovld atomic_fetch_max(
volatile __local atomic_long *,
long);
13406#if defined(__opencl_c_atomic_scope_device)
13407#if defined(__opencl_c_generic_address_space)
13422#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13441#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
13470#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13525#if defined(__opencl_c_generic_address_space)
13540#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13559#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
13588#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13643#if defined(cl_ext_float_atomics)
13645#if defined(__opencl_c_ext_fp16_global_atomic_load_store)
13663#if defined(__opencl_c_ext_fp16_local_atomic_load_store)
13681#if defined(__opencl_c_ext_fp16_global_atomic_load_store) && \
13682 defined(__opencl_c_ext_fp16_local_atomic_load_store)
13701#if defined(__opencl_c_ext_fp16_global_atomic_min_max)
13702half
__ovld atomic_fetch_min(
volatile __global atomic_half *, half);
13703half
__ovld atomic_fetch_max(
volatile __global atomic_half *, half);
13714#if defined(__opencl_c_ext_fp16_local_atomic_min_max)
13715half
__ovld atomic_fetch_min(
volatile __local atomic_half *, half);
13716half
__ovld atomic_fetch_max(
volatile __local atomic_half *, half);
13727#if defined(__opencl_c_ext_fp16_global_atomic_min_max) && \
13728 defined(__opencl_c_ext_fp16_local_atomic_min_max)
13729half
__ovld atomic_fetch_min(
volatile atomic_half *, half);
13730half
__ovld atomic_fetch_max(
volatile atomic_half *, half);
13742#if defined(__opencl_c_ext_fp32_global_atomic_min_max)
13743float __ovld atomic_fetch_min(
volatile __global atomic_float *,
float);
13744float __ovld atomic_fetch_max(
volatile __global atomic_float *,
float);
13755#if defined(__opencl_c_ext_fp32_local_atomic_min_max)
13756float __ovld atomic_fetch_min(
volatile __local atomic_float *,
float);
13757float __ovld atomic_fetch_max(
volatile __local atomic_float *,
float);
13768#if defined(__opencl_c_ext_fp32_global_atomic_min_max) && \
13769 defined(__opencl_c_ext_fp32_local_atomic_min_max)
13770float __ovld atomic_fetch_min(
volatile atomic_float *,
float);
13771float __ovld atomic_fetch_max(
volatile atomic_float *,
float);
13783#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13784#if defined(__opencl_c_ext_fp64_global_atomic_min_max)
13785double __ovld atomic_fetch_min(
volatile __global atomic_double *,
double);
13786double __ovld atomic_fetch_max(
volatile __global atomic_double *,
double);
13797#if defined(__opencl_c_ext_fp64_local_atomic_min_max)
13798double __ovld atomic_fetch_min(
volatile __local atomic_double *,
double);
13799double __ovld atomic_fetch_max(
volatile __local atomic_double *,
double);
13810#if defined(__opencl_c_ext_fp64_global_atomic_min_max) && \
13811 defined(__opencl_c_ext_fp64_local_atomic_min_max)
13812double __ovld atomic_fetch_min(
volatile atomic_double *,
double);
13813double __ovld atomic_fetch_max(
volatile atomic_double *,
double);
13827#if defined(__opencl_c_ext_fp16_global_atomic_add)
13840#if defined(__opencl_c_ext_fp16_local_atomic_add)
13853#if defined(__opencl_c_ext_fp16_global_atomic_add) && \
13854 defined(__opencl_c_ext_fp16_local_atomic_add)
13868#if defined(__opencl_c_ext_fp32_global_atomic_add)
13881#if defined(__opencl_c_ext_fp32_local_atomic_add)
13894#if defined(__opencl_c_ext_fp32_global_atomic_add) && \
13895 defined(__opencl_c_ext_fp32_local_atomic_add)
13909#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13910#if defined(__opencl_c_ext_fp64_global_atomic_add)
13923#if defined(__opencl_c_ext_fp64_local_atomic_add)
13936#if defined(__opencl_c_ext_fp64_global_atomic_add) && \
13937 defined(__opencl_c_ext_fp64_local_atomic_add)
13957#if defined(__opencl_c_atomic_order_seq_cst) && defined(__opencl_c_atomic_scope_device)
13958#if defined(__opencl_c_generic_address_space)
13963#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13971#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
13978#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
13991#if defined(__opencl_c_atomic_scope_device)
13992#if defined(__opencl_c_generic_address_space)
13996#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14004#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14011#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14024#if defined(__opencl_c_generic_address_space)
14028#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14036#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14043#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14056#if defined(__opencl_c_atomic_order_seq_cst) && defined(__opencl_c_atomic_scope_device)
14057#if defined(__opencl_c_generic_address_space)
14061#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14069#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14076#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14089#if defined(__opencl_c_atomic_scope_device)
14090#if defined(__opencl_c_generic_address_space)
14094#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14102#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14109#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14122#if defined(__opencl_c_generic_address_space)
14126#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14134#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14141#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14155#if defined(__opencl_c_atomic_order_seq_cst) && defined(__opencl_c_atomic_scope_device)
14156#if defined(__opencl_c_generic_address_space)
14160#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14168#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14175#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14188#if defined(__opencl_c_atomic_scope_device)
14189#if defined(__opencl_c_generic_address_space)
14193#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14201#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14208#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14221#if defined(__opencl_c_generic_address_space)
14225#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14233#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14240#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14253#if defined(__opencl_c_atomic_order_seq_cst) && defined(__opencl_c_atomic_scope_device)
14254#if defined(__opencl_c_generic_address_space)
14261#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14272#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14309#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14352#if defined(__opencl_c_atomic_scope_device)
14353#if defined(__opencl_c_generic_address_space)
14360#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14371#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14408#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14451#if defined(__opencl_c_generic_address_space)
14458#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14469#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14506#if defined(cl_khr_int64_base_atomics) && defined(cl_khr_int64_extended_atomics)
14549#if defined(__opencl_c_atomic_order_seq_cst) && defined(__opencl_c_atomic_scope_device)
14550#if defined(__opencl_c_generic_address_space)
14554#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14562#if defined(__opencl_c_atomic_scope_device)
14563#if defined(__opencl_c_generic_address_space)
14567#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
14575#if defined(__opencl_c_generic_address_space)
14579#if (__OPENCL_C_VERSION__ >= CL_VERSION_3_0 || __OPENCL_CPP_VERSION__ >= 202100)
15081#ifdef cl_khr_gl_msaa_sharing
15082#pragma OPENCL EXTENSION cl_khr_gl_msaa_sharing : enable
15194#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_1_2)
15212#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_1_2)
15222#ifdef cl_khr_depth_images
15230#if defined(cl_khr_gl_msaa_sharing)
15245#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
15246#ifdef cl_khr_mipmap_image
15260#ifdef cl_khr_depth_images
15268#ifdef cl_khr_depth_images
15288#ifdef cl_khr_depth_images
15296#ifdef cl_khr_depth_images
15307#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_1_2)
15333#ifdef cl_khr_depth_images
15346half4
__ovld __purefn read_imageh(read_only image1d_t, sampler_t,
int);
15347half4
__ovld __purefn read_imageh(read_only image1d_t, sampler_t,
float);
15348half4
__ovld __purefn read_imageh(read_only image2d_t, sampler_t, int2);
15349half4
__ovld __purefn read_imageh(read_only image2d_t, sampler_t, float2);
15350half4
__ovld __purefn read_imageh(read_only image3d_t, sampler_t, int4);
15351half4
__ovld __purefn read_imageh(read_only image3d_t, sampler_t, float4);
15352#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_1_2)
15353half4
__ovld __purefn read_imageh(read_only image1d_array_t, sampler_t, int2);
15354half4
__ovld __purefn read_imageh(read_only image1d_array_t, sampler_t, float2);
15355half4
__ovld __purefn read_imageh(read_only image2d_array_t, sampler_t, int4);
15356half4
__ovld __purefn read_imageh(read_only image2d_array_t, sampler_t, float4);
15363half4
__ovld __purefn read_imageh(read_only image1d_array_t, int2);
15364half4
__ovld __purefn read_imageh(read_only image2d_array_t, int4);
15365half4
__ovld __purefn read_imageh(read_only image1d_buffer_t,
int);
15370#if defined(__opencl_c_read_write_images)
15391#ifdef cl_khr_3d_image_writes
15397#ifdef cl_khr_depth_images
15402#if cl_khr_gl_msaa_sharing
15415#ifdef cl_khr_mipmap_image
15436#ifdef cl_khr_3d_image_writes
15462#ifdef cl_khr_3d_image_writes
15474#ifdef cl_khr_3d_image_writes
15477half4
__ovld __purefn read_imageh(read_write image1d_array_t, int2);
15478half4
__ovld __purefn read_imageh(read_write image2d_array_t, int4);
15479half4
__ovld __purefn read_imageh(read_write image1d_buffer_t,
int);
15570#ifdef cl_khr_3d_image_writes
15576#ifdef cl_khr_depth_images
15582#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
15583#if defined(cl_khr_mipmap_image_writes)
15603#ifdef cl_khr_3d_image_writes
15614void __ovld write_imageh(write_only image1d_t,
int, half4);
15615void __ovld write_imageh(write_only image2d_t, int2, half4);
15616#ifdef cl_khr_3d_image_writes
15617void __ovld write_imageh(write_only image3d_t, int4, half4);
15619void __ovld write_imageh(write_only image1d_array_t, int2, half4);
15620void __ovld write_imageh(write_only image2d_array_t, int4, half4);
15621void __ovld write_imageh(write_only image1d_buffer_t,
int, half4);
15625#if defined(__opencl_c_read_write_images)
15646#ifdef cl_khr_3d_image_writes
15652#ifdef cl_khr_depth_images
15657#if defined(cl_khr_mipmap_image_writes)
15677#ifdef cl_khr_3d_image_writes
15687void __ovld write_imageh(read_write image1d_t,
int, half4);
15688void __ovld write_imageh(read_write image2d_t, int2, half4);
15689#ifdef cl_khr_3d_image_writes
15690void __ovld write_imageh(read_write image3d_t, int4, half4);
15692void __ovld write_imageh(read_write image1d_array_t, int2, half4);
15693void __ovld write_imageh(read_write image2d_array_t, int4, half4);
15694void __ovld write_imageh(read_write image1d_buffer_t,
int, half4);
15712#ifdef cl_khr_depth_images
15716#if defined(cl_khr_gl_msaa_sharing)
15726#ifdef cl_khr_3d_image_writes
15731#ifdef cl_khr_depth_images
15735#if defined(cl_khr_gl_msaa_sharing)
15742#if defined(__opencl_c_read_write_images)
15746#ifdef cl_khr_3d_image_writes
15751#ifdef cl_khr_depth_images
15755#if defined(cl_khr_gl_msaa_sharing)
15769#ifdef cl_khr_depth_images
15773#if defined(cl_khr_gl_msaa_sharing)
15781#ifdef cl_khr_3d_image_writes
15785#ifdef cl_khr_depth_images
15789#if defined(cl_khr_gl_msaa_sharing)
15796#if defined(__opencl_c_read_write_images)
15798#ifdef cl_khr_3d_image_writes
15802#ifdef cl_khr_depth_images
15806#if defined(cl_khr_gl_msaa_sharing)
15819#ifdef cl_khr_3d_image_writes
15822#if defined(__opencl_c_read_write_images)
15828#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
15829#ifdef cl_khr_mipmap_image
15834int __ovld get_image_num_mip_levels(read_only image1d_t);
15835int __ovld get_image_num_mip_levels(read_only image2d_t);
15836int __ovld get_image_num_mip_levels(read_only image3d_t);
15838int __ovld get_image_num_mip_levels(write_only image1d_t);
15839int __ovld get_image_num_mip_levels(write_only image2d_t);
15840#ifdef cl_khr_3d_image_writes
15841int __ovld get_image_num_mip_levels(write_only image3d_t);
15844#if defined(__opencl_c_read_write_images)
15845int __ovld get_image_num_mip_levels(read_write image1d_t);
15846int __ovld get_image_num_mip_levels(read_write image2d_t);
15847#ifdef cl_khr_3d_image_writes
15848int __ovld get_image_num_mip_levels(read_write image3d_t);
15852int __ovld get_image_num_mip_levels(read_only image1d_array_t);
15853int __ovld get_image_num_mip_levels(read_only image2d_array_t);
15854#ifdef cl_khr_depth_images
15855int __ovld get_image_num_mip_levels(read_only image2d_array_depth_t);
15856int __ovld get_image_num_mip_levels(read_only image2d_depth_t);
15859int __ovld get_image_num_mip_levels(write_only image1d_array_t);
15860int __ovld get_image_num_mip_levels(write_only image2d_array_t);
15861#ifdef cl_khr_depth_images
15862int __ovld get_image_num_mip_levels(write_only image2d_array_depth_t);
15863int __ovld get_image_num_mip_levels(write_only image2d_depth_t);
15866#if defined(__opencl_c_read_write_images)
15867int __ovld get_image_num_mip_levels(read_write image1d_array_t);
15868int __ovld get_image_num_mip_levels(read_write image2d_array_t);
15869#ifdef cl_khr_depth_images
15870int __ovld get_image_num_mip_levels(read_write image2d_array_depth_t);
15871int __ovld get_image_num_mip_levels(read_write image2d_depth_t);
15903#ifdef cl_khr_depth_images
15907#if defined(cl_khr_gl_msaa_sharing)
15917#ifdef cl_khr_3d_image_writes
15922#ifdef cl_khr_depth_images
15926#if defined(cl_khr_gl_msaa_sharing)
15933#if defined(__opencl_c_read_write_images)
15937#ifdef cl_khr_3d_image_writes
15942#ifdef cl_khr_depth_images
15946#if defined(cl_khr_gl_msaa_sharing)
15977#ifdef cl_khr_depth_images
15981#if defined(cl_khr_gl_msaa_sharing)
15991#ifdef cl_khr_3d_image_writes
15996#ifdef cl_khr_depth_images
16000#if defined(cl_khr_gl_msaa_sharing)
16007#if defined(__opencl_c_read_write_images)
16011#ifdef cl_khr_3d_image_writes
16016#ifdef cl_khr_depth_images
16020#if defined(cl_khr_gl_msaa_sharing)
16035#ifdef cl_khr_depth_images
16039#if defined(cl_khr_gl_msaa_sharing)
16048#ifdef cl_khr_depth_images
16052#if defined(cl_khr_gl_msaa_sharing)
16059#if defined(__opencl_c_read_write_images)
16062#ifdef cl_khr_depth_images
16066#if defined(cl_khr_gl_msaa_sharing)
16081#ifdef cl_khr_3d_image_writes
16083#if defined(__opencl_c_read_write_images)
16094#ifdef cl_khr_depth_images
16097#if defined(cl_khr_gl_msaa_sharing)
16104#ifdef cl_khr_depth_images
16107#if defined(cl_khr_gl_msaa_sharing)
16112#if defined(__opencl_c_read_write_images)
16115#ifdef cl_khr_depth_images
16118#if defined(cl_khr_gl_msaa_sharing)
16127#if defined(cl_khr_gl_msaa_sharing)
16128int __ovld __cnfn get_image_num_samples(read_only image2d_msaa_t);
16129int __ovld __cnfn get_image_num_samples(read_only image2d_msaa_depth_t);
16130int __ovld __cnfn get_image_num_samples(read_only image2d_array_msaa_t);
16131int __ovld __cnfn get_image_num_samples(read_only image2d_array_msaa_depth_t);
16133int __ovld __cnfn get_image_num_samples(write_only image2d_msaa_t);
16134int __ovld __cnfn get_image_num_samples(write_only image2d_msaa_depth_t);
16135int __ovld __cnfn get_image_num_samples(write_only image2d_array_msaa_t);
16136int __ovld __cnfn get_image_num_samples(write_only image2d_array_msaa_depth_t);
16138#if defined(__opencl_c_read_write_images)
16139int __ovld __cnfn get_image_num_samples(read_write image2d_msaa_t);
16140int __ovld __cnfn get_image_num_samples(read_write image2d_msaa_depth_t);
16141int __ovld __cnfn get_image_num_samples(read_write image2d_array_msaa_t);
16142int __ovld __cnfn get_image_num_samples(read_write image2d_array_msaa_depth_t);
16148#if defined(__opencl_c_work_group_collective_functions)
16153half
__ovld __conv work_group_broadcast(half,
size_t local_id);
16154half
__ovld __conv work_group_broadcast(half,
size_t,
size_t);
16155half
__ovld __conv work_group_broadcast(half,
size_t,
size_t,
size_t);
16157int __ovld __conv work_group_broadcast(
int,
size_t local_id);
16158int __ovld __conv work_group_broadcast(
int,
size_t,
size_t);
16159int __ovld __conv work_group_broadcast(
int,
size_t,
size_t,
size_t);
16163long __ovld __conv work_group_broadcast(
long,
size_t local_id);
16164long __ovld __conv work_group_broadcast(
long,
size_t,
size_t);
16165long __ovld __conv work_group_broadcast(
long,
size_t,
size_t,
size_t);
16169float __ovld __conv work_group_broadcast(
float,
size_t local_id);
16170float __ovld __conv work_group_broadcast(
float,
size_t,
size_t);
16171float __ovld __conv work_group_broadcast(
float,
size_t,
size_t,
size_t);
16173double __ovld __conv work_group_broadcast(
double,
size_t local_id);
16174double __ovld __conv work_group_broadcast(
double,
size_t,
size_t);
16175double __ovld __conv work_group_broadcast(
double,
size_t,
size_t,
size_t);
16182half
__ovld __conv work_group_scan_exclusive_add(half);
16183half
__ovld __conv work_group_scan_exclusive_min(half);
16184half
__ovld __conv work_group_scan_exclusive_max(half);
16185half
__ovld __conv work_group_scan_inclusive_add(half);
16186half
__ovld __conv work_group_scan_inclusive_min(half);
16187half
__ovld __conv work_group_scan_inclusive_max(half);
16210long __ovld __conv work_group_scan_exclusive_add(
long);
16211long __ovld __conv work_group_scan_exclusive_min(
long);
16212long __ovld __conv work_group_scan_exclusive_max(
long);
16213long __ovld __conv work_group_scan_inclusive_add(
long);
16214long __ovld __conv work_group_scan_inclusive_min(
long);
16215long __ovld __conv work_group_scan_inclusive_max(
long);
16228float __ovld __conv work_group_scan_exclusive_add(
float);
16229float __ovld __conv work_group_scan_exclusive_min(
float);
16230float __ovld __conv work_group_scan_exclusive_max(
float);
16231float __ovld __conv work_group_scan_inclusive_add(
float);
16232float __ovld __conv work_group_scan_inclusive_min(
float);
16233float __ovld __conv work_group_scan_inclusive_max(
float);
16238double __ovld __conv work_group_scan_exclusive_add(
double);
16239double __ovld __conv work_group_scan_exclusive_min(
double);
16240double __ovld __conv work_group_scan_exclusive_max(
double);
16241double __ovld __conv work_group_scan_inclusive_add(
double);
16242double __ovld __conv work_group_scan_inclusive_min(
double);
16243double __ovld __conv work_group_scan_inclusive_max(
double);
16249#if defined(__opencl_c_pipes)
16250bool __ovld is_valid_reserve_id(reserve_id_t reserve_id);
16255#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
16257#ifdef __opencl_c_device_enqueue
16258ndrange_t
__ovld ndrange_1D(
size_t);
16259ndrange_t
__ovld ndrange_1D(
size_t,
size_t);
16260ndrange_t
__ovld ndrange_1D(
size_t,
size_t,
size_t);
16262ndrange_t
__ovld ndrange_2D(
const size_t[2]);
16263ndrange_t
__ovld ndrange_2D(
const size_t[2],
const size_t[2]);
16264ndrange_t
__ovld ndrange_2D(
const size_t[2],
const size_t[2],
const size_t[2]);
16266ndrange_t
__ovld ndrange_3D(
const size_t[3]);
16267ndrange_t
__ovld ndrange_3D(
const size_t[3],
const size_t[3]);
16268ndrange_t
__ovld ndrange_3D(
const size_t[3],
const size_t[3],
const size_t[3]);
16270int __ovld enqueue_marker(queue_t,
uint,
const clk_event_t*, clk_event_t*);
16272void __ovld retain_event(clk_event_t);
16274void __ovld release_event(clk_event_t);
16276clk_event_t
__ovld create_user_event(
void);
16278void __ovld set_user_event_status(clk_event_t e,
int state);
16280bool __ovld is_valid_event (clk_event_t event);
16284queue_t
__ovld get_default_queue(
void);
16290#if defined(__opencl_subgroup_builtins)
16295#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
16296uint __ovld get_enqueued_num_sub_groups(
void);
16302#if defined(__OPENCL_CPP_VERSION__) || (__OPENCL_C_VERSION__ >= CL_VERSION_2_0)
16333long __ovld __conv sub_group_scan_exclusive_add(
long );
16335float __ovld __conv sub_group_scan_exclusive_add(
float);
16338long __ovld __conv sub_group_scan_exclusive_min(
long );
16340float __ovld __conv sub_group_scan_exclusive_min(
float);
16343long __ovld __conv sub_group_scan_exclusive_max(
long );
16345float __ovld __conv sub_group_scan_exclusive_max(
float);
16349long __ovld __conv sub_group_scan_inclusive_add(
long );
16351float __ovld __conv sub_group_scan_inclusive_add(
float);
16354long __ovld __conv sub_group_scan_inclusive_min(
long );
16356float __ovld __conv sub_group_scan_inclusive_min(
float);
16359long __ovld __conv sub_group_scan_inclusive_max(
long );
16361float __ovld __conv sub_group_scan_inclusive_max(
float);
16381double __ovld __conv sub_group_scan_exclusive_add(
double);
16382double __ovld __conv sub_group_scan_exclusive_min(
double);
16383double __ovld __conv sub_group_scan_exclusive_max(
double);
16384double __ovld __conv sub_group_scan_inclusive_add(
double);
16385double __ovld __conv sub_group_scan_inclusive_min(
double);
16386double __ovld __conv sub_group_scan_inclusive_max(
double);
16391#if defined(cl_khr_subgroup_extended_types)
16457short __ovld __conv sub_group_reduce_add(
short value );
16462short __ovld __conv sub_group_reduce_min(
short value );
16467short __ovld __conv sub_group_reduce_max(
short value );
16470char __ovld __conv sub_group_scan_inclusive_add(
char value );
16472short __ovld __conv sub_group_scan_inclusive_add(
short value );
16475char __ovld __conv sub_group_scan_inclusive_min(
char value );
16477short __ovld __conv sub_group_scan_inclusive_min(
short value );
16480char __ovld __conv sub_group_scan_inclusive_max(
char value );
16482short __ovld __conv sub_group_scan_inclusive_max(
short value );
16485char __ovld __conv sub_group_scan_exclusive_add(
char value );
16487short __ovld __conv sub_group_scan_exclusive_add(
short value );
16490char __ovld __conv sub_group_scan_exclusive_min(
char value );
16492short __ovld __conv sub_group_scan_exclusive_min(
short value );
16495char __ovld __conv sub_group_scan_exclusive_max(
char value );
16497short __ovld __conv sub_group_scan_exclusive_max(
short value );
16500#if defined(cl_khr_fp16)
16509#if defined(cl_khr_fp64)
16520#if defined(cl_khr_subgroup_non_uniform_vote)
16521int __ovld sub_group_elect(
void);
16522int __ovld sub_group_non_uniform_all(
int predicate );
16523int __ovld sub_group_non_uniform_any(
int predicate );
16525int __ovld sub_group_non_uniform_all_equal(
char value );
16526int __ovld sub_group_non_uniform_all_equal(
uchar value );
16527int __ovld sub_group_non_uniform_all_equal(
short value );
16528int __ovld sub_group_non_uniform_all_equal(
ushort value );
16529int __ovld sub_group_non_uniform_all_equal(
int value );
16530int __ovld sub_group_non_uniform_all_equal(
uint value );
16531int __ovld sub_group_non_uniform_all_equal(
long value );
16532int __ovld sub_group_non_uniform_all_equal(
ulong value );
16533int __ovld sub_group_non_uniform_all_equal(
float value );
16535#if defined(cl_khr_fp16)
16536int __ovld sub_group_non_uniform_all_equal( half value );
16539#if defined(cl_khr_fp64)
16540int __ovld sub_group_non_uniform_all_equal(
double value );
16545#if defined(cl_khr_subgroup_ballot)
16546char __ovld sub_group_non_uniform_broadcast(
char value,
uint index );
16547char2
__ovld sub_group_non_uniform_broadcast( char2 value,
uint index );
16548char3
__ovld sub_group_non_uniform_broadcast( char3 value,
uint index );
16549char4
__ovld sub_group_non_uniform_broadcast( char4 value,
uint index );
16550char8
__ovld sub_group_non_uniform_broadcast( char8 value,
uint index );
16551char16
__ovld sub_group_non_uniform_broadcast( char16 value,
uint index );
16554uchar2
__ovld sub_group_non_uniform_broadcast( uchar2 value,
uint index );
16555uchar3
__ovld sub_group_non_uniform_broadcast( uchar3 value,
uint index );
16556uchar4
__ovld sub_group_non_uniform_broadcast( uchar4 value,
uint index );
16557uchar8
__ovld sub_group_non_uniform_broadcast( uchar8 value,
uint index );
16558uchar16
__ovld sub_group_non_uniform_broadcast( uchar16 value,
uint index );
16560short __ovld sub_group_non_uniform_broadcast(
short value,
uint index );
16561short2
__ovld sub_group_non_uniform_broadcast( short2 value,
uint index );
16562short3
__ovld sub_group_non_uniform_broadcast( short3 value,
uint index );
16563short4
__ovld sub_group_non_uniform_broadcast( short4 value,
uint index );
16564short8
__ovld sub_group_non_uniform_broadcast( short8 value,
uint index );
16565short16
__ovld sub_group_non_uniform_broadcast( short16 value,
uint index );
16568ushort2
__ovld sub_group_non_uniform_broadcast( ushort2 value,
uint index );
16569ushort3
__ovld sub_group_non_uniform_broadcast( ushort3 value,
uint index );
16570ushort4
__ovld sub_group_non_uniform_broadcast( ushort4 value,
uint index );
16571ushort8
__ovld sub_group_non_uniform_broadcast( ushort8 value,
uint index );
16572ushort16
__ovld sub_group_non_uniform_broadcast( ushort16 value,
uint index );
16574int __ovld sub_group_non_uniform_broadcast(
int value,
uint index );
16575int2
__ovld sub_group_non_uniform_broadcast( int2 value,
uint index );
16576int3
__ovld sub_group_non_uniform_broadcast( int3 value,
uint index );
16577int4
__ovld sub_group_non_uniform_broadcast( int4 value,
uint index );
16578int8
__ovld sub_group_non_uniform_broadcast( int8 value,
uint index );
16579int16
__ovld sub_group_non_uniform_broadcast( int16 value,
uint index );
16582uint2
__ovld sub_group_non_uniform_broadcast( uint2 value,
uint index );
16583uint3
__ovld sub_group_non_uniform_broadcast( uint3 value,
uint index );
16584uint4
__ovld sub_group_non_uniform_broadcast( uint4 value,
uint index );
16585uint8
__ovld sub_group_non_uniform_broadcast( uint8 value,
uint index );
16586uint16
__ovld sub_group_non_uniform_broadcast( uint16 value,
uint index );
16588long __ovld sub_group_non_uniform_broadcast(
long value,
uint index );
16589long2
__ovld sub_group_non_uniform_broadcast( long2 value,
uint index );
16590long3
__ovld sub_group_non_uniform_broadcast( long3 value,
uint index );
16591long4
__ovld sub_group_non_uniform_broadcast( long4 value,
uint index );
16592long8
__ovld sub_group_non_uniform_broadcast( long8 value,
uint index );
16593long16
__ovld sub_group_non_uniform_broadcast( long16 value,
uint index );
16596ulong2
__ovld sub_group_non_uniform_broadcast( ulong2 value,
uint index );
16597ulong3
__ovld sub_group_non_uniform_broadcast( ulong3 value,
uint index );
16598ulong4
__ovld sub_group_non_uniform_broadcast( ulong4 value,
uint index );
16599ulong8
__ovld sub_group_non_uniform_broadcast( ulong8 value,
uint index );
16600ulong16
__ovld sub_group_non_uniform_broadcast( ulong16 value,
uint index );
16602float __ovld sub_group_non_uniform_broadcast(
float value,
uint index );
16603float2
__ovld sub_group_non_uniform_broadcast( float2 value,
uint index );
16604float3
__ovld sub_group_non_uniform_broadcast( float3 value,
uint index );
16605float4
__ovld sub_group_non_uniform_broadcast( float4 value,
uint index );
16606float8
__ovld sub_group_non_uniform_broadcast( float8 value,
uint index );
16607float16
__ovld sub_group_non_uniform_broadcast( float16 value,
uint index );
16609char __ovld sub_group_broadcast_first(
char value );
16611short __ovld sub_group_broadcast_first(
short value );
16613int __ovld sub_group_broadcast_first(
int value );
16615long __ovld sub_group_broadcast_first(
long value );
16617float __ovld sub_group_broadcast_first(
float value );
16619uint4
__ovld sub_group_ballot(
int predicate );
16620int __ovld __cnfn sub_group_inverse_ballot( uint4 value );
16624uint __ovld sub_group_ballot_inclusive_scan( uint4 value );
16625uint __ovld sub_group_ballot_exclusive_scan( uint4 value );
16626uint __ovld sub_group_ballot_find_lsb( uint4 value );
16627uint __ovld sub_group_ballot_find_msb( uint4 value );
16635#if defined(cl_khr_fp16)
16636half
__ovld sub_group_non_uniform_broadcast( half value,
uint index );
16637half2
__ovld sub_group_non_uniform_broadcast( half2 value,
uint index );
16638half3
__ovld sub_group_non_uniform_broadcast( half3 value,
uint index );
16639half4
__ovld sub_group_non_uniform_broadcast( half4 value,
uint index );
16640half8
__ovld sub_group_non_uniform_broadcast( half8 value,
uint index );
16641half16
__ovld sub_group_non_uniform_broadcast( half16 value,
uint index );
16643half
__ovld sub_group_broadcast_first( half value );
16646#if defined(cl_khr_fp64)
16647double __ovld sub_group_non_uniform_broadcast(
double value,
uint index );
16648double2
__ovld sub_group_non_uniform_broadcast( double2 value,
uint index );
16649double3
__ovld sub_group_non_uniform_broadcast( double3 value,
uint index );
16650double4
__ovld sub_group_non_uniform_broadcast( double4 value,
uint index );
16651double8
__ovld sub_group_non_uniform_broadcast( double8 value,
uint index );
16652double16
__ovld sub_group_non_uniform_broadcast( double16 value,
uint index );
16654double __ovld sub_group_broadcast_first(
double value );
16659#if defined(cl_khr_subgroup_non_uniform_arithmetic)
16660char __ovld sub_group_non_uniform_reduce_add(
char value );
16662short __ovld sub_group_non_uniform_reduce_add(
short value );
16664int __ovld sub_group_non_uniform_reduce_add(
int value );
16666long __ovld sub_group_non_uniform_reduce_add(
long value );
16668float __ovld sub_group_non_uniform_reduce_add(
float value );
16670char __ovld sub_group_non_uniform_reduce_mul(
char value );
16672short __ovld sub_group_non_uniform_reduce_mul(
short value );
16674int __ovld sub_group_non_uniform_reduce_mul(
int value );
16676long __ovld sub_group_non_uniform_reduce_mul(
long value );
16678float __ovld sub_group_non_uniform_reduce_mul(
float value );
16680char __ovld sub_group_non_uniform_reduce_min(
char value );
16682short __ovld sub_group_non_uniform_reduce_min(
short value );
16684int __ovld sub_group_non_uniform_reduce_min(
int value );
16686long __ovld sub_group_non_uniform_reduce_min(
long value );
16688float __ovld sub_group_non_uniform_reduce_min(
float value );
16690char __ovld sub_group_non_uniform_reduce_max(
char value );
16692short __ovld sub_group_non_uniform_reduce_max(
short value );
16694int __ovld sub_group_non_uniform_reduce_max(
int value );
16696long __ovld sub_group_non_uniform_reduce_max(
long value );
16698float __ovld sub_group_non_uniform_reduce_max(
float value );
16700char __ovld sub_group_non_uniform_scan_inclusive_add(
char value );
16702short __ovld sub_group_non_uniform_scan_inclusive_add(
short value );
16704int __ovld sub_group_non_uniform_scan_inclusive_add(
int value );
16705uint __ovld sub_group_non_uniform_scan_inclusive_add(
uint value );
16706long __ovld sub_group_non_uniform_scan_inclusive_add(
long value );
16708float __ovld sub_group_non_uniform_scan_inclusive_add(
float value );
16710char __ovld sub_group_non_uniform_scan_inclusive_mul(
char value );
16712short __ovld sub_group_non_uniform_scan_inclusive_mul(
short value );
16714int __ovld sub_group_non_uniform_scan_inclusive_mul(
int value );
16715uint __ovld sub_group_non_uniform_scan_inclusive_mul(
uint value );
16716long __ovld sub_group_non_uniform_scan_inclusive_mul(
long value );
16718float __ovld sub_group_non_uniform_scan_inclusive_mul(
float value );
16720char __ovld sub_group_non_uniform_scan_inclusive_min(
char value );
16722short __ovld sub_group_non_uniform_scan_inclusive_min(
short value );
16724int __ovld sub_group_non_uniform_scan_inclusive_min(
int value );
16725uint __ovld sub_group_non_uniform_scan_inclusive_min(
uint value );
16726long __ovld sub_group_non_uniform_scan_inclusive_min(
long value );
16728float __ovld sub_group_non_uniform_scan_inclusive_min(
float value );
16730char __ovld sub_group_non_uniform_scan_inclusive_max(
char value );
16732short __ovld sub_group_non_uniform_scan_inclusive_max(
short value );
16734int __ovld sub_group_non_uniform_scan_inclusive_max(
int value );
16735uint __ovld sub_group_non_uniform_scan_inclusive_max(
uint value );
16736long __ovld sub_group_non_uniform_scan_inclusive_max(
long value );
16738float __ovld sub_group_non_uniform_scan_inclusive_max(
float value );
16740char __ovld sub_group_non_uniform_scan_exclusive_add(
char value );
16742short __ovld sub_group_non_uniform_scan_exclusive_add(
short value );
16744int __ovld sub_group_non_uniform_scan_exclusive_add(
int value );
16745uint __ovld sub_group_non_uniform_scan_exclusive_add(
uint value );
16746long __ovld sub_group_non_uniform_scan_exclusive_add(
long value );
16748float __ovld sub_group_non_uniform_scan_exclusive_add(
float value );
16750char __ovld sub_group_non_uniform_scan_exclusive_mul(
char value );
16752short __ovld sub_group_non_uniform_scan_exclusive_mul(
short value );
16754int __ovld sub_group_non_uniform_scan_exclusive_mul(
int value );
16755uint __ovld sub_group_non_uniform_scan_exclusive_mul(
uint value );
16756long __ovld sub_group_non_uniform_scan_exclusive_mul(
long value );
16758float __ovld sub_group_non_uniform_scan_exclusive_mul(
float value );
16760char __ovld sub_group_non_uniform_scan_exclusive_min(
char value );
16762short __ovld sub_group_non_uniform_scan_exclusive_min(
short value );
16764int __ovld sub_group_non_uniform_scan_exclusive_min(
int value );
16765uint __ovld sub_group_non_uniform_scan_exclusive_min(
uint value );
16766long __ovld sub_group_non_uniform_scan_exclusive_min(
long value );
16768float __ovld sub_group_non_uniform_scan_exclusive_min(
float value );
16770char __ovld sub_group_non_uniform_scan_exclusive_max(
char value );
16772short __ovld sub_group_non_uniform_scan_exclusive_max(
short value );
16774int __ovld sub_group_non_uniform_scan_exclusive_max(
int value );
16775uint __ovld sub_group_non_uniform_scan_exclusive_max(
uint value );
16776long __ovld sub_group_non_uniform_scan_exclusive_max(
long value );
16778float __ovld sub_group_non_uniform_scan_exclusive_max(
float value );
16780char __ovld sub_group_non_uniform_reduce_and(
char value );
16782short __ovld sub_group_non_uniform_reduce_and(
short value );
16784int __ovld sub_group_non_uniform_reduce_and(
int value );
16786long __ovld sub_group_non_uniform_reduce_and(
long value );
16789char __ovld sub_group_non_uniform_reduce_or(
char value );
16791short __ovld sub_group_non_uniform_reduce_or(
short value );
16793int __ovld sub_group_non_uniform_reduce_or(
int value );
16795long __ovld sub_group_non_uniform_reduce_or(
long value );
16798char __ovld sub_group_non_uniform_reduce_xor(
char value );
16800short __ovld sub_group_non_uniform_reduce_xor(
short value );
16802int __ovld sub_group_non_uniform_reduce_xor(
int value );
16804long __ovld sub_group_non_uniform_reduce_xor(
long value );
16807char __ovld sub_group_non_uniform_scan_inclusive_and(
char value );
16809short __ovld sub_group_non_uniform_scan_inclusive_and(
short value );
16811int __ovld sub_group_non_uniform_scan_inclusive_and(
int value );
16812uint __ovld sub_group_non_uniform_scan_inclusive_and(
uint value );
16813long __ovld sub_group_non_uniform_scan_inclusive_and(
long value );
16816char __ovld sub_group_non_uniform_scan_inclusive_or(
char value );
16818short __ovld sub_group_non_uniform_scan_inclusive_or(
short value );
16820int __ovld sub_group_non_uniform_scan_inclusive_or(
int value );
16821uint __ovld sub_group_non_uniform_scan_inclusive_or(
uint value );
16822long __ovld sub_group_non_uniform_scan_inclusive_or(
long value );
16825char __ovld sub_group_non_uniform_scan_inclusive_xor(
char value );
16827short __ovld sub_group_non_uniform_scan_inclusive_xor(
short value );
16829int __ovld sub_group_non_uniform_scan_inclusive_xor(
int value );
16830uint __ovld sub_group_non_uniform_scan_inclusive_xor(
uint value );
16831long __ovld sub_group_non_uniform_scan_inclusive_xor(
long value );
16834char __ovld sub_group_non_uniform_scan_exclusive_and(
char value );
16836short __ovld sub_group_non_uniform_scan_exclusive_and(
short value );
16838int __ovld sub_group_non_uniform_scan_exclusive_and(
int value );
16839uint __ovld sub_group_non_uniform_scan_exclusive_and(
uint value );
16840long __ovld sub_group_non_uniform_scan_exclusive_and(
long value );
16843char __ovld sub_group_non_uniform_scan_exclusive_or(
char value );
16845short __ovld sub_group_non_uniform_scan_exclusive_or(
short value );
16847int __ovld sub_group_non_uniform_scan_exclusive_or(
int value );
16848uint __ovld sub_group_non_uniform_scan_exclusive_or(
uint value );
16849long __ovld sub_group_non_uniform_scan_exclusive_or(
long value );
16852char __ovld sub_group_non_uniform_scan_exclusive_xor(
char value );
16854short __ovld sub_group_non_uniform_scan_exclusive_xor(
short value );
16856int __ovld sub_group_non_uniform_scan_exclusive_xor(
int value );
16857uint __ovld sub_group_non_uniform_scan_exclusive_xor(
uint value );
16858long __ovld sub_group_non_uniform_scan_exclusive_xor(
long value );
16861int __ovld sub_group_non_uniform_reduce_logical_and(
int predicate );
16862int __ovld sub_group_non_uniform_reduce_logical_or(
int predicate );
16863int __ovld sub_group_non_uniform_reduce_logical_xor(
int predicate );
16865int __ovld sub_group_non_uniform_scan_inclusive_logical_and(
int predicate );
16866int __ovld sub_group_non_uniform_scan_inclusive_logical_or(
int predicate );
16867int __ovld sub_group_non_uniform_scan_inclusive_logical_xor(
int predicate );
16869int __ovld sub_group_non_uniform_scan_exclusive_logical_and(
int predicate );
16870int __ovld sub_group_non_uniform_scan_exclusive_logical_or(
int predicate );
16871int __ovld sub_group_non_uniform_scan_exclusive_logical_xor(
int predicate );
16873#if defined(cl_khr_fp16)
16874half
__ovld sub_group_non_uniform_reduce_add( half value );
16875half
__ovld sub_group_non_uniform_reduce_mul( half value );
16876half
__ovld sub_group_non_uniform_reduce_min( half value );
16877half
__ovld sub_group_non_uniform_reduce_max( half value );
16878half
__ovld sub_group_non_uniform_scan_inclusive_add( half value );
16879half
__ovld sub_group_non_uniform_scan_inclusive_mul( half value );
16880half
__ovld sub_group_non_uniform_scan_inclusive_min( half value );
16881half
__ovld sub_group_non_uniform_scan_inclusive_max( half value );
16882half
__ovld sub_group_non_uniform_scan_exclusive_add( half value );
16883half
__ovld sub_group_non_uniform_scan_exclusive_mul( half value );
16884half
__ovld sub_group_non_uniform_scan_exclusive_min( half value );
16885half
__ovld sub_group_non_uniform_scan_exclusive_max( half value );
16888#if defined(cl_khr_fp64)
16889double __ovld sub_group_non_uniform_reduce_add(
double value );
16890double __ovld sub_group_non_uniform_reduce_mul(
double value );
16891double __ovld sub_group_non_uniform_reduce_min(
double value );
16892double __ovld sub_group_non_uniform_reduce_max(
double value );
16893double __ovld sub_group_non_uniform_scan_inclusive_add(
double value );
16894double __ovld sub_group_non_uniform_scan_inclusive_mul(
double value );
16895double __ovld sub_group_non_uniform_scan_inclusive_min(
double value );
16896double __ovld sub_group_non_uniform_scan_inclusive_max(
double value );
16897double __ovld sub_group_non_uniform_scan_exclusive_add(
double value );
16898double __ovld sub_group_non_uniform_scan_exclusive_mul(
double value );
16899double __ovld sub_group_non_uniform_scan_exclusive_min(
double value );
16900double __ovld sub_group_non_uniform_scan_exclusive_max(
double value );
16905#if defined(cl_khr_subgroup_shuffle)
16906char __ovld sub_group_shuffle(
char value,
uint index );
16908short __ovld sub_group_shuffle(
short value,
uint index );
16910int __ovld sub_group_shuffle(
int value,
uint index );
16912long __ovld sub_group_shuffle(
long value,
uint index );
16914float __ovld sub_group_shuffle(
float value,
uint index );
16916char __ovld sub_group_shuffle_xor(
char value,
uint mask );
16918short __ovld sub_group_shuffle_xor(
short value,
uint mask );
16920int __ovld sub_group_shuffle_xor(
int value,
uint mask );
16922long __ovld sub_group_shuffle_xor(
long value,
uint mask );
16924float __ovld sub_group_shuffle_xor(
float value,
uint mask );
16926#if defined(cl_khr_fp16)
16927half
__ovld sub_group_shuffle( half value,
uint index );
16928half
__ovld sub_group_shuffle_xor( half value,
uint mask );
16931#if defined(cl_khr_fp64)
16932double __ovld sub_group_shuffle(
double value,
uint index );
16933double __ovld sub_group_shuffle_xor(
double value,
uint mask );
16938#if defined(cl_khr_subgroup_shuffle_relative)
16939char __ovld sub_group_shuffle_up(
char value,
uint delta );
16941short __ovld sub_group_shuffle_up(
short value,
uint delta );
16943int __ovld sub_group_shuffle_up(
int value,
uint delta );
16945long __ovld sub_group_shuffle_up(
long value,
uint delta );
16947float __ovld sub_group_shuffle_up(
float value,
uint delta );
16949char __ovld sub_group_shuffle_down(
char value,
uint delta );
16951short __ovld sub_group_shuffle_down(
short value,
uint delta );
16953int __ovld sub_group_shuffle_down(
int value,
uint delta );
16955long __ovld sub_group_shuffle_down(
long value,
uint delta );
16957float __ovld sub_group_shuffle_down(
float value,
uint delta );
16959#if defined(cl_khr_fp16)
16960half
__ovld sub_group_shuffle_up( half value,
uint delta );
16961half
__ovld sub_group_shuffle_down( half value,
uint delta );
16964#if defined(cl_khr_fp64)
16965double __ovld sub_group_shuffle_up(
double value,
uint delta );
16966double __ovld sub_group_shuffle_down(
double value,
uint delta );
16971#if defined(cl_khr_subgroup_clustered_reduce)
16972char __ovld sub_group_clustered_reduce_add(
char value,
uint clustersize );
16974short __ovld sub_group_clustered_reduce_add(
short value,
uint clustersize );
16976int __ovld sub_group_clustered_reduce_add(
int value,
uint clustersize );
16978long __ovld sub_group_clustered_reduce_add(
long value,
uint clustersize );
16980float __ovld sub_group_clustered_reduce_add(
float value,
uint clustersize );
16982char __ovld sub_group_clustered_reduce_mul(
char value,
uint clustersize );
16984short __ovld sub_group_clustered_reduce_mul(
short value,
uint clustersize );
16986int __ovld sub_group_clustered_reduce_mul(
int value,
uint clustersize );
16988long __ovld sub_group_clustered_reduce_mul(
long value,
uint clustersize );
16990float __ovld sub_group_clustered_reduce_mul(
float value,
uint clustersize );
16992char __ovld sub_group_clustered_reduce_min(
char value,
uint clustersize );
16994short __ovld sub_group_clustered_reduce_min(
short value,
uint clustersize );
16996int __ovld sub_group_clustered_reduce_min(
int value,
uint clustersize );
16998long __ovld sub_group_clustered_reduce_min(
long value,
uint clustersize );
17000float __ovld sub_group_clustered_reduce_min(
float value,
uint clustersize );
17002char __ovld sub_group_clustered_reduce_max(
char value,
uint clustersize );
17004short __ovld sub_group_clustered_reduce_max(
short value,
uint clustersize );
17006int __ovld sub_group_clustered_reduce_max(
int value,
uint clustersize );
17008long __ovld sub_group_clustered_reduce_max(
long value,
uint clustersize );
17010float __ovld sub_group_clustered_reduce_max(
float value,
uint clustersize );
17012char __ovld sub_group_clustered_reduce_and(
char value,
uint clustersize );
17014short __ovld sub_group_clustered_reduce_and(
short value,
uint clustersize );
17016int __ovld sub_group_clustered_reduce_and(
int value,
uint clustersize );
17018long __ovld sub_group_clustered_reduce_and(
long value,
uint clustersize );
17021char __ovld sub_group_clustered_reduce_or(
char value,
uint clustersize );
17023short __ovld sub_group_clustered_reduce_or(
short value,
uint clustersize );
17025int __ovld sub_group_clustered_reduce_or(
int value,
uint clustersize );
17027long __ovld sub_group_clustered_reduce_or(
long value,
uint clustersize );
17030char __ovld sub_group_clustered_reduce_xor(
char value,
uint clustersize );
17032short __ovld sub_group_clustered_reduce_xor(
short value,
uint clustersize );
17034int __ovld sub_group_clustered_reduce_xor(
int value,
uint clustersize );
17036long __ovld sub_group_clustered_reduce_xor(
long value,
uint clustersize );
17039int __ovld sub_group_clustered_reduce_logical_and(
int predicate,
uint clustersize );
17040int __ovld sub_group_clustered_reduce_logical_or(
int predicate,
uint clustersize );
17041int __ovld sub_group_clustered_reduce_logical_xor(
int predicate,
uint clustersize );
17043#if defined(cl_khr_fp16)
17044half
__ovld sub_group_clustered_reduce_add( half value,
uint clustersize );
17045half
__ovld sub_group_clustered_reduce_mul( half value,
uint clustersize );
17046half
__ovld sub_group_clustered_reduce_min( half value,
uint clustersize );
17047half
__ovld sub_group_clustered_reduce_max( half value,
uint clustersize );
17050#if defined(cl_khr_fp64)
17051double __ovld sub_group_clustered_reduce_add(
double value,
uint clustersize );
17052double __ovld sub_group_clustered_reduce_mul(
double value,
uint clustersize );
17053double __ovld sub_group_clustered_reduce_min(
double value,
uint clustersize );
17054double __ovld sub_group_clustered_reduce_max(
double value,
uint clustersize );
17059#if defined(cl_khr_extended_bit_ops)
17259#if defined(__opencl_c_integer_dot_product_input_4x8bit)
17271#if defined(__opencl_c_integer_dot_product_input_4x8bit_packed)
17283#if defined(cl_khr_subgroup_rotate)
17293#if defined(cl_khr_fp64)
17296#if defined(cl_khr_fp16)
17309#if defined(cl_khr_fp64)
17312#if defined(cl_khr_fp16)
17317#if defined(cl_intel_subgroups)
17343float __ovld __conv intel_sub_group_shuffle_down(
float cur,
float next,
uint );
17344float2
__ovld __conv intel_sub_group_shuffle_down( float2 cur, float2 next,
uint );
17345float3
__ovld __conv intel_sub_group_shuffle_down( float3 cur, float3 next,
uint );
17346float4
__ovld __conv intel_sub_group_shuffle_down( float4 cur, float4 next,
uint );
17347float8
__ovld __conv intel_sub_group_shuffle_down( float8 cur, float8 next,
uint );
17348float16
__ovld __conv intel_sub_group_shuffle_down( float16 cur, float16 next,
uint );
17351int2
__ovld __conv intel_sub_group_shuffle_down( int2 cur, int2 next,
uint );
17352int3
__ovld __conv intel_sub_group_shuffle_down( int3 cur, int3 next,
uint );
17353int4
__ovld __conv intel_sub_group_shuffle_down( int4 cur, int4 next,
uint );
17354int8
__ovld __conv intel_sub_group_shuffle_down( int8 cur, int8 next,
uint );
17355int16
__ovld __conv intel_sub_group_shuffle_down( int16 cur, int16 next,
uint );
17358uint2
__ovld __conv intel_sub_group_shuffle_down( uint2 cur, uint2 next,
uint );
17359uint3
__ovld __conv intel_sub_group_shuffle_down( uint3 cur, uint3 next,
uint );
17360uint4
__ovld __conv intel_sub_group_shuffle_down( uint4 cur, uint4 next,
uint );
17361uint8
__ovld __conv intel_sub_group_shuffle_down( uint8 cur, uint8 next,
uint );
17362uint16
__ovld __conv intel_sub_group_shuffle_down( uint16 cur, uint16 next,
uint );
17364long __ovld __conv intel_sub_group_shuffle_down(
long prev,
long cur,
uint );
17367float __ovld __conv intel_sub_group_shuffle_up(
float prev,
float cur,
uint );
17368float2
__ovld __conv intel_sub_group_shuffle_up( float2 prev, float2 cur,
uint );
17369float3
__ovld __conv intel_sub_group_shuffle_up( float3 prev, float3 cur,
uint );
17370float4
__ovld __conv intel_sub_group_shuffle_up( float4 prev, float4 cur,
uint );
17371float8
__ovld __conv intel_sub_group_shuffle_up( float8 prev, float8 cur,
uint );
17372float16
__ovld __conv intel_sub_group_shuffle_up( float16 prev, float16 cur,
uint );
17375int2
__ovld __conv intel_sub_group_shuffle_up( int2 prev, int2 cur,
uint );
17376int3
__ovld __conv intel_sub_group_shuffle_up( int3 prev, int3 cur,
uint );
17377int4
__ovld __conv intel_sub_group_shuffle_up( int4 prev, int4 cur,
uint );
17378int8
__ovld __conv intel_sub_group_shuffle_up( int8 prev, int8 cur,
uint );
17379int16
__ovld __conv intel_sub_group_shuffle_up( int16 prev, int16 cur,
uint );
17382uint2
__ovld __conv intel_sub_group_shuffle_up( uint2 prev, uint2 cur,
uint );
17383uint3
__ovld __conv intel_sub_group_shuffle_up( uint3 prev, uint3 cur,
uint );
17384uint4
__ovld __conv intel_sub_group_shuffle_up( uint4 prev, uint4 cur,
uint );
17385uint8
__ovld __conv intel_sub_group_shuffle_up( uint8 prev, uint8 cur,
uint );
17386uint16
__ovld __conv intel_sub_group_shuffle_up( uint16 prev, uint16 cur,
uint );
17388long __ovld __conv intel_sub_group_shuffle_up(
long prev,
long cur,
uint );
17415#if defined(__opencl_c_images)
17417uint2
__ovld __conv intel_sub_group_block_read2(read_only image2d_t, int2);
17418uint4
__ovld __conv intel_sub_group_block_read4(read_only image2d_t, int2);
17419uint8
__ovld __conv intel_sub_group_block_read8(read_only image2d_t, int2);
17422#if defined(__opencl_c_read_write_images)
17424uint2
__ovld __conv intel_sub_group_block_read2(read_write image2d_t, int2);
17425uint4
__ovld __conv intel_sub_group_block_read4(read_write image2d_t, int2);
17426uint8
__ovld __conv intel_sub_group_block_read8(read_write image2d_t, int2);
17434#if defined(__opencl_c_images)
17435void __ovld __conv intel_sub_group_block_write(write_only image2d_t, int2,
uint);
17436void __ovld __conv intel_sub_group_block_write2(write_only image2d_t, int2, uint2);
17437void __ovld __conv intel_sub_group_block_write4(write_only image2d_t, int2, uint4);
17438void __ovld __conv intel_sub_group_block_write8(write_only image2d_t, int2, uint8);
17441#if defined(__opencl_c_read_write_images)
17442void __ovld __conv intel_sub_group_block_write(read_write image2d_t, int2,
uint);
17443void __ovld __conv intel_sub_group_block_write2(read_write image2d_t, int2, uint2);
17444void __ovld __conv intel_sub_group_block_write4(read_write image2d_t, int2, uint4);
17445void __ovld __conv intel_sub_group_block_write8(read_write image2d_t, int2, uint8);
17449void __ovld __conv intel_sub_group_block_write2( __global
uint* p, uint2 data );
17450void __ovld __conv intel_sub_group_block_write4( __global
uint* p, uint4 data );
17451void __ovld __conv intel_sub_group_block_write8( __global
uint* p, uint8 data );
17455half
__ovld __conv intel_sub_group_shuffle_down( half prev, half cur,
uint );
17456half
__ovld __conv intel_sub_group_shuffle_up( half prev, half cur,
uint );
17460#if defined(cl_khr_fp64)
17462double __ovld __conv intel_sub_group_shuffle_down(
double prev,
double cur,
uint );
17463double __ovld __conv intel_sub_group_shuffle_up(
double prev,
double cur,
uint );
17469#if defined(cl_intel_subgroups_short)
17470short __ovld __conv intel_sub_group_broadcast(
short ,
uint sub_group_local_id );
17471short2
__ovld __conv intel_sub_group_broadcast( short2,
uint sub_group_local_id );
17472short3
__ovld __conv intel_sub_group_broadcast( short3,
uint sub_group_local_id );
17473short4
__ovld __conv intel_sub_group_broadcast( short4,
uint sub_group_local_id );
17474short8
__ovld __conv intel_sub_group_broadcast( short8,
uint sub_group_local_id );
17477ushort2
__ovld __conv intel_sub_group_broadcast( ushort2,
uint sub_group_local_id );
17478ushort3
__ovld __conv intel_sub_group_broadcast( ushort3,
uint sub_group_local_id );
17479ushort4
__ovld __conv intel_sub_group_broadcast( ushort4,
uint sub_group_local_id );
17480ushort8
__ovld __conv intel_sub_group_broadcast( ushort8,
uint sub_group_local_id );
17496short __ovld __conv intel_sub_group_shuffle_down(
short cur,
short next,
uint );
17497short2
__ovld __conv intel_sub_group_shuffle_down( short2 cur, short2 next,
uint );
17498short3
__ovld __conv intel_sub_group_shuffle_down( short3 cur, short3 next,
uint );
17499short4
__ovld __conv intel_sub_group_shuffle_down( short4 cur, short4 next,
uint );
17500short8
__ovld __conv intel_sub_group_shuffle_down( short8 cur, short8 next,
uint );
17501short16
__ovld __conv intel_sub_group_shuffle_down( short16 cur, short16 next,
uint );
17504ushort2
__ovld __conv intel_sub_group_shuffle_down( ushort2 cur, ushort2 next,
uint );
17505ushort3
__ovld __conv intel_sub_group_shuffle_down( ushort3 cur, ushort3 next,
uint );
17506ushort4
__ovld __conv intel_sub_group_shuffle_down( ushort4 cur, ushort4 next,
uint );
17507ushort8
__ovld __conv intel_sub_group_shuffle_down( ushort8 cur, ushort8 next,
uint );
17508ushort16
__ovld __conv intel_sub_group_shuffle_down( ushort16 cur, ushort16 next,
uint );
17510short __ovld __conv intel_sub_group_shuffle_up(
short cur,
short next,
uint );
17511short2
__ovld __conv intel_sub_group_shuffle_up( short2 cur, short2 next,
uint );
17512short3
__ovld __conv intel_sub_group_shuffle_up( short3 cur, short3 next,
uint );
17513short4
__ovld __conv intel_sub_group_shuffle_up( short4 cur, short4 next,
uint );
17514short8
__ovld __conv intel_sub_group_shuffle_up( short8 cur, short8 next,
uint );
17515short16
__ovld __conv intel_sub_group_shuffle_up( short16 cur, short16 next,
uint );
17518ushort2
__ovld __conv intel_sub_group_shuffle_up( ushort2 cur, ushort2 next,
uint );
17519ushort3
__ovld __conv intel_sub_group_shuffle_up( ushort3 cur, ushort3 next,
uint );
17520ushort4
__ovld __conv intel_sub_group_shuffle_up( ushort4 cur, ushort4 next,
uint );
17521ushort8
__ovld __conv intel_sub_group_shuffle_up( ushort8 cur, ushort8 next,
uint );
17522ushort16
__ovld __conv intel_sub_group_shuffle_up( ushort16 cur, ushort16 next,
uint );
17538short __ovld __conv intel_sub_group_reduce_add(
short x );
17540short __ovld __conv intel_sub_group_reduce_min(
short x );
17542short __ovld __conv intel_sub_group_reduce_max(
short x );
17545short __ovld __conv intel_sub_group_scan_exclusive_add(
short x );
17547short __ovld __conv intel_sub_group_scan_exclusive_min(
short x );
17549short __ovld __conv intel_sub_group_scan_exclusive_max(
short x );
17552short __ovld __conv intel_sub_group_scan_inclusive_add(
short x );
17554short __ovld __conv intel_sub_group_scan_inclusive_min(
short x );
17556short __ovld __conv intel_sub_group_scan_inclusive_max(
short x );
17559#if defined(__opencl_c_images)
17560uint __ovld __conv intel_sub_group_block_read_ui(read_only image2d_t, int2);
17561uint2
__ovld __conv intel_sub_group_block_read_ui2(read_only image2d_t, int2);
17562uint4
__ovld __conv intel_sub_group_block_read_ui4(read_only image2d_t, int2);
17563uint8
__ovld __conv intel_sub_group_block_read_ui8(read_only image2d_t, int2);
17566#if defined(__opencl_c_read_write_images)
17567uint __ovld __conv intel_sub_group_block_read_ui(read_write image2d_t, int2);
17568uint2
__ovld __conv intel_sub_group_block_read_ui2(read_write image2d_t, int2);
17569uint4
__ovld __conv intel_sub_group_block_read_ui4(read_write image2d_t, int2);
17570uint8
__ovld __conv intel_sub_group_block_read_ui8(read_write image2d_t, int2);
17574uint2
__ovld __conv intel_sub_group_block_read_ui2(
const __global
uint* p );
17575uint4
__ovld __conv intel_sub_group_block_read_ui4(
const __global
uint* p );
17576uint8
__ovld __conv intel_sub_group_block_read_ui8(
const __global
uint* p );
17578#if defined(__opencl_c_images)
17579void __ovld __conv intel_sub_group_block_write_ui(read_only image2d_t, int2,
uint);
17580void __ovld __conv intel_sub_group_block_write_ui2(read_only image2d_t, int2, uint2);
17581void __ovld __conv intel_sub_group_block_write_ui4(read_only image2d_t, int2, uint4);
17582void __ovld __conv intel_sub_group_block_write_ui8(read_only image2d_t, int2, uint8);
17585#if defined(__opencl_c_read_write_images)
17586void __ovld __conv intel_sub_group_block_write_ui(read_write image2d_t, int2,
uint);
17587void __ovld __conv intel_sub_group_block_write_ui2(read_write image2d_t, int2, uint2);
17588void __ovld __conv intel_sub_group_block_write_ui4(read_write image2d_t, int2, uint4);
17589void __ovld __conv intel_sub_group_block_write_ui8(read_write image2d_t, int2, uint8);
17593void __ovld __conv intel_sub_group_block_write_ui2( __global
uint* p, uint2 data );
17594void __ovld __conv intel_sub_group_block_write_ui4( __global
uint* p, uint4 data );
17595void __ovld __conv intel_sub_group_block_write_ui8( __global
uint* p, uint8 data );
17597#if defined(__opencl_c_images)
17599ushort2
__ovld __conv intel_sub_group_block_read_us2(read_only image2d_t, int2);
17600ushort4
__ovld __conv intel_sub_group_block_read_us4(read_only image2d_t, int2);
17601ushort8
__ovld __conv intel_sub_group_block_read_us8(read_only image2d_t, int2);
17604#if defined(__opencl_c_read_write_images)
17606ushort2
__ovld __conv intel_sub_group_block_read_us2(read_write image2d_t, int2);
17607ushort4
__ovld __conv intel_sub_group_block_read_us4(read_write image2d_t, int2);
17608ushort8
__ovld __conv intel_sub_group_block_read_us8(read_write image2d_t, int2);
17616#if defined(__opencl_c_images)
17617void __ovld __conv intel_sub_group_block_write_us(write_only image2d_t, int2,
ushort);
17618void __ovld __conv intel_sub_group_block_write_us2(write_only image2d_t, int2, ushort2);
17619void __ovld __conv intel_sub_group_block_write_us4(write_only image2d_t, int2, ushort4);
17620void __ovld __conv intel_sub_group_block_write_us8(write_only image2d_t, int2, ushort8);
17623#if defined(__opencl_c_read_write_images)
17624void __ovld __conv intel_sub_group_block_write_us(read_write image2d_t, int2,
ushort);
17625void __ovld __conv intel_sub_group_block_write_us2(read_write image2d_t, int2, ushort2);
17626void __ovld __conv intel_sub_group_block_write_us4(read_write image2d_t, int2, ushort4);
17627void __ovld __conv intel_sub_group_block_write_us8(read_write image2d_t, int2, ushort8);
17631void __ovld __conv intel_sub_group_block_write_us2( __global
ushort* p, ushort2 data );
17632void __ovld __conv intel_sub_group_block_write_us4( __global
ushort* p, ushort4 data );
17633void __ovld __conv intel_sub_group_block_write_us8( __global
ushort* p, ushort8 data );
17636#ifdef cl_intel_device_side_avc_motion_estimation
17637#pragma OPENCL EXTENSION cl_intel_device_side_avc_motion_estimation : begin
17641intel_sub_group_avc_mce_get_default_inter_base_multi_reference_penalty(
17643ulong __ovld intel_sub_group_avc_mce_get_default_inter_shape_penalty(
17645uchar __ovld intel_sub_group_avc_mce_get_default_inter_direction_penalty(
17647uint __ovld intel_sub_group_avc_mce_get_default_intra_luma_shape_penalty(
17650intel_sub_group_avc_mce_get_default_inter_motion_vector_cost_table(
17652uchar __ovld intel_sub_group_avc_mce_get_default_intra_luma_mode_penalty(
17655uint2
__ovld intel_sub_group_avc_mce_get_default_high_penalty_cost_table();
17656uint2
__ovld intel_sub_group_avc_mce_get_default_medium_penalty_cost_table();
17657uint2
__ovld intel_sub_group_avc_mce_get_default_low_penalty_cost_table();
17658uint __ovld intel_sub_group_avc_mce_get_default_non_dc_luma_intra_penalty();
17660intel_sub_group_avc_mce_get_default_intra_chroma_mode_base_penalty();
17662intel_sub_group_avc_mce_payload_t
__ovld
17663intel_sub_group_avc_mce_set_inter_base_multi_reference_penalty(
17664 uchar reference_base_penalty, intel_sub_group_avc_mce_payload_t payload);
17665intel_sub_group_avc_mce_payload_t
__ovld
17666intel_sub_group_avc_mce_set_inter_shape_penalty(
17667 ulong packed_shape_penalty, intel_sub_group_avc_mce_payload_t payload);
17668intel_sub_group_avc_mce_payload_t
__ovld
17669intel_sub_group_avc_mce_set_inter_direction_penalty(
17670 uchar direction_cost, intel_sub_group_avc_mce_payload_t payload);
17671intel_sub_group_avc_mce_payload_t
__ovld
17672intel_sub_group_avc_mce_set_motion_vector_cost_function(
17673 ulong packed_cost_center_delta, uint2 packed_cost_table,
17674 uchar cost_precision, intel_sub_group_avc_mce_payload_t payload);
17675intel_sub_group_avc_mce_payload_t
__ovld
17676intel_sub_group_avc_mce_set_ac_only_haar(
17677 intel_sub_group_avc_mce_payload_t payload);
17678intel_sub_group_avc_mce_payload_t
__ovld
17679intel_sub_group_avc_mce_set_source_interlaced_field_polarity(
17680 uchar src_field_polarity, intel_sub_group_avc_mce_payload_t payload);
17681intel_sub_group_avc_mce_payload_t
__ovld
17682intel_sub_group_avc_mce_set_single_reference_interlaced_field_polarity(
17683 uchar ref_field_polarity, intel_sub_group_avc_mce_payload_t payload);
17684intel_sub_group_avc_mce_payload_t
__ovld
17685intel_sub_group_avc_mce_set_dual_reference_interlaced_field_polarities(
17686 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
17687 intel_sub_group_avc_mce_payload_t payload);
17689ulong __ovld intel_sub_group_avc_mce_get_motion_vectors(
17690 intel_sub_group_avc_mce_result_t result);
17691ushort __ovld intel_sub_group_avc_mce_get_inter_distortions(
17692 intel_sub_group_avc_mce_result_t result);
17693ushort __ovld intel_sub_group_avc_mce_get_best_inter_distortion(
17694 intel_sub_group_avc_mce_result_t result);
17695uchar __ovld intel_sub_group_avc_mce_get_inter_major_shape(
17696 intel_sub_group_avc_mce_result_t result);
17697uchar __ovld intel_sub_group_avc_mce_get_inter_minor_shapes(
17698 intel_sub_group_avc_mce_result_t result);
17699uchar __ovld intel_sub_group_avc_mce_get_inter_directions(
17700 intel_sub_group_avc_mce_result_t result);
17701uchar __ovld intel_sub_group_avc_mce_get_inter_motion_vector_count(
17702 intel_sub_group_avc_mce_result_t result);
17703uint __ovld intel_sub_group_avc_mce_get_inter_reference_ids(
17704 intel_sub_group_avc_mce_result_t result);
17706intel_sub_group_avc_mce_get_inter_reference_interlaced_field_polarities(
17707 uint packed_reference_ids,
uint packed_reference_parameter_field_polarities,
17708 intel_sub_group_avc_mce_result_t result);
17711intel_sub_group_avc_ime_payload_t
__ovld
17712intel_sub_group_avc_ime_initialize(
17713 ushort2 src_coord,
uchar partition_mask,
uchar sad_adjustment);
17714intel_sub_group_avc_ime_payload_t
__ovld
17715intel_sub_group_avc_ime_set_single_reference(
17716 short2 ref_offset,
uchar search_window_config,
17717 intel_sub_group_avc_ime_payload_t payload);
17718intel_sub_group_avc_ime_payload_t
__ovld
17719intel_sub_group_avc_ime_set_dual_reference(
17720 short2 fwd_ref_offset, short2 bwd_ref_offset,
uchar search_window_config,
17721 intel_sub_group_avc_ime_payload_t payload);
17722intel_sub_group_avc_ime_payload_t
__ovld
17723intel_sub_group_avc_ime_set_max_motion_vector_count(
17724 uchar max_motion_vector_count, intel_sub_group_avc_ime_payload_t payload);
17725intel_sub_group_avc_ime_payload_t
__ovld
17726intel_sub_group_avc_ime_set_unidirectional_mix_disable(
17727 intel_sub_group_avc_ime_payload_t payload);
17728intel_sub_group_avc_ime_payload_t
__ovld
17729intel_sub_group_avc_ime_set_early_search_termination_threshold(
17730 uchar threshold, intel_sub_group_avc_ime_payload_t payload);
17731intel_sub_group_avc_ime_payload_t
__ovld
17732intel_sub_group_avc_ime_set_weighted_sad(
17733 uint packed_sad_weights, intel_sub_group_avc_ime_payload_t payload);
17735__attribute__((deprecated(
"If you use the latest Intel driver, please use "
17736 "intel_sub_group_avc_ime_ref_window_size instead",
17737 "intel_sub_group_avc_ime_ref_window_size")))
17739intel_sub_group_ime_ref_window_size(
uchar search_window_config,
char dual_ref);
17740ushort2
__ovld intel_sub_group_avc_ime_ref_window_size(
17741 uchar search_window_config,
char dual_ref);
17742short2
__ovld intel_sub_group_avc_ime_adjust_ref_offset(
17743 short2 ref_offset, ushort2 src_coord, ushort2 ref_window_size,
17744 ushort2 image_size);
17746#if defined(__opencl_c_images)
17747intel_sub_group_avc_ime_result_t
__ovld
17748intel_sub_group_avc_ime_evaluate_with_single_reference(
17749 read_only image2d_t src_image, read_only image2d_t ref_image,
17750 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload);
17751intel_sub_group_avc_ime_result_t
__ovld
17752intel_sub_group_avc_ime_evaluate_with_dual_reference(
17753 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17754 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17755 intel_sub_group_avc_ime_payload_t payload);
17756intel_sub_group_avc_ime_result_single_reference_streamout_t
__ovld
17757intel_sub_group_avc_ime_evaluate_with_single_reference_streamout(
17758 read_only image2d_t src_image, read_only image2d_t ref_image,
17759 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload);
17760intel_sub_group_avc_ime_result_dual_reference_streamout_t
__ovld
17761intel_sub_group_avc_ime_evaluate_with_dual_reference_streamout(
17762 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17763 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17764 intel_sub_group_avc_ime_payload_t payload);
17765intel_sub_group_avc_ime_result_t
__ovld
17766intel_sub_group_avc_ime_evaluate_with_single_reference_streamin(
17767 read_only image2d_t src_image, read_only image2d_t ref_image,
17768 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload,
17769 intel_sub_group_avc_ime_single_reference_streamin_t streamin_components);
17770intel_sub_group_avc_ime_result_t
__ovld
17771intel_sub_group_avc_ime_evaluate_with_dual_reference_streamin(
17772 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17773 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17774 intel_sub_group_avc_ime_payload_t payload,
17775 intel_sub_group_avc_ime_dual_reference_streamin_t streamin_components);
17776intel_sub_group_avc_ime_result_single_reference_streamout_t
__ovld
17777intel_sub_group_avc_ime_evaluate_with_single_reference_streaminout(
17778 read_only image2d_t src_image, read_only image2d_t ref_image,
17779 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload,
17780 intel_sub_group_avc_ime_single_reference_streamin_t streamin_components);
17781intel_sub_group_avc_ime_result_dual_reference_streamout_t
__ovld
17782intel_sub_group_avc_ime_evaluate_with_dual_reference_streaminout(
17783 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17784 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17785 intel_sub_group_avc_ime_payload_t payload,
17786 intel_sub_group_avc_ime_dual_reference_streamin_t streamin_components);
17789intel_sub_group_avc_ime_single_reference_streamin_t
__ovld
17790intel_sub_group_avc_ime_get_single_reference_streamin(
17791 intel_sub_group_avc_ime_result_single_reference_streamout_t result);
17792intel_sub_group_avc_ime_dual_reference_streamin_t
__ovld
17793intel_sub_group_avc_ime_get_dual_reference_streamin(
17794 intel_sub_group_avc_ime_result_dual_reference_streamout_t result);
17795intel_sub_group_avc_ime_result_t
__ovld
17796intel_sub_group_avc_ime_strip_single_reference_streamout(
17797 intel_sub_group_avc_ime_result_single_reference_streamout_t result);
17798intel_sub_group_avc_ime_result_t
__ovld
17799intel_sub_group_avc_ime_strip_dual_reference_streamout(
17800 intel_sub_group_avc_ime_result_dual_reference_streamout_t result);
17802uint __ovld intel_sub_group_avc_ime_get_streamout_major_shape_motion_vectors(
17803 intel_sub_group_avc_ime_result_single_reference_streamout_t result,
17804 uchar major_shape);
17805ushort __ovld intel_sub_group_avc_ime_get_streamout_major_shape_distortions(
17806 intel_sub_group_avc_ime_result_single_reference_streamout_t result,
17807 uchar major_shape);
17808uchar __ovld intel_sub_group_avc_ime_get_streamout_major_shape_reference_ids(
17809 intel_sub_group_avc_ime_result_single_reference_streamout_t result,
17810 uchar major_shape);
17811uint __ovld intel_sub_group_avc_ime_get_streamout_major_shape_motion_vectors(
17812 intel_sub_group_avc_ime_result_dual_reference_streamout_t result,
17814ushort __ovld intel_sub_group_avc_ime_get_streamout_major_shape_distortions(
17815 intel_sub_group_avc_ime_result_dual_reference_streamout_t result,
17817uchar __ovld intel_sub_group_avc_ime_get_streamout_major_shape_reference_ids(
17818 intel_sub_group_avc_ime_result_dual_reference_streamout_t result,
17821uchar __ovld intel_sub_group_avc_ime_get_border_reached(
17822 uchar image_select, intel_sub_group_avc_ime_result_t result);
17823uchar __ovld intel_sub_group_avc_ime_get_truncated_search_indication(
17824 intel_sub_group_avc_ime_result_t result);
17826intel_sub_group_avc_ime_get_unidirectional_early_search_termination(
17827 intel_sub_group_avc_ime_result_t result);
17828uint __ovld intel_sub_group_avc_ime_get_weighting_pattern_minimum_motion_vector(
17829 intel_sub_group_avc_ime_result_t result);
17830ushort __ovld intel_sub_group_avc_ime_get_weighting_pattern_minimum_distortion(
17831 intel_sub_group_avc_ime_result_t result);
17834intel_sub_group_avc_ref_payload_t
__ovld
17835intel_sub_group_avc_fme_initialize(
17836 ushort2 src_coord,
ulong motion_vectors,
uchar major_shapes,
17838 uchar sad_adjustment);
17839intel_sub_group_avc_ref_payload_t
__ovld
17840intel_sub_group_avc_bme_initialize(
17841 ushort2 src_coord,
ulong motion_vectors,
uchar major_shapes,
17843 uchar bidirectional_weight,
uchar sad_adjustment);
17845intel_sub_group_avc_ref_payload_t
__ovld
17846intel_sub_group_avc_ref_set_bidirectional_mix_disable(
17847 intel_sub_group_avc_ref_payload_t payload);
17848intel_sub_group_avc_ref_payload_t
__ovld
17849intel_sub_group_avc_ref_set_bilinear_filter_enable(
17850 intel_sub_group_avc_ref_payload_t payload);
17852#if defined(__opencl_c_images)
17853intel_sub_group_avc_ref_result_t
__ovld
17854intel_sub_group_avc_ref_evaluate_with_single_reference(
17855 read_only image2d_t src_image, read_only image2d_t ref_image,
17856 sampler_t vme_media_sampler, intel_sub_group_avc_ref_payload_t payload);
17857intel_sub_group_avc_ref_result_t
__ovld
17858intel_sub_group_avc_ref_evaluate_with_dual_reference(
17859 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17860 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17861 intel_sub_group_avc_ref_payload_t payload);
17862intel_sub_group_avc_ref_result_t
__ovld
17863intel_sub_group_avc_ref_evaluate_with_multi_reference(
17864 read_only image2d_t src_image,
uint packed_reference_ids,
17865 sampler_t vme_media_sampler, intel_sub_group_avc_ref_payload_t payload);
17866intel_sub_group_avc_ref_result_t
__ovld
17867intel_sub_group_avc_ref_evaluate_with_multi_reference(
17868 read_only image2d_t src_image,
uint packed_reference_ids,
17869 uchar packed_reference_field_polarities, sampler_t vme_media_sampler,
17870 intel_sub_group_avc_ref_payload_t payload);
17874intel_sub_group_avc_sic_payload_t
__ovld
17875intel_sub_group_avc_sic_initialize(
17876 ushort2 src_coord);
17877intel_sub_group_avc_sic_payload_t
__ovld
17878intel_sub_group_avc_sic_configure_skc(
17879 uint skip_block_partition_type,
uint skip_motion_vector_mask,
17880 ulong motion_vectors,
uchar bidirectional_weight,
uchar skip_sad_adjustment,
17881 intel_sub_group_avc_sic_payload_t payload);
17882intel_sub_group_avc_sic_payload_t
__ovld intel_sub_group_avc_sic_configure_ipe(
17883 uchar luma_intra_partition_mask,
uchar intra_neighbour_availability,
17884 uchar left_edge_luma_pixels,
uchar upper_left_corner_luma_pixel,
17885 uchar upper_edge_luma_pixels,
uchar upper_right_edge_luma_pixels,
17886 uchar intra_sad_adjustment, intel_sub_group_avc_sic_payload_t payload);
17887intel_sub_group_avc_sic_payload_t
__ovld intel_sub_group_avc_sic_configure_ipe(
17888 uchar luma_intra_partition_mask,
uchar intra_neighbour_availability,
17889 uchar left_edge_luma_pixels,
uchar upper_left_corner_luma_pixel,
17890 uchar upper_edge_luma_pixels,
uchar upper_right_edge_luma_pixels,
17891 ushort left_edge_chroma_pixels,
ushort upper_left_corner_chroma_pixel,
17892 ushort upper_edge_chroma_pixels,
uchar intra_sad_adjustment,
17893 intel_sub_group_avc_sic_payload_t payload);
17895intel_sub_group_avc_sic_get_motion_vector_mask(
17896 uint skip_block_partition_type,
uchar direction);
17898intel_sub_group_avc_sic_payload_t
__ovld
17899intel_sub_group_avc_sic_set_intra_luma_shape_penalty(
17900 uint packed_shape_cost, intel_sub_group_avc_sic_payload_t payload);
17901intel_sub_group_avc_sic_payload_t
__ovld
17902intel_sub_group_avc_sic_set_intra_luma_mode_cost_function(
17903 uchar luma_mode_penalty,
uint luma_packed_neighbor_modes,
17904 uint luma_packed_non_dc_penalty, intel_sub_group_avc_sic_payload_t payload);
17905intel_sub_group_avc_sic_payload_t
__ovld
17906intel_sub_group_avc_sic_set_intra_chroma_mode_cost_function(
17907 uchar chroma_mode_penalty, intel_sub_group_avc_sic_payload_t payload);
17909intel_sub_group_avc_sic_payload_t
__ovld
17910intel_sub_group_avc_sic_set_skc_bilinear_filter_enable(
17911 intel_sub_group_avc_sic_payload_t payload);
17912intel_sub_group_avc_sic_payload_t
__ovld
17913intel_sub_group_avc_sic_set_skc_forward_transform_enable(
17914 ulong packed_sad_coefficients, intel_sub_group_avc_sic_payload_t payload);
17915intel_sub_group_avc_sic_payload_t
__ovld
17916intel_sub_group_avc_sic_set_block_based_raw_skip_sad(
17917 uchar block_based_skip_type,
17918 intel_sub_group_avc_sic_payload_t payload);
17920#if defined(__opencl_c_images)
17921intel_sub_group_avc_sic_result_t
__ovld
17922intel_sub_group_avc_sic_evaluate_ipe(
17923 read_only image2d_t src_image, sampler_t vme_media_sampler,
17924 intel_sub_group_avc_sic_payload_t payload);
17925intel_sub_group_avc_sic_result_t
__ovld
17926intel_sub_group_avc_sic_evaluate_with_single_reference(
17927 read_only image2d_t src_image, read_only image2d_t ref_image,
17928 sampler_t vme_media_sampler, intel_sub_group_avc_sic_payload_t payload);
17929intel_sub_group_avc_sic_result_t
__ovld
17930intel_sub_group_avc_sic_evaluate_with_dual_reference(
17931 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17932 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17933 intel_sub_group_avc_sic_payload_t payload);
17934intel_sub_group_avc_sic_result_t
__ovld
17935intel_sub_group_avc_sic_evaluate_with_multi_reference(
17936 read_only image2d_t src_image,
uint packed_reference_ids,
17937 sampler_t vme_media_sampler, intel_sub_group_avc_sic_payload_t payload);
17938intel_sub_group_avc_sic_result_t
__ovld
17939intel_sub_group_avc_sic_evaluate_with_multi_reference(
17940 read_only image2d_t src_image,
uint packed_reference_ids,
17941 uchar packed_reference_field_polarities, sampler_t vme_media_sampler,
17942 intel_sub_group_avc_sic_payload_t payload);
17945uchar __ovld intel_sub_group_avc_sic_get_ipe_luma_shape(
17946 intel_sub_group_avc_sic_result_t result);
17947ushort __ovld intel_sub_group_avc_sic_get_best_ipe_luma_distortion(
17948 intel_sub_group_avc_sic_result_t result);
17949ushort __ovld intel_sub_group_avc_sic_get_best_ipe_chroma_distortion(
17950 intel_sub_group_avc_sic_result_t result);
17951ulong __ovld intel_sub_group_avc_sic_get_packed_ipe_luma_modes(
17952 intel_sub_group_avc_sic_result_t result);
17953uchar __ovld intel_sub_group_avc_sic_get_ipe_chroma_mode(
17954 intel_sub_group_avc_sic_result_t result);
17955uint __ovld intel_sub_group_avc_sic_get_packed_skc_luma_count_threshold(
17956 intel_sub_group_avc_sic_result_t result);
17957ulong __ovld intel_sub_group_avc_sic_get_packed_skc_luma_sum_threshold(
17958 intel_sub_group_avc_sic_result_t result);
17959ushort __ovld intel_sub_group_avc_sic_get_inter_raw_sads(
17960 intel_sub_group_avc_sic_result_t result);
17963intel_sub_group_avc_ime_payload_t
__ovld
17964intel_sub_group_avc_ime_set_inter_base_multi_reference_penalty(
17965 uchar reference_base_penalty, intel_sub_group_avc_ime_payload_t payload);
17966intel_sub_group_avc_ref_payload_t
__ovld
17967intel_sub_group_avc_ref_set_inter_base_multi_reference_penalty(
17968 uchar reference_base_penalty, intel_sub_group_avc_ref_payload_t payload);
17969intel_sub_group_avc_sic_payload_t
__ovld
17970intel_sub_group_avc_sic_set_inter_base_multi_reference_penalty(
17971 uchar reference_base_penalty, intel_sub_group_avc_sic_payload_t payload);
17973intel_sub_group_avc_ime_payload_t
__ovld
17974intel_sub_group_avc_ime_set_inter_shape_penalty(
17975 ulong packed_shape_cost, intel_sub_group_avc_ime_payload_t payload);
17976intel_sub_group_avc_ref_payload_t
__ovld
17977intel_sub_group_avc_ref_set_inter_shape_penalty(
17978 ulong packed_shape_cost, intel_sub_group_avc_ref_payload_t payload);
17979intel_sub_group_avc_sic_payload_t
__ovld
17980intel_sub_group_avc_sic_set_inter_shape_penalty(
17981 ulong packed_shape_cost, intel_sub_group_avc_sic_payload_t payload);
17983intel_sub_group_avc_ime_payload_t
__ovld
17984intel_sub_group_avc_ime_set_inter_direction_penalty(
17985 uchar direction_cost, intel_sub_group_avc_ime_payload_t payload);
17986intel_sub_group_avc_ref_payload_t
__ovld
17987intel_sub_group_avc_ref_set_inter_direction_penalty(
17988 uchar direction_cost, intel_sub_group_avc_ref_payload_t payload);
17989intel_sub_group_avc_sic_payload_t
__ovld
17990intel_sub_group_avc_sic_set_inter_direction_penalty(
17991 uchar direction_cost, intel_sub_group_avc_sic_payload_t payload);
17993intel_sub_group_avc_ime_payload_t
__ovld
17994intel_sub_group_avc_ime_set_motion_vector_cost_function(
17995 ulong packed_cost_center_delta, uint2 packed_cost_table,
17996 uchar cost_precision, intel_sub_group_avc_ime_payload_t payload);
17997intel_sub_group_avc_ref_payload_t
__ovld
17998intel_sub_group_avc_ref_set_motion_vector_cost_function(
17999 ulong packed_cost_center_delta, uint2 packed_cost_table,
18000 uchar cost_precision, intel_sub_group_avc_ref_payload_t payload);
18001intel_sub_group_avc_sic_payload_t
__ovld
18002intel_sub_group_avc_sic_set_motion_vector_cost_function(
18003 ulong packed_cost_center_delta, uint2 packed_cost_table,
18004 uchar cost_precision, intel_sub_group_avc_sic_payload_t payload);
18006intel_sub_group_avc_ime_payload_t
__ovld
18007intel_sub_group_avc_ime_set_source_interlaced_field_polarity(
18008 uchar src_field_polarity, intel_sub_group_avc_ime_payload_t payload);
18009intel_sub_group_avc_ref_payload_t
__ovld
18010intel_sub_group_avc_ref_set_source_interlaced_field_polarity(
18011 uchar src_field_polarity, intel_sub_group_avc_ref_payload_t payload);
18012intel_sub_group_avc_sic_payload_t
__ovld
18013intel_sub_group_avc_sic_set_source_interlaced_field_polarity(
18014 uchar src_field_polarity, intel_sub_group_avc_sic_payload_t payload);
18016intel_sub_group_avc_ime_payload_t
__ovld
18017intel_sub_group_avc_ime_set_single_reference_interlaced_field_polarity(
18018 uchar ref_field_polarity, intel_sub_group_avc_ime_payload_t payload);
18019intel_sub_group_avc_ref_payload_t
__ovld
18020intel_sub_group_avc_ref_set_single_reference_interlaced_field_polarity(
18021 uchar ref_field_polarity, intel_sub_group_avc_ref_payload_t payload);
18022intel_sub_group_avc_sic_payload_t
__ovld
18023intel_sub_group_avc_sic_set_single_reference_interlaced_field_polarity(
18024 uchar ref_field_polarity, intel_sub_group_avc_sic_payload_t payload);
18025intel_sub_group_avc_ime_payload_t
__ovld
18026intel_sub_group_avc_ime_set_dual_reference_interlaced_field_polarities(
18027 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
18028 intel_sub_group_avc_ime_payload_t payload);
18029intel_sub_group_avc_ref_payload_t
__ovld
18030intel_sub_group_avc_ref_set_dual_reference_interlaced_field_polarities(
18031 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
18032 intel_sub_group_avc_ref_payload_t payload);
18033intel_sub_group_avc_sic_payload_t
__ovld
18034intel_sub_group_avc_sic_set_dual_reference_interlaced_field_polarities(
18035 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
18036 intel_sub_group_avc_sic_payload_t payload);
18038intel_sub_group_avc_ime_payload_t
__ovld
18039intel_sub_group_avc_ime_set_ac_only_haar(
18040 intel_sub_group_avc_ime_payload_t payload);
18041intel_sub_group_avc_ref_payload_t
__ovld
18042intel_sub_group_avc_ref_set_ac_only_haar(
18043 intel_sub_group_avc_ref_payload_t payload);
18044intel_sub_group_avc_sic_payload_t
__ovld
18045intel_sub_group_avc_sic_set_ac_only_haar(
18046 intel_sub_group_avc_sic_payload_t payload);
18048ulong __ovld intel_sub_group_avc_ime_get_motion_vectors(
18049 intel_sub_group_avc_ime_result_t result);
18050ulong __ovld intel_sub_group_avc_ref_get_motion_vectors(
18051 intel_sub_group_avc_ref_result_t result);
18053ushort __ovld intel_sub_group_avc_ime_get_inter_distortions(
18054 intel_sub_group_avc_ime_result_t result);
18055ushort __ovld intel_sub_group_avc_ref_get_inter_distortions(
18056 intel_sub_group_avc_ref_result_t result);
18057ushort __ovld intel_sub_group_avc_sic_get_inter_distortions(
18058 intel_sub_group_avc_sic_result_t result);
18060ushort __ovld intel_sub_group_avc_ime_get_best_inter_distortion(
18061 intel_sub_group_avc_ime_result_t result);
18062ushort __ovld intel_sub_group_avc_ref_get_best_inter_distortion(
18063 intel_sub_group_avc_ref_result_t result);
18065uchar __ovld intel_sub_group_avc_ime_get_inter_major_shape(
18066 intel_sub_group_avc_ime_result_t result);
18067uchar __ovld intel_sub_group_avc_ref_get_inter_major_shape(
18068 intel_sub_group_avc_ref_result_t result);
18069uchar __ovld intel_sub_group_avc_ime_get_inter_minor_shapes(
18070 intel_sub_group_avc_ime_result_t result);
18071uchar __ovld intel_sub_group_avc_ref_get_inter_minor_shapes(
18072 intel_sub_group_avc_ref_result_t result);
18074uchar __ovld intel_sub_group_avc_ime_get_inter_directions(
18075 intel_sub_group_avc_ime_result_t result);
18076uchar __ovld intel_sub_group_avc_ref_get_inter_directions(
18077 intel_sub_group_avc_ref_result_t result);
18079uchar __ovld intel_sub_group_avc_ime_get_inter_motion_vector_count(
18080 intel_sub_group_avc_ime_result_t result);
18081uchar __ovld intel_sub_group_avc_ref_get_inter_motion_vector_count(
18082 intel_sub_group_avc_ref_result_t result);
18084uint __ovld intel_sub_group_avc_ime_get_inter_reference_ids(
18085 intel_sub_group_avc_ime_result_t result);
18086uint __ovld intel_sub_group_avc_ref_get_inter_reference_ids(
18087 intel_sub_group_avc_ref_result_t result);
18090intel_sub_group_avc_ime_get_inter_reference_interlaced_field_polarities(
18091 uint packed_reference_ids,
uint packed_reference_parameter_field_polarities,
18092 intel_sub_group_avc_ime_result_t result);
18094intel_sub_group_avc_ref_get_inter_reference_interlaced_field_polarities(
18095 uint packed_reference_ids,
uint packed_reference_parameter_field_polarities,
18096 intel_sub_group_avc_ref_result_t result);
18099intel_sub_group_avc_mce_payload_t
__ovld
18100intel_sub_group_avc_ime_convert_to_mce_payload(
18101 intel_sub_group_avc_ime_payload_t payload);
18102intel_sub_group_avc_ime_payload_t
__ovld
18103intel_sub_group_avc_mce_convert_to_ime_payload(
18104 intel_sub_group_avc_mce_payload_t payload);
18105intel_sub_group_avc_mce_payload_t
__ovld
18106intel_sub_group_avc_ref_convert_to_mce_payload(
18107 intel_sub_group_avc_ref_payload_t payload);
18108intel_sub_group_avc_ref_payload_t
__ovld
18109intel_sub_group_avc_mce_convert_to_ref_payload(
18110 intel_sub_group_avc_mce_payload_t payload);
18111intel_sub_group_avc_mce_payload_t
__ovld
18112intel_sub_group_avc_sic_convert_to_mce_payload(
18113 intel_sub_group_avc_sic_payload_t payload);
18114intel_sub_group_avc_sic_payload_t
__ovld
18115intel_sub_group_avc_mce_convert_to_sic_payload(
18116 intel_sub_group_avc_mce_payload_t payload);
18118intel_sub_group_avc_mce_result_t
__ovld
18119intel_sub_group_avc_ime_convert_to_mce_result(
18120 intel_sub_group_avc_ime_result_t result);
18121intel_sub_group_avc_ime_result_t
__ovld
18122intel_sub_group_avc_mce_convert_to_ime_result(
18123 intel_sub_group_avc_mce_result_t result);
18124intel_sub_group_avc_mce_result_t
__ovld
18125intel_sub_group_avc_ref_convert_to_mce_result(
18126 intel_sub_group_avc_ref_result_t result);
18127intel_sub_group_avc_ref_result_t
__ovld
18128intel_sub_group_avc_mce_convert_to_ref_result(
18129 intel_sub_group_avc_mce_result_t result);
18130intel_sub_group_avc_mce_result_t
__ovld
18131intel_sub_group_avc_sic_convert_to_mce_result(
18132 intel_sub_group_avc_sic_result_t result);
18133intel_sub_group_avc_sic_result_t
__ovld
18134intel_sub_group_avc_mce_convert_to_sic_result(
18135 intel_sub_group_avc_mce_result_t result);
18136#pragma OPENCL EXTENSION cl_intel_device_side_avc_motion_estimation : end
18139#ifdef cl_amd_media_ops
18141uint2
__ovld amd_bitalign(uint2, uint2, uint2);
18142uint3
__ovld amd_bitalign(uint3, uint3, uint3);
18143uint4
__ovld amd_bitalign(uint4, uint4, uint4);
18144uint8
__ovld amd_bitalign(uint8, uint8, uint8);
18145uint16
__ovld amd_bitalign(uint16, uint16, uint16);
18148uint2
__ovld amd_bytealign(uint2, uint2, uint2);
18149uint3
__ovld amd_bytealign(uint3, uint3, uint3);
18150uint4
__ovld amd_bytealign(uint4, uint4, uint4);
18151uint8
__ovld amd_bytealign(uint8, uint8, uint8);
18152uint16
__ovld amd_bytealign(uint16, uint16, uint16);
18155uint2
__ovld amd_lerp(uint2, uint2, uint2);
18156uint3
__ovld amd_lerp(uint3, uint3, uint3);
18157uint4
__ovld amd_lerp(uint4, uint4, uint4);
18158uint8
__ovld amd_lerp(uint8, uint8, uint8);
18159uint16
__ovld amd_lerp(uint16, uint16, uint16);
18166uint2
__ovld amd_sadhi(uint2, uint2, uint2);
18167uint3
__ovld amd_sadhi(uint3, uint3, uint3);
18168uint4
__ovld amd_sadhi(uint4, uint4, uint4);
18169uint8
__ovld amd_sadhi(uint8, uint8, uint8);
18170uint16
__ovld amd_sadhi(uint16, uint16, uint16);
18173uint2
__ovld amd_sad(uint2, uint2, uint2);
18174uint3
__ovld amd_sad(uint3, uint3, uint3);
18175uint4
__ovld amd_sad(uint4, uint4, uint4);
18176uint8
__ovld amd_sad(uint8, uint8, uint8);
18177uint16
__ovld amd_sad(uint16, uint16, uint16);
18180float2
__ovld amd_unpack0(uint2);
18181float3
__ovld amd_unpack0(uint3);
18182float4
__ovld amd_unpack0(uint4);
18183float8
__ovld amd_unpack0(uint8);
18184float16
__ovld amd_unpack0(uint16);
18187float2
__ovld amd_unpack1(uint2);
18188float3
__ovld amd_unpack1(uint3);
18189float4
__ovld amd_unpack1(uint4);
18190float8
__ovld amd_unpack1(uint8);
18191float16
__ovld amd_unpack1(uint16);
18194float2
__ovld amd_unpack2(uint2);
18195float3
__ovld amd_unpack2(uint3);
18196float4
__ovld amd_unpack2(uint4);
18197float8
__ovld amd_unpack2(uint8);
18198float16
__ovld amd_unpack2(uint16);
18201float2
__ovld amd_unpack3(uint2);
18202float3
__ovld amd_unpack3(uint3);
18203float4
__ovld amd_unpack3(uint4);
18204float8
__ovld amd_unpack3(uint8);
18205float16
__ovld amd_unpack3(uint16);
18208#ifdef cl_amd_media_ops2
18210int2
__ovld amd_bfe(int2 src0, uint2 src1, uint2 src2);
18211int3
__ovld amd_bfe(int3 src0, uint3 src1, uint3 src2);
18212int4
__ovld amd_bfe(int4 src0, uint4 src1, uint4 src2);
18213int8
__ovld amd_bfe(int8 src0, uint8 src1, uint8 src2);
18214int16
__ovld amd_bfe(int16 src0, uint16 src1, uint16 src2);
18217uint2
__ovld amd_bfe(uint2 src0, uint2 src1, uint2 src2);
18218uint3
__ovld amd_bfe(uint3 src0, uint3 src1, uint3 src2);
18219uint4
__ovld amd_bfe(uint4 src0, uint4 src1, uint4 src2);
18220uint8
__ovld amd_bfe(uint8 src0, uint8 src1, uint8 src2);
18221uint16
__ovld amd_bfe(uint16 src0, uint16 src1, uint16 src2);
18224uint2
__ovld amd_bfm(uint2 src0, uint2 src1);
18225uint3
__ovld amd_bfm(uint3 src0, uint3 src1);
18226uint4
__ovld amd_bfm(uint4 src0, uint4 src1);
18227uint8
__ovld amd_bfm(uint8 src0, uint8 src1);
18228uint16
__ovld amd_bfm(uint16 src0, uint16 src1);
18230float __ovld amd_max3(
float src0,
float src1,
float src2);
18231float2
__ovld amd_max3(float2 src0, float2 src1, float2 src2);
18232float3
__ovld amd_max3(float3 src0, float3 src1, float3 src2);
18233float4
__ovld amd_max3(float4 src0, float4 src1, float4 src2);
18234float8
__ovld amd_max3(float8 src0, float8 src1, float8 src2);
18235float16
__ovld amd_max3(float16 src0, float16 src1, float16 src2);
18237int __ovld amd_max3(
int src0,
int src1,
int src2);
18238int2
__ovld amd_max3(int2 src0, int2 src1, int2 src2);
18239int3
__ovld amd_max3(int3 src0, int3 src1, int3 src2);
18240int4
__ovld amd_max3(int4 src0, int4 src1, int4 src2);
18241int8
__ovld amd_max3(int8 src0, int8 src1, int8 src2);
18242int16
__ovld amd_max3(int16 src0, int16 src1, int16 src2);
18245uint2
__ovld amd_max3(uint2 src0, uint2 src1, uint2 src2);
18246uint3
__ovld amd_max3(uint3 src0, uint3 src1, uint3 src2);
18247uint4
__ovld amd_max3(uint4 src0, uint4 src1, uint4 src2);
18248uint8
__ovld amd_max3(uint8 src0, uint8 src1, uint8 src2);
18249uint16
__ovld amd_max3(uint16 src0, uint16 src1, uint16 src2);
18251float __ovld amd_median3(
float src0,
float src1,
float src2);
18252float2
__ovld amd_median3(float2 src0, float2 src1, float2 src2);
18253float3
__ovld amd_median3(float3 src0, float3 src1, float3 src2);
18254float4
__ovld amd_median3(float4 src0, float4 src1, float4 src2);
18255float8
__ovld amd_median3(float8 src0, float8 src1, float8 src2);
18256float16
__ovld amd_median3(float16 src0, float16 src1, float16 src2);
18258int __ovld amd_median3(
int src0,
int src1,
int src2);
18259int2
__ovld amd_median3(int2 src0, int2 src1, int2 src2);
18260int3
__ovld amd_median3(int3 src0, int3 src1, int3 src2);
18261int4
__ovld amd_median3(int4 src0, int4 src1, int4 src2);
18262int8
__ovld amd_median3(int8 src0, int8 src1, int8 src2);
18263int16
__ovld amd_median3(int16 src0, int16 src1, int16 src2);
18266uint2
__ovld amd_median3(uint2 src0, uint2 src1, uint2 src2);
18267uint3
__ovld amd_median3(uint3 src0, uint3 src1, uint3 src2);
18268uint4
__ovld amd_median3(uint4 src0, uint4 src1, uint4 src2);
18269uint8
__ovld amd_median3(uint8 src0, uint8 src1, uint8 src2);
18270uint16
__ovld amd_median3(uint16 src0, uint16 src1, uint16 src2);
18272float __ovld amd_min3(
float src0,
float src1,
float src);
18273float2
__ovld amd_min3(float2 src0, float2 src1, float2 src);
18274float3
__ovld amd_min3(float3 src0, float3 src1, float3 src);
18275float4
__ovld amd_min3(float4 src0, float4 src1, float4 src);
18276float8
__ovld amd_min3(float8 src0, float8 src1, float8 src);
18277float16
__ovld amd_min3(float16 src0, float16 src1, float16 src);
18279int __ovld amd_min3(
int src0,
int src1,
int src2);
18280int2
__ovld amd_min3(int2 src0, int2 src1, int2 src2);
18281int3
__ovld amd_min3(int3 src0, int3 src1, int3 src2);
18282int4
__ovld amd_min3(int4 src0, int4 src1, int4 src2);
18283int8
__ovld amd_min3(int8 src0, int8 src1, int8 src2);
18284int16
__ovld amd_min3(int16 src0, int16 src1, int16 src2);
18287uint2
__ovld amd_min3(uint2 src0, uint2 src1, uint2 src2);
18288uint3
__ovld amd_min3(uint3 src0, uint3 src1, uint3 src2);
18289uint4
__ovld amd_min3(uint4 src0, uint4 src1, uint4 src2);
18290uint8
__ovld amd_min3(uint8 src0, uint8 src1, uint8 src2);
18291uint16
__ovld amd_min3(uint16 src0, uint16 src1, uint16 src2);
18294ulong2
__ovld amd_mqsad(ulong2 src0, uint2 src1, ulong2 src2);
18295ulong3
__ovld amd_mqsad(ulong3 src0, uint3 src1, ulong3 src2);
18296ulong4
__ovld amd_mqsad(ulong4 src0, uint4 src1, ulong4 src2);
18297ulong8
__ovld amd_mqsad(ulong8 src0, uint8 src1, ulong8 src2);
18298ulong16
__ovld amd_mqsad(ulong16 src0, uint16 src1, ulong16 src2);
18301ulong2
__ovld amd_qsad(ulong2 src0, uint2 src1, ulong2 src2);
18302ulong3
__ovld amd_qsad(ulong3 src0, uint3 src1, ulong3 src2);
18303ulong4
__ovld amd_qsad(ulong4 src0, uint4 src1, ulong4 src2);
18304ulong8
__ovld amd_qsad(ulong8 src0, uint8 src1, ulong8 src2);
18305ulong16
__ovld amd_qsad(ulong16 src0, uint16 src1, ulong16 src2);
18308uint2
__ovld amd_msad(uint2 src0, uint2 src1, uint2 src2);
18309uint3
__ovld amd_msad(uint3 src0, uint3 src1, uint3 src2);
18310uint4
__ovld amd_msad(uint4 src0, uint4 src1, uint4 src2);
18311uint8
__ovld amd_msad(uint8 src0, uint8 src1, uint8 src2);
18312uint16
__ovld amd_msad(uint16 src0, uint16 src1, uint16 src2);
18315uint2
__ovld amd_sadd(uint2 src0, uint2 src1, uint2 src2);
18316uint3
__ovld amd_sadd(uint3 src0, uint3 src1, uint3 src2);
18317uint4
__ovld amd_sadd(uint4 src0, uint4 src1, uint4 src2);
18318uint8
__ovld amd_sadd(uint8 src0, uint8 src1, uint8 src2);
18319uint16
__ovld amd_sadd(uint16 src0, uint16 src1, uint16 src2);
18322uint2
__ovld amd_sadw(uint2 src0, uint2 src1, uint2 src2);
18323uint3
__ovld amd_sadw(uint3 src0, uint3 src1, uint3 src2);
18324uint4
__ovld amd_sadw(uint4 src0, uint4 src1, uint4 src2);
18325uint8
__ovld amd_sadw(uint8 src0, uint8 src1, uint8 src2);
18326uint16
__ovld amd_sadw(uint16 src0, uint16 src1, uint16 src2);
18329#if defined(cl_arm_integer_dot_product_int8)
18331int __ovld arm_dot(char4, char4);
18334#if defined(cl_arm_integer_dot_product_accumulate_int8)
18336int __ovld arm_dot_acc(char4, char4,
int);
18339#if defined(cl_arm_integer_dot_product_accumulate_int16)
18341int __ovld arm_dot_acc(short2, short2,
int);
18344#if defined(cl_arm_integer_dot_product_accumulate_saturate_int8)
18346int __ovld arm_dot_acc_sat(char4, char4,
int);
18350#pragma OPENCL EXTENSION all : disable
18352#undef __opencl_c_named_address_space_builtins
_Float16 __2f16 __attribute__((ext_vector_type(2)))
Zeroes the upper 128 bits (bits 255:128) of all YMM registers.
__PTRDIFF_TYPE__ ptrdiff_t
__INTPTR_TYPE__ intptr_t
A signed integer type with the property that any valid pointer to void can be converted to this type,...
__UINTPTR_TYPE__ uintptr_t
An unsigned integer type with the property that any valid pointer to void can be converted to this ty...
unsigned char uchar
An unsigned 8-bit integer.
unsigned long ulong
An unsigned 64-bit integer.
unsigned int uint
An unsigned 32-bit integer.
unsigned short ushort
An unsigned 16-bit integer.
int4 __ovld __cnfn convert_int4_rte(char4)
void __ovld vstore16(char16, size_t, __global char *)
uint8 __ovld __cnfn convert_uint8_rte(char8)
long __ovld __cnfn convert_long_rtp(char)
long2 __ovld __cnfn convert_long2_sat_rtp(char2)
char2 __ovld __cnfn convert_char2_rtp(char2)
void __ovld vstorea_half2_rte(float2, size_t, __global half *)
short8 __ovld __cnfn convert_short8_sat_rte(char8)
uchar8 __ovld __cnfn convert_uchar8_rtp(char8)
ulong16 __ovld __cnfn convert_ulong16_sat(char16)
uchar __ovld __cnfn convert_uchar(char)
ulong8 __ovld __cnfn convert_ulong8_rte(char8)
float __ovld __cnfn half_tan(float)
Compute tangent.
void __ovld vstore2(char2, size_t, __global char *)
int16 __ovld __cnfn convert_int16_sat_rtn(char16)
int3 __ovld __cnfn convert_int3_rtn(char3)
float __ovld __cnfn nan(uint)
Returns a quiet NaN.
void __ovld vstorea_half4(float4, size_t, __global half *)
int __ovld __cnfn isequal(float, float)
intn isequal (floatn x, floatn y) Returns the component-wise compare of x == y.
short4 __ovld __cnfn convert_short4_rtp(char4)
int __ovld atomic_or(volatile __global int *, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
ulong2 __ovld __cnfn convert_ulong2_rtn(char2)
void __ovld vstore_half4(float4, size_t, __global half *)
ushort8 __ovld __cnfn convert_ushort8_rtn(char8)
uint16 __ovld __cnfn convert_uint16_sat_rtp(char16)
char __ovld __cnfn mad_hi(char, char, char)
Returns mul_hi(a, b) + c.
int3 __ovld __cnfn convert_int3_rtp(char3)
void __ovld vstorea_half2_rtz(float2, size_t, __global half *)
char3 __ovld __cnfn convert_char3_sat(char3)
char4 __ovld __cnfn convert_char4_sat(char4)
long __ovld __cnfn convert_long_rtz(char)
ushort8 __ovld __cnfn convert_ushort8_sat_rtn(char8)
float __ovld __cnfn native_tan(float)
Compute tangent over an implementation-defined range.
uint __ovld __cnfn convert_uint_sat_rtn(char)
uint16 __ovld __cnfn convert_uint16_sat_rtn(char16)
uchar8 __ovld __cnfn convert_uchar8(char8)
char __ovld __cnfn sub_sat(char, char)
Returns x - y and saturates the result.
float8 __ovld __purefn vload_half8(size_t, const __constant half *)
uchar2 __ovld __cnfn convert_uchar2_sat(char2)
void __ovld vstore_half8_rtz(float8, size_t, __global half *)
int3 __ovld __cnfn convert_int3(char3)
short __ovld __cnfn convert_short_sat_rtn(char)
uchar2 __ovld __cnfn convert_uchar2_rte(char2)
float __ovld fract(float, __global float *)
Returns fmin(x - floor (x), 0x1.fffffep-1f ).
uchar16 __ovld __cnfn convert_uchar16_sat_rtn(char16)
float __ovld __cnfn pown(float, int)
Compute x to the power y, where y is an integer.
float __ovld __cnfn dot(float, float)
Compute dot product.
ulong4 __ovld __cnfn convert_ulong4_rtp(char4)
ushort3 __ovld __cnfn convert_ushort3_rtz(char3)
void __ovld vstorea_half16_rtz(float16, size_t, __global half *)
int16 __ovld __cnfn convert_int16_sat(char16)
int __ovld __cnfn get_image_width(read_only image1d_t)
Return the image width in pixels.
float __ovld __cnfn native_sin(float)
Compute sine over an implementation-defined range.
char4 __ovld __cnfn convert_char4_rte(char4)
int __ovld atomic_max(volatile __global int *, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
int2 __ovld __cnfn convert_int2_sat_rtz(char2)
char __ovld __cnfn clz(char)
Returns the number of leading 0-bits in x, starting at the most significant bit position.
float __ovld __cnfn convert_float_rte(char)
ulong __ovld __cnfn convert_ulong_rtz(char)
float2 __ovld __cnfn convert_float2_rtp(char2)
short4 __ovld __cnfn convert_short4_sat_rtn(char4)
short2 __ovld __cnfn convert_short2_rtz(char2)
char8 __ovld __cnfn convert_char8_sat_rte(char8)
ushort8 __ovld __cnfn convert_ushort8_sat_rtp(char8)
void __ovld write_imagei(write_only image2d_t, int2, int4)
void __ovld vstorea_half3_rtn(float3, size_t, __global half *)
void __ovld vstore_half2_rte(float2, size_t, __global half *)
int3 __ovld __cnfn convert_int3_rtz(char3)
ushort8 __ovld __cnfn convert_ushort8_sat_rtz(char8)
char8 __ovld __cnfn convert_char8_sat_rtn(char8)
int2 __ovld __cnfn convert_int2_sat(char2)
size_t __ovld __cnfn get_global_offset(uint)
get_global_offset returns the offset values specified in global_work_offset argument to clEnqueueNDRa...
float __ovld __cnfn fast_length(float)
Returns the length of vector p computed as: half_sqrt(p.x2 + p.y2 + ...)
ushort3 __ovld __cnfn convert_ushort3_rtn(char3)
float4 __ovld __cnfn convert_float4(char4)
int __ovld __cnfn isnotequal(float, float)
Returns the component-wise compare of x != y.
char __ovld __cnfn add_sat(char, char)
Returns x + y and saturates the result.
ulong8 __ovld __cnfn convert_ulong8_rtp(char8)
uint3 __ovld __cnfn convert_uint3_rtn(char3)
ushort3 __ovld __cnfn convert_ushort3_sat_rtn(char3)
long2 __ovld __cnfn convert_long2_sat(char2)
ushort3 __ovld __cnfn convert_ushort3_rte(char3)
ulong16 __ovld __cnfn convert_ulong16_sat_rtp(char16)
size_t __ovld __cnfn get_local_id(uint)
Returns the unique local work-item ID i.e.
float __ovld __cnfn native_log(float)
Compute natural logarithm over an implementationdefined range.
char8 __ovld __cnfn convert_char8(char8)
char __ovld __cnfn convert_char_sat(char)
ulong3 __ovld __cnfn convert_ulong3_sat_rtn(char3)
ushort __ovld __cnfn convert_ushort_rtn(char)
float __ovld __cnfn native_recip(float)
Compute reciprocal over an implementation-defined range.
uint4 __ovld __cnfn convert_uint4_rtz(char4)
float16 __ovld __cnfn convert_float16_rtn(char16)
short3 __ovld __cnfn convert_short3_rtp(char3)
int __ovld __cnfn convert_int_sat_rtz(char)
float __ovld __cnfn asinpi(float)
Compute asin (x) / PI.
int16 __ovld __cnfn convert_int16(char16)
uint __ovld __cnfn convert_uint_rtz(char)
int __ovld atomic_xchg(volatile __global int *, int)
Swaps the old value stored at location p with new value given by val.
ushort8 __ovld __cnfn convert_ushort8_rte(char8)
long3 __ovld __cnfn convert_long3_sat_rtz(char3)
short16 __ovld __cnfn convert_short16_sat_rte(char16)
ulong8 __ovld __cnfn convert_ulong8_sat_rtn(char8)
void __ovld vstore_half_rte(float, size_t, __global half *)
void __ovld vstorea_half3_rtp(float3, size_t, __global half *)
ushort3 __ovld __cnfn convert_ushort3_sat(char3)
int8 __ovld __cnfn convert_int8_sat(char8)
float3 __ovld __cnfn convert_float3_rtp(char3)
int16 __ovld __cnfn convert_int16_rtp(char16)
ulong4 __ovld __cnfn convert_ulong4_sat_rtn(char4)
float __ovld __cnfn half_recip(float)
Compute reciprocal.
uchar2 __ovld __cnfn convert_uchar2_sat_rtp(char2)
ulong2 __ovld __cnfn convert_ulong2_sat_rtz(char2)
int4 __ovld __cnfn convert_int4_sat_rtz(char4)
void __ovld vstore_half2(float2, size_t, __global half *)
The floatn value given by data is converted to a halfn value using the appropriate rounding mode.
ushort8 __ovld __cnfn convert_ushort8_sat(char8)
void __ovld vstore_half16_rtz(float16, size_t, __global half *)
uint3 __ovld __cnfn convert_uint3_sat(char3)
void __ovld vstore_half2_rtn(float2, size_t, __global half *)
ulong4 __ovld __cnfn convert_ulong4_sat(char4)
int16 __ovld __cnfn convert_int16_sat_rtp(char16)
char16 __ovld __cnfn convert_char16_sat_rtz(char16)
uint __ovld __cnfn convert_uint_sat(char)
ushort4 __ovld __cnfn convert_ushort4_sat_rtn(char4)
float3 __ovld __cnfn convert_float3_rtn(char3)
long16 __ovld __cnfn convert_long16(char16)
short16 __ovld __cnfn convert_short16_rtn(char16)
float4 __ovld __purefn vload_half4(size_t, const __constant half *)
short2 __ovld __cnfn convert_short2_rtp(char2)
uchar8 __ovld __cnfn convert_uchar8_rtz(char8)
float __ovld __cnfn half_powr(float, float)
Compute x to the power y, where x is >= 0.
int __ovld __cnfn convert_int_rtz(char)
char16 __ovld __cnfn convert_char16_rtz(char16)
ushort16 __ovld __cnfn convert_ushort16_rte(char16)
int2 __ovld __cnfn convert_int2_sat_rtp(char2)
float __ovld __cnfn atanpi(float)
Compute atan (x) / PI.
char __ovld __cnfn convert_char_sat_rtn(char)
short2 __ovld __cnfn convert_short2(char2)
short2 __ovld __cnfn convert_short2_sat_rtp(char2)
int __ovld __cnfn convert_int_rtn(char)
ushort __ovld __cnfn convert_ushort_sat_rtz(char)
long4 __ovld __cnfn convert_long4(char4)
short16 __ovld __cnfn convert_short16_sat(char16)
uchar3 __ovld __cnfn convert_uchar3_rtn(char3)
short8 __ovld __cnfn convert_short8(char8)
ulong2 __ovld __cnfn convert_ulong2_sat(char2)
ulong3 __ovld __cnfn convert_ulong3_sat_rte(char3)
short4 __ovld __cnfn convert_short4_sat_rte(char4)
ulong8 __ovld __cnfn convert_ulong8_sat(char8)
void __ovld vstorea_half4_rtz(float4, size_t, __global half *)
char2 __ovld __cnfn convert_char2_sat_rtp(char2)
uint __ovld __cnfn convert_uint_sat_rte(char)
uint8 __ovld __cnfn convert_uint8_sat_rte(char8)
int16 __ovld __cnfn convert_int16_rte(char16)
char __ovld __cnfn ctz(char)
Returns the count of trailing 0-bits in x.
char16 __ovld __cnfn convert_char16_sat_rtn(char16)
ulong __ovld __cnfn convert_ulong_sat_rte(char)
char __ovld __cnfn hadd(char, char)
Returns (x + y) >> 1.
float __ovld __cnfn convert_float_rtp(char)
ulong2 __ovld __cnfn convert_ulong2_sat_rtp(char2)
uint3 __ovld __cnfn convert_uint3_rtp(char3)
float16 __ovld __cnfn convert_float16_rtp(char16)
float2 __ovld __purefn vload_half2(size_t, const __constant half *)
Read sizeof (halfn) bytes of data from address (p + (offset * n)).
short4 __ovld __cnfn convert_short4_sat_rtz(char4)
int3 __ovld __cnfn convert_int3_sat_rtz(char3)
ushort3 __ovld __cnfn convert_ushort3_sat_rte(char3)
ulong __ovld __cnfn convert_ulong_sat(char)
long3 __ovld __cnfn convert_long3_sat(char3)
ulong4 __ovld __cnfn convert_ulong4_sat_rtz(char4)
long8 __ovld __cnfn convert_long8_sat_rte(char8)
int4 __ovld __cnfn convert_int4(char4)
ushort8 __ovld __cnfn convert_ushort8_rtz(char8)
short __ovld __cnfn convert_short_sat_rtp(char)
ulong4 __ovld __cnfn convert_ulong4_rtn(char4)
long16 __ovld __cnfn convert_long16_rtn(char16)
uint __ovld __cnfn convert_uint_rtn(char)
uchar __ovld __cnfn abs_diff(char, char)
Returns | x - y | without modulo overflow.
float __ovld __cnfn mix(float, float, float)
Returns the linear blend of x & y implemented as: x + (y - x) * a a must be a value in the range 0....
float __ovld sincos(float, __global float *)
Compute sine and cosine of x.
void __ovld vstorea_half4_rtp(float4, size_t, __global half *)
void __ovld vstore_half(float, size_t, __global half *)
The float value given by data is first converted to a half value using the appropriate rounding mode.
float __ovld __cnfn half_exp2(float)
Compute the base- 2 exponential of x.
short2 __ovld __cnfn convert_short2_rte(char2)
ulong3 __ovld __cnfn convert_ulong3_rtp(char3)
ulong16 __ovld __cnfn convert_ulong16_rtz(char16)
int2 __ovld __cnfn convert_int2_rte(char2)
float __ovld __cnfn step(float, float)
Returns 0.0 if x < edge, otherwise it returns 1.0.
float8 __ovld __cnfn convert_float8_rte(char8)
uchar3 __ovld __cnfn convert_uchar3(char3)
float __ovld __cnfn convert_float_rtz(char)
char4 __ovld __cnfn convert_char4_sat_rte(char4)
float __ovld __cnfn exp10(float)
Exponential base 10 function.
char __ovld __cnfn convert_char(char)
float __ovld __cnfn half_exp(float)
Compute the base- e exponential of x.
ushort16 __ovld __cnfn convert_ushort16_sat_rte(char16)
int __ovld __cnfn isinf(float)
Test for infinity value (+ve or -ve) .
ushort3 __ovld __cnfn convert_ushort3_sat_rtz(char3)
int __ovld __cnfn get_image_height(read_only image2d_t)
Return the image height in pixels.
short __ovld __cnfn convert_short_rtp(char)
int2 __ovld __cnfn get_image_dim(read_only image2d_t)
Return the 2D image width and height as an int2 type.
uchar __ovld __cnfn convert_uchar_rte(char)
int __ovld atomic_sub(volatile __global int *, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
float3 __ovld __cnfn convert_float3_rtz(char3)
long __ovld __cnfn convert_long_rte(char)
float __ovld __cnfn native_exp2(float)
Compute the base- 2 exponential of x over an implementation-defined range.
short8 __ovld __cnfn convert_short8_rtz(char8)
float __ovld __cnfn sign(float)
Returns 1.0 if x > 0, -0.0 if x = -0.0, +0.0 if x = +0.0, or -1.0 if x < 0.
float __ovld __cnfn radians(float)
Converts degrees to radians, i.e.
char __ovld __cnfn mul_hi(char, char)
Computes x * y and returns the high half of the product of x and y.
size_t __ovld get_global_linear_id(void)
char __ovld __cnfn convert_char_sat_rtz(char)
void __ovld vstorea_half2(float2, size_t, __global half *)
The floatn value given by data is converted to a halfn value using the appropriate rounding mode.
int __ovld __cnfn convert_int_rtp(char)
long3 __ovld __cnfn convert_long3_sat_rtp(char3)
void __ovld vstorea_half8_rtz(float8, size_t, __global half *)
uchar __ovld __cnfn convert_uchar_rtp(char)
char __ovld __cnfn max(char, char)
Returns y if x < y, otherwise it returns x.
size_t __ovld __cnfn get_num_groups(uint)
Returns the number of work-groups that will execute a kernel for dimension identified by dimindx.
ulong4 __ovld __cnfn convert_ulong4(char4)
uint4 __ovld __cnfn convert_uint4_sat(char4)
ulong2 __ovld __cnfn convert_ulong2(char2)
long2 __ovld __cnfn convert_long2_rtn(char2)
long16 __ovld __cnfn convert_long16_rtp(char16)
void __ovld vstorea_half8_rtn(float8, size_t, __global half *)
int __ovld atomic_fetch_max_explicit(volatile __global atomic_int *, int, memory_order, memory_scope)
ushort16 __ovld __cnfn convert_ushort16_sat_rtn(char16)
long3 __ovld __cnfn convert_long3_sat_rtn(char3)
float __ovld __cnfn degrees(float)
Converts radians to degrees, i.e.
uint2 __ovld __cnfn convert_uint2_rtp(char2)
uint3 __ovld __cnfn convert_uint3(char3)
void __ovld vstorea_half4_rtn(float4, size_t, __global half *)
ushort4 __ovld __cnfn convert_ushort4_sat(char4)
short __ovld __cnfn convert_short_rtz(char)
uint8 __ovld __cnfn convert_uint8_sat_rtn(char8)
uchar __ovld __cnfn convert_uchar_sat(char)
float8 __ovld __cnfn convert_float8_rtn(char8)
short4 __ovld __cnfn convert_short4_sat(char4)
float4 __ovld __cnfn convert_float4_rte(char4)
uchar4 __ovld __cnfn convert_uchar4_rtz(char4)
char4 __ovld __cnfn convert_char4_rtp(char4)
uchar16 __ovld __cnfn convert_uchar16_sat(char16)
long8 __ovld __cnfn convert_long8_sat_rtp(char8)
float __ovld __cnfn native_exp(float)
Compute the base- e exponential of x over an implementation-defined range.
short3 __ovld __cnfn convert_short3_rte(char3)
uint3 __ovld __cnfn convert_uint3_sat_rtz(char3)
char3 __ovld __cnfn convert_char3_sat_rtp(char3)
int __ovld __cnfn all(char)
Returns 1 if the most significant bit in all components of x is set; otherwise returns 0.
ushort16 __ovld __cnfn convert_ushort16(char16)
void __ovld vstore_half_rtp(float, size_t, __global half *)
long4 __ovld __cnfn convert_long4_sat_rtp(char4)
uint8 __ovld __cnfn convert_uint8_rtn(char8)
float8 __ovld __cnfn convert_float8(char8)
uchar __ovld __cnfn abs(char)
Returns | x |.
float __ovld __cnfn half_log2(float)
Compute a base 2 logarithm.
float16 __ovld __cnfn convert_float16(char16)
char8 __ovld __cnfn convert_char8_rtp(char8)
short3 __ovld __cnfn convert_short3_rtz(char3)
char16 __ovld __cnfn convert_char16_sat_rte(char16)
void __ovld vstore_half16(float16, size_t, __global half *)
long16 __ovld __cnfn convert_long16_rte(char16)
int __ovld atomic_dec(volatile __global int *)
Read the 32-bit value (referred to as old) stored at location pointed by p.
uchar3 __ovld __cnfn convert_uchar3_sat(char3)
uchar16 __ovld __cnfn convert_uchar16_sat_rte(char16)
char __ovld __cnfn rhadd(char, char)
Returns (x + y + 1) >> 1.
void __ovld vstorea_half16_rtn(float16, size_t, __global half *)
long8 __ovld __cnfn convert_long8_rtz(char8)
ushort16 __ovld __cnfn convert_ushort16_rtn(char16)
ulong2 __ovld __cnfn convert_ulong2_sat_rtn(char2)
int __ovld __cnfn isless(float, float)
Returns the component-wise compare of x < y.
float __ovld __cnfn length(float)
Return the length of vector p, i.e., sqrt(p.x2 + p.y 2 + ...)
char4 __ovld __cnfn convert_char4(char4)
int2 __ovld __cnfn convert_int2_rtz(char2)
short16 __ovld __cnfn convert_short16_sat_rtn(char16)
ulong __ovld __cnfn convert_ulong_rtn(char)
ulong16 __ovld __cnfn convert_ulong16_rtp(char16)
char3 __ovld __cnfn convert_char3_sat_rtn(char3)
short __ovld __cnfn convert_short_rte(char)
short3 __ovld __cnfn convert_short3_sat(char3)
long8 __ovld __cnfn convert_long8_sat(char8)
uint __ovld __cnfn convert_uint_sat_rtp(char)
char2 __ovld __cnfn convert_char2_sat_rte(char2)
float __ovld __cnfn half_log(float)
Compute natural logarithm.
char4 __ovld __cnfn convert_char4_sat_rtp(char4)
long8 __ovld __cnfn convert_long8_rtp(char8)
uint __ovld __cnfn convert_uint_rtp(char)
ulong __ovld __cnfn convert_ulong(char)
short4 __ovld __cnfn convert_short4_rtz(char4)
uchar3 __ovld __cnfn convert_uchar3_sat_rtn(char3)
ulong8 __ovld __cnfn convert_ulong8_rtn(char8)
char __ovld __cnfn mad_sat(char, char, char)
Returns a * b + c and saturates the result.
void __ovld vstorea_half2_rtp(float2, size_t, __global half *)
size_t __ovld get_local_linear_id(void)
short2 __ovld __cnfn convert_short2_sat(char2)
char3 __ovld __cnfn convert_char3_rtz(char3)
uint2 __ovld __cnfn convert_uint2_sat_rtz(char2)
uchar4 __ovld __cnfn convert_uchar4_sat_rte(char4)
float __ovld __cnfn minmag(float, float)
Returns x if | x | < | y |, y if | y | < | x |, otherwise fmin(x, y).
int8 __ovld __cnfn convert_int8(char8)
ulong16 __ovld __cnfn convert_ulong16_rte(char16)
char16 __ovld __cnfn convert_char16_rtp(char16)
float __ovld __cnfn native_powr(float, float)
Compute x to the power y, where x is >= 0.
int16 __ovld __cnfn convert_int16_sat_rte(char16)
long16 __ovld __cnfn convert_long16_sat(char16)
uchar __ovld __cnfn convert_uchar_rtz(char)
char3 __ovld __cnfn convert_char3_rtp(char3)
void __ovld vstorea_half16_rte(float16, size_t, __global half *)
int8 __ovld __cnfn convert_int8_sat_rtp(char8)
ulong2 __ovld __cnfn convert_ulong2_rte(char2)
char __ovld __cnfn convert_char_rtz(char)
short16 __ovld __cnfn convert_short16_sat_rtp(char16)
size_t __ovld __cnfn get_image_array_size(read_only image1d_array_t)
Return the image array size.
float4 __ovld __cnfn convert_float4_rtz(char4)
void __ovld vstorea_half3_rte(float3, size_t, __global half *)
uint4 __ovld __cnfn convert_uint4_rtn(char4)
float __ovld __cnfn convert_float_rtn(char)
int __ovld atomic_and(volatile __global int *, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
float __ovld __cnfn rsqrt(float)
Compute inverse square root.
float2 __ovld __cnfn convert_float2_rte(char2)
float __ovld __cnfn smoothstep(float, float, float)
Returns 0.0 if x <= edge0 and 1.0 if x >= edge1 and performs smooth Hermite interpolation between 0 a...
void __ovld vstore_half4_rte(float4, size_t, __global half *)
ushort4 __ovld __cnfn convert_ushort4_rtp(char4)
char3 __ovld __cnfn convert_char3_rtn(char3)
char3 __ovld __cnfn convert_char3_sat_rte(char3)
void __ovld wait_group_events(int, event_t *)
Wait for events that identify the async_work_group_copy operations to complete.
int __ovld __cnfn convert_int_sat_rte(char)
short8 __ovld __cnfn convert_short8_sat_rtz(char8)
uchar8 __ovld __cnfn convert_uchar8_sat_rtp(char8)
uchar2 __ovld __cnfn convert_uchar2(char2)
uint4 __ovld __cnfn convert_uint4_rtp(char4)
ushort4 __ovld __cnfn convert_ushort4_rtz(char4)
char __ovld __cnfn select(char, char, char)
For each component of a vector type, result[i] = if MSB of c[i] is set ? b[i] : a[i].
void __ovld vstore_half8_rtp(float8, size_t, __global half *)
size_t __ovld __cnfn get_global_id(uint)
Returns the unique global work-item ID value for dimension identified by dimindx.
ushort __ovld __cnfn convert_ushort_sat(char)
int3 __ovld __cnfn convert_int3_sat_rtp(char3)
uint8 __ovld __cnfn convert_uint8_sat_rtp(char8)
ulong8 __ovld __cnfn convert_ulong8_rtz(char8)
char4 __ovld __cnfn convert_char4_sat_rtn(char4)
int4 __ovld __purefn read_imagei(read_only image2d_t, sampler_t, int2)
float __ovld __cnfn half_exp10(float)
Compute the base- 10 exponential of x.
void __ovld vstore_half16_rte(float16, size_t, __global half *)
short __ovld __cnfn convert_short_sat_rtz(char)
ulong3 __ovld __cnfn convert_ulong3_sat_rtp(char3)
uchar3 __ovld __cnfn convert_uchar3_sat_rte(char3)
ulong16 __ovld __cnfn convert_ulong16_rtn(char16)
char2 __ovld __cnfn convert_char2_rte(char2)
uchar4 __ovld __cnfn convert_uchar4_sat_rtn(char4)
char2 __ovld __cnfn shuffle(char2, uchar2)
The shuffle and shuffle2 built-in functions construct a permutation of elements from one or two input...
char4 __ovld __cnfn convert_char4_sat_rtz(char4)
float __ovld __cnfn native_cos(float)
Compute cosine over an implementation-defined range.
short3 __ovld __cnfn convert_short3_sat_rtp(char3)
ushort2 __ovld __cnfn convert_ushort2_sat(char2)
float8 __ovld __cnfn convert_float8_rtz(char8)
short3 __ovld __cnfn convert_short3_sat_rte(char3)
char8 __ovld __cnfn convert_char8_sat_rtz(char8)
float8 __ovld __purefn vloada_half8(size_t, const __constant half *)
int __ovld atomic_inc(volatile __global int *)
Read the 32-bit value (referred to as old) stored at location pointed by p.
char __ovld __cnfn popcount(char)
uchar2 __ovld __cnfn convert_uchar2_rtp(char2)
size_t __ovld get_enqueued_local_size(uint)
float __ovld __cnfn maxmag(float, float)
Returns x if | x | > | y |, y if | y | > | x |, otherwise fmax(x, y).
ushort16 __ovld __cnfn convert_ushort16_sat_rtz(char16)
uint4 __ovld __cnfn convert_uint4_sat_rte(char4)
short16 __ovld __cnfn convert_short16_sat_rtz(char16)
float16 __ovld __purefn vload_half16(size_t, const __constant half *)
uchar3 __ovld __cnfn convert_uchar3_rtp(char3)
ushort4 __ovld __cnfn convert_ushort4_sat_rtz(char4)
uint3 __ovld __cnfn convert_uint3_rtz(char3)
uint8 __ovld __cnfn convert_uint8_sat(char8)
uchar2 __ovld __cnfn convert_uchar2_sat_rtn(char2)
int __ovld __cnfn isgreaterequal(float, float)
Returns the component-wise compare of x >= y.
void __ovld vstore_half8(float8, size_t, __global half *)
float3 __ovld __purefn vloada_half3(size_t, const __constant half *)
ushort2 __ovld __cnfn convert_ushort2_rtz(char2)
int __ovld __cnfn isfinite(float)
Test for finite value.
char __ovld __cnfn rotate(char, char)
For each element in v, the bits are shifted left by the number of bits given by the corresponding ele...
void __ovld vstore_half3_rtn(float3, size_t, __global half *)
float __ovld __cnfn native_rsqrt(float)
Compute inverse square root over an implementationdefined range.
float3 __ovld __cnfn convert_float3(char3)
int4 __ovld __cnfn convert_int4_sat_rte(char4)
char8 __ovld __cnfn convert_char8_rtz(char8)
void __ovld vstore_half8_rte(float8, size_t, __global half *)
short4 __ovld __cnfn convert_short4_sat_rtp(char4)
int2 __ovld __cnfn convert_int2_rtp(char2)
long4 __ovld __cnfn convert_long4_sat_rtn(char4)
int16 __ovld __cnfn convert_int16_sat_rtz(char16)
int __ovld atomic_add(volatile __global int *, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
uchar4 __ovld __cnfn convert_uchar4_sat(char4)
ushort __ovld __cnfn convert_ushort_rtz(char)
short8 __ovld __cnfn convert_short8_rtp(char8)
long4 __ovld __cnfn convert_long4_rtn(char4)
int4 __ovld __cnfn convert_int4_sat_rtn(char4)
char __ovld __cnfn clamp(char, char, char)
Returns min(max(x, minval), maxval).
long __ovld __cnfn convert_long(char)
short8 __ovld __cnfn convert_short8_rte(char8)
char16 __ovld __cnfn convert_char16_rte(char16)
int __ovld __cnfn mad24(int, int, int)
Multiply two 24-bit integer values x and y and add the 32-bit integer result to the 32-bit integer z.
int3 __ovld __cnfn convert_int3_sat_rte(char3)
void __ovld vstorea_half8(float8, size_t, __global half *)
float __ovld __cnfn cospi(float)
Compute cos (PI * x).
float __ovld __cnfn fast_normalize(float)
Returns a vector in the same direction as p but with a length of 1.
ushort2 __ovld __cnfn convert_ushort2_sat_rtz(char2)
short4 __ovld __cnfn convert_short4_rtn(char4)
float2 __ovld __cnfn convert_float2(char2)
void __ovld write_imagef(write_only image2d_t, int2, float4)
Write color value to location specified by coordinate (coord.x, coord.y) in the 2D image object speci...
long2 __ovld __cnfn convert_long2_rtz(char2)
char __ovld __cnfn convert_char_sat_rtp(char)
uint16 __ovld __cnfn convert_uint16_rtz(char16)
short3 __ovld __cnfn convert_short3_sat_rtn(char3)
uchar16 __ovld __cnfn convert_uchar16(char16)
uint3 __ovld __cnfn convert_uint3_rte(char3)
uint16 __ovld __cnfn convert_uint16_sat_rte(char16)
long3 __ovld __cnfn convert_long3_rtp(char3)
int __ovld __cnfn isnormal(float)
Test for a normal value.
ushort2 __ovld __cnfn convert_ushort2_rtn(char2)
char8 __ovld __cnfn convert_char8_sat(char8)
uint16 __ovld __cnfn convert_uint16_rtn(char16)
long8 __ovld __cnfn convert_long8_sat_rtn(char8)
void __ovld vstore_half3(float3, size_t, __global half *)
uchar8 __ovld __cnfn convert_uchar8_sat_rtn(char8)
uchar8 __ovld __cnfn convert_uchar8_rte(char8)
uint4 __ovld __cnfn convert_uint4_sat_rtz(char4)
int16 __ovld __cnfn convert_int16_rtn(char16)
void __ovld vstorea_half3(float3, size_t, __global half *)
int4 __ovld __cnfn convert_int4_rtz(char4)
float __ovld __cnfn distance(float, float)
Returns the distance between p0 and p1.
uint2 __ovld __cnfn convert_uint2_rte(char2)
int __ovld __cnfn isordered(float, float)
Test if arguments are ordered.
void __ovld vstorea_half8_rte(float8, size_t, __global half *)
ulong16 __ovld __cnfn convert_ulong16(char16)
float __ovld __purefn vload_half(size_t, const __constant half *)
Read sizeof (half) bytes of data from address (p + offset).
char __ovld __cnfn convert_char_rtp(char)
uchar8 __ovld __cnfn convert_uchar8_sat_rtz(char8)
ulong3 __ovld __cnfn convert_ulong3(char3)
char3 __ovld __cnfn convert_char3(char3)
long __ovld __cnfn convert_long_sat_rtz(char)
long2 __ovld __cnfn convert_long2_sat_rtz(char2)
ulong4 __ovld __cnfn convert_ulong4_sat_rte(char4)
char2 __ovld __cnfn convert_char2_rtn(char2)
short2 __ovld __cnfn convert_short2_sat_rtz(char2)
short8 __ovld __cnfn convert_short8_sat_rtn(char8)
uint2 __ovld __cnfn convert_uint2_sat_rtn(char2)
void __ovld write_imageui(write_only image2d_t, int2, uint4)
char __ovld __cnfn min(char, char)
Returns y if y < x, otherwise it returns x.
uchar3 __ovld __cnfn convert_uchar3_rtz(char3)
uint3 __ovld __cnfn convert_uint3_sat_rtn(char3)
char __ovld __cnfn bitselect(char, char, char)
Each bit of the result is the corresponding bit of a if the corresponding bit of c is 0.
uchar4 __ovld __cnfn convert_uchar4_rtn(char4)
float3 __ovld __purefn vload_half3(size_t, const __constant half *)
uint4 __ovld __cnfn convert_uint4_sat_rtn(char4)
int8 __ovld __cnfn convert_int8_sat_rte(char8)
ulong3 __ovld __cnfn convert_ulong3_sat(char3)
float __ovld __cnfn normalize(float)
Returns a vector in the same direction as p but with a length of 1.
ushort3 __ovld __cnfn convert_ushort3_rtp(char3)
float4 __ovld __purefn read_imagef(read_only image2d_t, sampler_t, int2)
Use the coordinate (coord.xy) to do an element lookup in the 2D image object specified by image.
float3 __ovld __cnfn convert_float3_rte(char3)
uchar __ovld __cnfn convert_uchar_rtn(char)
void __ovld vstore8(char8, size_t, __global char *)
long4 __ovld __cnfn convert_long4_sat_rte(char4)
int3 __ovld __cnfn convert_int3_sat_rtn(char3)
long __ovld __cnfn convert_long_rtn(char)
uchar8 __ovld __cnfn convert_uchar8_sat_rte(char8)
long2 __ovld __cnfn convert_long2(char2)
ulong16 __ovld __cnfn convert_ulong16_sat_rte(char16)
long __ovld __cnfn convert_long_sat(char)
short __ovld __cnfn convert_short_sat_rte(char)
float __ovld __cnfn native_log10(float)
Compute a base 10 logarithm over an implementationdefined range.
ulong16 __ovld __cnfn convert_ulong16_sat_rtz(char16)
ushort __ovld __cnfn convert_ushort_sat_rte(char)
short2 __ovld __cnfn convert_short2_sat_rte(char2)
void __ovld vstore_half16_rtp(float16, size_t, __global half *)
uint8 __ovld __cnfn convert_uint8(char8)
float __ovld __cnfn half_divide(float, float)
Compute x / y.
float __ovld modf(float, __global float *)
Decompose a floating-point number.
void __ovld vstore3(char3, size_t, __global char *)
uint __ovld __cnfn get_work_dim(void)
Returns the number of dimensions in use.
long2 __ovld __cnfn convert_long2_sat_rtn(char2)
int2 __ovld __cnfn convert_int2_rtn(char2)
long8 __ovld __cnfn convert_long8_rte(char8)
char16 __ovld __cnfn convert_char16_sat_rtp(char16)
uchar __ovld __cnfn convert_uchar_sat_rte(char)
uchar4 __ovld __cnfn convert_uchar4(char4)
uchar8 __ovld __cnfn convert_uchar8_rtn(char8)
void __ovld vstore_half4_rtz(float4, size_t, __global half *)
ushort8 __ovld __cnfn convert_ushort8_rtp(char8)
float4 __ovld __cnfn convert_float4_rtp(char4)
uint2 __ovld __cnfn convert_uint2_sat_rtp(char2)
long8 __ovld __cnfn convert_long8_rtn(char8)
char2 __ovld __cnfn convert_char2_rtz(char2)
ulong4 __ovld __cnfn convert_ulong4_rtz(char4)
void __ovld vstorea_half3_rtz(float3, size_t, __global half *)
ushort3 __ovld __cnfn convert_ushort3_sat_rtp(char3)
long16 __ovld __cnfn convert_long16_sat_rtp(char16)
uchar __ovld __cnfn convert_uchar_sat_rtn(char)
ushort4 __ovld __cnfn convert_ushort4_sat_rtp(char4)
uchar __ovld __cnfn convert_uchar_sat_rtz(char)
void __ovld vstore_half4_rtp(float4, size_t, __global half *)
long4 __ovld __cnfn convert_long4_rtp(char4)
int __ovld atomic_min(volatile __global int *, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
void __ovld vstore_half8_rtn(float8, size_t, __global half *)
ushort3 __ovld __cnfn convert_ushort3(char3)
int __ovld atomic_xor(volatile __global int *, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
long2 __ovld __cnfn convert_long2_rtp(char2)
size_t __ovld __cnfn get_group_id(uint)
get_group_id returns the work-group ID which is a number from 0 .
char4 __ovld __cnfn convert_char4_rtz(char4)
void __ovld vstore_half_rtz(float, size_t, __global half *)
uchar4 __ovld __cnfn convert_uchar4_rtp(char4)
int __ovld __cnfn convert_int_sat_rtn(char)
uchar16 __ovld __cnfn convert_uchar16_rtz(char16)
char2 __ovld __cnfn convert_char2(char2)
void __ovld vstore_half2_rtz(float2, size_t, __global half *)
char2 __ovld __purefn vload2(size_t, const __constant char *)
Use generic type gentype to indicate the built-in data types char, uchar, short, ushort,...
long4 __ovld __cnfn convert_long4_rtz(char4)
float __ovld __cnfn powr(float, float)
Compute x to the power y, where x is >= 0.
char __ovld __cnfn convert_char_rte(char)
int __ovld __cnfn islessgreater(float, float)
Returns the component-wise compare of (x < y) || (x > y) .
ushort __ovld __cnfn convert_ushort(char)
uint8 __ovld __cnfn convert_uint8_rtp(char8)
long16 __ovld __cnfn convert_long16_rtz(char16)
ushort8 __ovld __cnfn convert_ushort8_sat_rte(char8)
short16 __ovld __cnfn convert_short16_rtp(char16)
long4 __ovld __cnfn convert_long4_sat(char4)
long4 __ovld __cnfn convert_long4_rte(char4)
short __ovld __cnfn upsample(char, uchar)
result[i] = ((short)hi[i] << 8) | lo[i] result[i] = ((ushort)hi[i] << 8) | lo[i]
int __ovld __cnfn get_image_depth(read_only image3d_t)
Return the image depth in pixels.
float __ovld __cnfn half_sqrt(float)
Compute square root.
void __ovld vstore_half16_rtn(float16, size_t, __global half *)
char8 __ovld __cnfn convert_char8_rtn(char8)
short3 __ovld __cnfn convert_short3(char3)
int8 __ovld __cnfn convert_int8_sat_rtn(char8)
char3 __ovld __cnfn convert_char3_sat_rtz(char3)
ulong8 __ovld __cnfn convert_ulong8(char8)
float __ovld __cnfn native_divide(float, float)
Compute x / y over an implementation-defined range.
uchar3 __ovld __cnfn convert_uchar3_sat_rtz(char3)
long3 __ovld __cnfn convert_long3_rte(char3)
char8 __ovld __cnfn convert_char8_sat_rtp(char8)
char __ovld __cnfn convert_char_rtn(char)
long3 __ovld __cnfn convert_long3_sat_rte(char3)
char __ovld __cnfn convert_char_sat_rte(char)
ulong16 __ovld __cnfn convert_ulong16_sat_rtn(char16)
uint2 __ovld __cnfn convert_uint2_rtz(char2)
long __ovld __cnfn convert_long_sat_rte(char)
int2 __ovld __cnfn convert_int2(char2)
int __ovld __cnfn isnan(float)
Test for a NaN.
int __ovld __cnfn any(char)
Returns 1 if the most significant bit in any component of x is set; otherwise returns 0.
short3 __ovld __cnfn convert_short3_rtn(char3)
int2 __ovld __cnfn convert_int2_sat_rtn(char2)
void __ovld write_mem_fence(cl_mem_fence_flags)
Write memory barrier that orders only stores.
short __ovld __cnfn convert_short_rtn(char)
ulong2 __ovld __cnfn convert_ulong2_rtz(char2)
uint2 __ovld __cnfn convert_uint2_sat(char2)
int4 __ovld __cnfn convert_int4_sat_rtp(char4)
uchar16 __ovld __cnfn convert_uchar16_sat_rtp(char16)
short3 __ovld __cnfn convert_short3_sat_rtz(char3)
uint2 __ovld __cnfn convert_uint2_rtn(char2)
int __ovld __cnfn convert_int_rte(char)
void __ovld atomic_work_item_fence(cl_mem_fence_flags, memory_order, memory_scope)
int8 __ovld __cnfn convert_int8_rte(char8)
uchar __ovld __cnfn convert_uchar_sat_rtp(char)
ulong3 __ovld __cnfn convert_ulong3_sat_rtz(char3)
float __ovld __cnfn tanpi(float)
Compute tan (PI * x).
ushort2 __ovld __cnfn convert_ushort2_sat_rtp(char2)
uchar2 __ovld __cnfn convert_uchar2_rtz(char2)
int __ovld __cnfn convert_int(char)
ushort16 __ovld __cnfn convert_ushort16_rtp(char16)
int __ovld __cnfn isgreater(float, float)
Returns the component-wise compare of x > y.
ulong4 __ovld __cnfn convert_ulong4_sat_rtp(char4)
int4 __ovld __cnfn convert_int4_rtp(char4)
float __ovld __cnfn native_sqrt(float)
Compute square root over an implementation-defined range.
void __ovld vstore_half3_rtz(float3, size_t, __global half *)
float __ovld __cnfn acospi(float)
Compute acos (x) / PI.
ulong __ovld __cnfn convert_ulong_sat_rtp(char)
void __ovld prefetch(const __global char *, size_t)
Prefetch num_elements * sizeof(gentype) bytes into the global cache.
short2 __ovld __cnfn convert_short2_rtn(char2)
size_t __ovld __cnfn get_global_size(uint)
Returns the number of global work-items specified for dimension identified by dimindx.
event_t __ovld async_work_group_copy(__local char *, const __global char *, size_t, event_t)
event_t async_work_group_copy ( __global gentype *dst, const __local gentype *src,...
int16 __ovld __cnfn convert_int16_rtz(char16)
ulong __ovld __cnfn convert_ulong_sat_rtz(char)
int __ovld __cnfn islessequal(float, float)
Returns the component-wise compare of x <= y.
long8 __ovld __cnfn convert_long8(char8)
uchar3 __ovld __cnfn convert_uchar3_rte(char3)
long __ovld __cnfn convert_long_sat_rtn(char)
uchar2 __ovld __cnfn convert_uchar2_sat_rte(char2)
ushort16 __ovld __cnfn convert_ushort16_sat_rtp(char16)
ushort16 __ovld __cnfn convert_ushort16_rtz(char16)
ushort2 __ovld __cnfn convert_ushort2_sat_rtn(char2)
char2 __ovld __cnfn shuffle2(char2, char2, uchar2)
int8 __ovld __cnfn convert_int8_sat_rtz(char8)
float4 __ovld __purefn vloada_half4(size_t, const __constant half *)
event_t __ovld async_work_group_strided_copy(__local char *, const __global char *, size_t, size_t, event_t)
Perform an async gather of num_elements gentype elements from src to dst.
long16 __ovld __cnfn convert_long16_sat_rte(char16)
uchar16 __ovld __cnfn convert_uchar16_rtp(char16)
float2 __ovld __purefn vloada_half2(size_t, const __constant half *)
For n = 1, 2, 4, 8 and 16 read sizeof (halfn) bytes of data from address (p + (offset * n)).
uchar2 __ovld __cnfn convert_uchar2_rtn(char2)
int __ovld __cnfn signbit(float)
Test for sign bit.
short16 __ovld __cnfn convert_short16_rte(char16)
ulong8 __ovld __cnfn convert_ulong8_sat_rtp(char8)
long8 __ovld __cnfn convert_long8_sat_rtz(char8)
char16 __ovld __purefn vload16(size_t, const __constant char *)
short8 __ovld __cnfn convert_short8_sat(char8)
float __ovld __cnfn half_log10(float)
Compute a base 10 logarithm.
float2 __ovld __cnfn convert_float2_rtn(char2)
void __ovld vstorea_half2_rtn(float2, size_t, __global half *)
char8 __ovld __purefn vload8(size_t, const __constant char *)
ulong3 __ovld __cnfn convert_ulong3_rtn(char3)
char4 __ovld __cnfn convert_char4_rtn(char4)
int __ovld atomic_cmpxchg(volatile __global int *, int, int)
Read the 32-bit value (referred to as old) stored at location pointed by p.
float __ovld __cnfn native_exp10(float)
Compute the base- 10 exponential of x over an implementation-defined range.
int3 __ovld __cnfn convert_int3_rte(char3)
int2 __ovld __cnfn convert_int2_sat_rte(char2)
long4 __ovld __cnfn convert_long4_sat_rtz(char4)
float __ovld __cnfn fast_distance(float, float)
Returns fast_length(p0 - p1).
ulong __ovld __cnfn convert_ulong_rte(char)
float16 __ovld __cnfn convert_float16_rtz(char16)
ulong8 __ovld __cnfn convert_ulong8_sat_rtz(char8)
uint __ovld __cnfn convert_uint_rte(char)
size_t __ovld __cnfn get_local_size(uint)
Returns the number of local work-items specified in dimension identified by dimindx.
uchar4 __ovld __cnfn convert_uchar4_sat_rtz(char4)
long3 __ovld __cnfn convert_long3(char3)
short8 __ovld __cnfn convert_short8_sat_rtp(char8)
uint16 __ovld __cnfn convert_uint16(char16)
short16 __ovld __cnfn convert_short16(char16)
long __ovld __cnfn convert_long_sat_rtp(char)
long3 __ovld __cnfn convert_long3_rtz(char3)
void __ovld vstore_half4_rtn(float4, size_t, __global half *)
char16 __ovld __cnfn convert_char16_sat(char16)
short4 __ovld __cnfn convert_short4_rte(char4)
void __ovld __conv barrier(cl_mem_fence_flags)
All work-items in a work-group executing the kernel on a processor must execute this function before ...
void __ovld vstore_half3_rtp(float3, size_t, __global half *)
float __ovld __cnfn convert_float(char)
int4 __ovld __cnfn convert_int4_sat(char4)
long16 __ovld __cnfn convert_long16_sat_rtz(char16)
uchar16 __ovld __cnfn convert_uchar16_rte(char16)
int8 __ovld __cnfn convert_int8_rtp(char8)
uint16 __ovld __cnfn convert_uint16_rtp(char16)
int __ovld __cnfn isunordered(float, float)
Test if arguments are unordered.
float __ovld __cnfn half_sin(float)
Compute sine.
ushort __ovld __cnfn convert_ushort_rte(char)
long2 __ovld __cnfn convert_long2_sat_rte(char2)
long16 __ovld __cnfn convert_long16_sat_rtn(char16)
ulong2 __ovld __cnfn convert_ulong2_sat_rte(char2)
uchar16 __ovld __cnfn convert_uchar16_sat_rtz(char16)
uchar4 __ovld __cnfn convert_uchar4_sat_rtp(char4)
ulong4 __ovld __cnfn convert_ulong4_rte(char4)
int __ovld __cnfn convert_int_sat_rtp(char)
ulong __ovld __cnfn convert_ulong_rtp(char)
ushort2 __ovld __cnfn convert_ushort2_rtp(char2)
uint16 __ovld __cnfn convert_uint16_sat(char16)
void __ovld vstorea_half16(float16, size_t, __global half *)
int __ovld atomic_fetch_min_explicit(volatile __global atomic_int *, int, memory_order, memory_scope)
void __ovld vstorea_half4_rte(float4, size_t, __global half *)
float __ovld __cnfn sinpi(float)
Compute sin (PI * x).
uchar8 __ovld __cnfn convert_uchar8_sat(char8)
ushort2 __ovld __cnfn convert_ushort2_rte(char2)
uint4 __ovld __purefn read_imageui(read_only image2d_t, sampler_t, int2)
char16 __ovld __cnfn convert_char16(char16)
float16 __ovld __cnfn convert_float16_rte(char16)
char2 __ovld __cnfn convert_char2_sat_rtz(char2)
uint __ovld __cnfn convert_uint(char)
int8 __ovld __cnfn convert_int8_rtn(char8)
int4 __ovld __cnfn convert_int4_rtn(char4)
float8 __ovld __cnfn convert_float8_rtp(char8)
float4 __ovld __cnfn cross(float4, float4)
Returns the cross product of p0.xyz and p1.xyz.
float4 __ovld __cnfn convert_float4_rtn(char4)
ushort4 __ovld __cnfn convert_ushort4_rte(char4)
int __ovld __cnfn get_image_channel_data_type(read_only image1d_t)
Return the channel data type.
uint3 __ovld __cnfn convert_uint3_sat_rtp(char3)
uint4 __ovld __cnfn convert_uint4(char4)
ushort2 __ovld __cnfn convert_ushort2_sat_rte(char2)
float __ovld __cnfn atan2pi(float, float)
Compute atan2 (y, x) / PI.
short __ovld __cnfn convert_short_sat(char)
uint2 __ovld __cnfn convert_uint2_sat_rte(char2)
ushort __ovld __cnfn convert_ushort_sat_rtn(char)
void __ovld vstore_half_rtn(float, size_t, __global half *)
void __ovld mem_fence(cl_mem_fence_flags)
Orders loads and stores of a work-item executing a kernel.
uint16 __ovld __cnfn convert_uint16_sat_rtz(char16)
ushort4 __ovld __cnfn convert_ushort4_rtn(char4)
uint4 __ovld __cnfn convert_uint4_sat_rtp(char4)
int __ovld __cnfn get_image_channel_order(read_only image1d_t)
Return the image channel order.
void __ovld vstore4(char4, size_t, __global char *)
uchar4 __ovld __cnfn convert_uchar4_rte(char4)
ushort2 __ovld __cnfn convert_ushort2(char2)
int __ovld __cnfn mul24(int, int)
Multiply two 24-bit integer values x and y.
float __ovld __cnfn native_log2(float)
Compute a base 2 logarithm over an implementationdefined range.
uint __ovld __cnfn convert_uint_sat_rtz(char)
void __ovld vstorea_half16_rtp(float16, size_t, __global half *)
uchar2 __ovld __cnfn convert_uchar2_sat_rtz(char2)
uint8 __ovld __cnfn convert_uint8_rtz(char8)
ushort4 __ovld __cnfn convert_ushort4(char4)
float __ovld lgamma_r(float, __global int *)
char16 __ovld __cnfn convert_char16_rtn(char16)
ulong8 __ovld __cnfn convert_ulong8_sat_rte(char8)
uint3 __ovld __cnfn convert_uint3_sat_rte(char3)
uint2 __ovld __cnfn convert_uint2(char2)
uint8 __ovld __cnfn convert_uint8_sat_rtz(char8)
uint16 __ovld __cnfn convert_uint16_rte(char16)
short2 __ovld __cnfn convert_short2_sat_rtn(char2)
char8 __ovld __cnfn convert_char8_rte(char8)
float2 __ovld __cnfn convert_float2_rtz(char2)
float __ovld __cnfn half_cos(float)
Compute cosine.
char3 __ovld __cnfn convert_char3_rte(char3)
int __ovld __cnfn convert_int_sat(char)
char2 __ovld __cnfn convert_char2_sat_rtn(char2)
ushort __ovld __cnfn convert_ushort_rtp(char)
ulong3 __ovld __cnfn convert_ulong3_rte(char3)
ulong2 __ovld __cnfn convert_ulong2_rtp(char2)
ushort16 __ovld __cnfn convert_ushort16_sat(char16)
short __ovld __cnfn convert_short(char)
short8 __ovld __cnfn convert_short8_rtn(char8)
char4 __ovld __purefn vload4(size_t, const __constant char *)
long3 __ovld __cnfn convert_long3_rtn(char3)
float __ovld __cnfn rootn(float, int)
Compute x to the power 1/y.
void __ovld vstorea_half8_rtp(float8, size_t, __global half *)
char2 __ovld __cnfn convert_char2_sat(char2)
void __ovld read_mem_fence(cl_mem_fence_flags)
Read memory barrier that orders only loads.
ushort4 __ovld __cnfn convert_ushort4_sat_rte(char4)
uchar3 __ovld __cnfn convert_uchar3_sat_rtp(char3)
short4 __ovld __cnfn convert_short4(char4)
ulong3 __ovld __cnfn convert_ulong3_rtz(char3)
float __ovld __cnfn half_rsqrt(float)
Compute inverse square root.
uchar16 __ovld __cnfn convert_uchar16_rtn(char16)
char3 __ovld __purefn vload3(size_t, const __constant char *)
ulong __ovld __cnfn convert_ulong_sat_rtn(char)
short16 __ovld __cnfn convert_short16_rtz(char16)
long2 __ovld __cnfn convert_long2_rte(char2)
void __ovld vstore_half2_rtp(float2, size_t, __global half *)
float __ovld __cnfn mad(float, float, float)
mad approximates a * b + c.
uint4 __ovld __cnfn convert_uint4_rte(char4)
ushort8 __ovld __cnfn convert_ushort8(char8)
int8 __ovld __cnfn convert_int8_rtz(char8)
ushort __ovld __cnfn convert_ushort_sat_rtp(char)
int3 __ovld __cnfn convert_int3_sat(char3)
void __ovld __conv work_group_barrier(cl_mem_fence_flags, memory_scope)
float16 __ovld __purefn vloada_half16(size_t, const __constant half *)
void __ovld vstore_half3_rte(float3, size_t, __global half *)
#define atomic_fetch_xor(object, operand)
#define atomic_store(object, desired)
#define atomic_compare_exchange_weak(object, expected, desired)
#define atomic_compare_exchange_weak_explicit
#define atomic_compare_exchange_strong(object, expected, desired)
#define atomic_exchange(object, desired)
#define atomic_fetch_or(object, operand)
#define atomic_flag_clear(object)
#define atomic_fetch_and_explicit
#define atomic_fetch_sub(object, operand)
#define atomic_fetch_sub_explicit
#define atomic_flag_test_and_set_explicit(object, order)
#define atomic_fetch_xor_explicit
#define atomic_store_explicit
#define atomic_flag_test_and_set(object)
#define atomic_fetch_or_explicit
#define atomic_load_explicit
#define atomic_flag_clear_explicit(object, order)
#define atomic_exchange_explicit
#define atomic_load(object)
#define atomic_fetch_and(object, operand)
#define atomic_compare_exchange_strong_explicit
#define atomic_fetch_add_explicit
#define atomic_fetch_add(object, operand)
#define copysign(__x, __y)
#define remquo(__x, __y, __z)
#define nextafter(__x, __y)
#define remainder(__x, __y)
#define fma(__x, __y, __z)