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_khr_kernel_clock)
17318#if defined(__opencl_c_kernel_clock_scope_device)
17320uint2
__ovld clock_read_hilo_device();
17322#if defined(__opencl_c_kernel_clock_scope_work_group)
17324uint2
__ovld clock_read_hilo_work_group();
17326#if defined(__opencl_c_kernel_clock_scope_sub_group)
17328uint2
__ovld clock_read_hilo_sub_group();
17332#if defined(cl_intel_subgroups)
17358float __ovld __conv intel_sub_group_shuffle_down(
float cur,
float next,
uint );
17359float2
__ovld __conv intel_sub_group_shuffle_down( float2 cur, float2 next,
uint );
17360float3
__ovld __conv intel_sub_group_shuffle_down( float3 cur, float3 next,
uint );
17361float4
__ovld __conv intel_sub_group_shuffle_down( float4 cur, float4 next,
uint );
17362float8
__ovld __conv intel_sub_group_shuffle_down( float8 cur, float8 next,
uint );
17363float16
__ovld __conv intel_sub_group_shuffle_down( float16 cur, float16 next,
uint );
17366int2
__ovld __conv intel_sub_group_shuffle_down( int2 cur, int2 next,
uint );
17367int3
__ovld __conv intel_sub_group_shuffle_down( int3 cur, int3 next,
uint );
17368int4
__ovld __conv intel_sub_group_shuffle_down( int4 cur, int4 next,
uint );
17369int8
__ovld __conv intel_sub_group_shuffle_down( int8 cur, int8 next,
uint );
17370int16
__ovld __conv intel_sub_group_shuffle_down( int16 cur, int16 next,
uint );
17373uint2
__ovld __conv intel_sub_group_shuffle_down( uint2 cur, uint2 next,
uint );
17374uint3
__ovld __conv intel_sub_group_shuffle_down( uint3 cur, uint3 next,
uint );
17375uint4
__ovld __conv intel_sub_group_shuffle_down( uint4 cur, uint4 next,
uint );
17376uint8
__ovld __conv intel_sub_group_shuffle_down( uint8 cur, uint8 next,
uint );
17377uint16
__ovld __conv intel_sub_group_shuffle_down( uint16 cur, uint16 next,
uint );
17379long __ovld __conv intel_sub_group_shuffle_down(
long prev,
long cur,
uint );
17382float __ovld __conv intel_sub_group_shuffle_up(
float prev,
float cur,
uint );
17383float2
__ovld __conv intel_sub_group_shuffle_up( float2 prev, float2 cur,
uint );
17384float3
__ovld __conv intel_sub_group_shuffle_up( float3 prev, float3 cur,
uint );
17385float4
__ovld __conv intel_sub_group_shuffle_up( float4 prev, float4 cur,
uint );
17386float8
__ovld __conv intel_sub_group_shuffle_up( float8 prev, float8 cur,
uint );
17387float16
__ovld __conv intel_sub_group_shuffle_up( float16 prev, float16 cur,
uint );
17390int2
__ovld __conv intel_sub_group_shuffle_up( int2 prev, int2 cur,
uint );
17391int3
__ovld __conv intel_sub_group_shuffle_up( int3 prev, int3 cur,
uint );
17392int4
__ovld __conv intel_sub_group_shuffle_up( int4 prev, int4 cur,
uint );
17393int8
__ovld __conv intel_sub_group_shuffle_up( int8 prev, int8 cur,
uint );
17394int16
__ovld __conv intel_sub_group_shuffle_up( int16 prev, int16 cur,
uint );
17397uint2
__ovld __conv intel_sub_group_shuffle_up( uint2 prev, uint2 cur,
uint );
17398uint3
__ovld __conv intel_sub_group_shuffle_up( uint3 prev, uint3 cur,
uint );
17399uint4
__ovld __conv intel_sub_group_shuffle_up( uint4 prev, uint4 cur,
uint );
17400uint8
__ovld __conv intel_sub_group_shuffle_up( uint8 prev, uint8 cur,
uint );
17401uint16
__ovld __conv intel_sub_group_shuffle_up( uint16 prev, uint16 cur,
uint );
17403long __ovld __conv intel_sub_group_shuffle_up(
long prev,
long cur,
uint );
17430#if defined(__opencl_c_images)
17432uint2
__ovld __conv intel_sub_group_block_read2(read_only image2d_t, int2);
17433uint4
__ovld __conv intel_sub_group_block_read4(read_only image2d_t, int2);
17434uint8
__ovld __conv intel_sub_group_block_read8(read_only image2d_t, int2);
17437#if defined(__opencl_c_read_write_images)
17439uint2
__ovld __conv intel_sub_group_block_read2(read_write image2d_t, int2);
17440uint4
__ovld __conv intel_sub_group_block_read4(read_write image2d_t, int2);
17441uint8
__ovld __conv intel_sub_group_block_read8(read_write image2d_t, int2);
17449#if defined(__opencl_c_images)
17450void __ovld __conv intel_sub_group_block_write(write_only image2d_t, int2,
uint);
17451void __ovld __conv intel_sub_group_block_write2(write_only image2d_t, int2, uint2);
17452void __ovld __conv intel_sub_group_block_write4(write_only image2d_t, int2, uint4);
17453void __ovld __conv intel_sub_group_block_write8(write_only image2d_t, int2, uint8);
17456#if defined(__opencl_c_read_write_images)
17457void __ovld __conv intel_sub_group_block_write(read_write image2d_t, int2,
uint);
17458void __ovld __conv intel_sub_group_block_write2(read_write image2d_t, int2, uint2);
17459void __ovld __conv intel_sub_group_block_write4(read_write image2d_t, int2, uint4);
17460void __ovld __conv intel_sub_group_block_write8(read_write image2d_t, int2, uint8);
17464void __ovld __conv intel_sub_group_block_write2( __global
uint* p, uint2 data );
17465void __ovld __conv intel_sub_group_block_write4( __global
uint* p, uint4 data );
17466void __ovld __conv intel_sub_group_block_write8( __global
uint* p, uint8 data );
17470half
__ovld __conv intel_sub_group_shuffle_down( half prev, half cur,
uint );
17471half
__ovld __conv intel_sub_group_shuffle_up( half prev, half cur,
uint );
17475#if defined(cl_khr_fp64)
17477double __ovld __conv intel_sub_group_shuffle_down(
double prev,
double cur,
uint );
17478double __ovld __conv intel_sub_group_shuffle_up(
double prev,
double cur,
uint );
17484#if defined(cl_intel_subgroups_short)
17485short __ovld __conv intel_sub_group_broadcast(
short ,
uint sub_group_local_id );
17486short2
__ovld __conv intel_sub_group_broadcast( short2,
uint sub_group_local_id );
17487short3
__ovld __conv intel_sub_group_broadcast( short3,
uint sub_group_local_id );
17488short4
__ovld __conv intel_sub_group_broadcast( short4,
uint sub_group_local_id );
17489short8
__ovld __conv intel_sub_group_broadcast( short8,
uint sub_group_local_id );
17492ushort2
__ovld __conv intel_sub_group_broadcast( ushort2,
uint sub_group_local_id );
17493ushort3
__ovld __conv intel_sub_group_broadcast( ushort3,
uint sub_group_local_id );
17494ushort4
__ovld __conv intel_sub_group_broadcast( ushort4,
uint sub_group_local_id );
17495ushort8
__ovld __conv intel_sub_group_broadcast( ushort8,
uint sub_group_local_id );
17511short __ovld __conv intel_sub_group_shuffle_down(
short cur,
short next,
uint );
17512short2
__ovld __conv intel_sub_group_shuffle_down( short2 cur, short2 next,
uint );
17513short3
__ovld __conv intel_sub_group_shuffle_down( short3 cur, short3 next,
uint );
17514short4
__ovld __conv intel_sub_group_shuffle_down( short4 cur, short4 next,
uint );
17515short8
__ovld __conv intel_sub_group_shuffle_down( short8 cur, short8 next,
uint );
17516short16
__ovld __conv intel_sub_group_shuffle_down( short16 cur, short16 next,
uint );
17519ushort2
__ovld __conv intel_sub_group_shuffle_down( ushort2 cur, ushort2 next,
uint );
17520ushort3
__ovld __conv intel_sub_group_shuffle_down( ushort3 cur, ushort3 next,
uint );
17521ushort4
__ovld __conv intel_sub_group_shuffle_down( ushort4 cur, ushort4 next,
uint );
17522ushort8
__ovld __conv intel_sub_group_shuffle_down( ushort8 cur, ushort8 next,
uint );
17523ushort16
__ovld __conv intel_sub_group_shuffle_down( ushort16 cur, ushort16 next,
uint );
17525short __ovld __conv intel_sub_group_shuffle_up(
short cur,
short next,
uint );
17526short2
__ovld __conv intel_sub_group_shuffle_up( short2 cur, short2 next,
uint );
17527short3
__ovld __conv intel_sub_group_shuffle_up( short3 cur, short3 next,
uint );
17528short4
__ovld __conv intel_sub_group_shuffle_up( short4 cur, short4 next,
uint );
17529short8
__ovld __conv intel_sub_group_shuffle_up( short8 cur, short8 next,
uint );
17530short16
__ovld __conv intel_sub_group_shuffle_up( short16 cur, short16 next,
uint );
17533ushort2
__ovld __conv intel_sub_group_shuffle_up( ushort2 cur, ushort2 next,
uint );
17534ushort3
__ovld __conv intel_sub_group_shuffle_up( ushort3 cur, ushort3 next,
uint );
17535ushort4
__ovld __conv intel_sub_group_shuffle_up( ushort4 cur, ushort4 next,
uint );
17536ushort8
__ovld __conv intel_sub_group_shuffle_up( ushort8 cur, ushort8 next,
uint );
17537ushort16
__ovld __conv intel_sub_group_shuffle_up( ushort16 cur, ushort16 next,
uint );
17553short __ovld __conv intel_sub_group_reduce_add(
short x );
17555short __ovld __conv intel_sub_group_reduce_min(
short x );
17557short __ovld __conv intel_sub_group_reduce_max(
short x );
17560short __ovld __conv intel_sub_group_scan_exclusive_add(
short x );
17562short __ovld __conv intel_sub_group_scan_exclusive_min(
short x );
17564short __ovld __conv intel_sub_group_scan_exclusive_max(
short x );
17567short __ovld __conv intel_sub_group_scan_inclusive_add(
short x );
17569short __ovld __conv intel_sub_group_scan_inclusive_min(
short x );
17571short __ovld __conv intel_sub_group_scan_inclusive_max(
short x );
17574#if defined(__opencl_c_images)
17575uint __ovld __conv intel_sub_group_block_read_ui(read_only image2d_t, int2);
17576uint2
__ovld __conv intel_sub_group_block_read_ui2(read_only image2d_t, int2);
17577uint4
__ovld __conv intel_sub_group_block_read_ui4(read_only image2d_t, int2);
17578uint8
__ovld __conv intel_sub_group_block_read_ui8(read_only image2d_t, int2);
17581#if defined(__opencl_c_read_write_images)
17582uint __ovld __conv intel_sub_group_block_read_ui(read_write image2d_t, int2);
17583uint2
__ovld __conv intel_sub_group_block_read_ui2(read_write image2d_t, int2);
17584uint4
__ovld __conv intel_sub_group_block_read_ui4(read_write image2d_t, int2);
17585uint8
__ovld __conv intel_sub_group_block_read_ui8(read_write image2d_t, int2);
17589uint2
__ovld __conv intel_sub_group_block_read_ui2(
const __global
uint* p );
17590uint4
__ovld __conv intel_sub_group_block_read_ui4(
const __global
uint* p );
17591uint8
__ovld __conv intel_sub_group_block_read_ui8(
const __global
uint* p );
17593#if defined(__opencl_c_images)
17594void __ovld __conv intel_sub_group_block_write_ui(read_only image2d_t, int2,
uint);
17595void __ovld __conv intel_sub_group_block_write_ui2(read_only image2d_t, int2, uint2);
17596void __ovld __conv intel_sub_group_block_write_ui4(read_only image2d_t, int2, uint4);
17597void __ovld __conv intel_sub_group_block_write_ui8(read_only image2d_t, int2, uint8);
17600#if defined(__opencl_c_read_write_images)
17601void __ovld __conv intel_sub_group_block_write_ui(read_write image2d_t, int2,
uint);
17602void __ovld __conv intel_sub_group_block_write_ui2(read_write image2d_t, int2, uint2);
17603void __ovld __conv intel_sub_group_block_write_ui4(read_write image2d_t, int2, uint4);
17604void __ovld __conv intel_sub_group_block_write_ui8(read_write image2d_t, int2, uint8);
17608void __ovld __conv intel_sub_group_block_write_ui2( __global
uint* p, uint2 data );
17609void __ovld __conv intel_sub_group_block_write_ui4( __global
uint* p, uint4 data );
17610void __ovld __conv intel_sub_group_block_write_ui8( __global
uint* p, uint8 data );
17612#if defined(__opencl_c_images)
17614ushort2
__ovld __conv intel_sub_group_block_read_us2(read_only image2d_t, int2);
17615ushort4
__ovld __conv intel_sub_group_block_read_us4(read_only image2d_t, int2);
17616ushort8
__ovld __conv intel_sub_group_block_read_us8(read_only image2d_t, int2);
17619#if defined(__opencl_c_read_write_images)
17621ushort2
__ovld __conv intel_sub_group_block_read_us2(read_write image2d_t, int2);
17622ushort4
__ovld __conv intel_sub_group_block_read_us4(read_write image2d_t, int2);
17623ushort8
__ovld __conv intel_sub_group_block_read_us8(read_write image2d_t, int2);
17631#if defined(__opencl_c_images)
17632void __ovld __conv intel_sub_group_block_write_us(write_only image2d_t, int2,
ushort);
17633void __ovld __conv intel_sub_group_block_write_us2(write_only image2d_t, int2, ushort2);
17634void __ovld __conv intel_sub_group_block_write_us4(write_only image2d_t, int2, ushort4);
17635void __ovld __conv intel_sub_group_block_write_us8(write_only image2d_t, int2, ushort8);
17638#if defined(__opencl_c_read_write_images)
17639void __ovld __conv intel_sub_group_block_write_us(read_write image2d_t, int2,
ushort);
17640void __ovld __conv intel_sub_group_block_write_us2(read_write image2d_t, int2, ushort2);
17641void __ovld __conv intel_sub_group_block_write_us4(read_write image2d_t, int2, ushort4);
17642void __ovld __conv intel_sub_group_block_write_us8(read_write image2d_t, int2, ushort8);
17646void __ovld __conv intel_sub_group_block_write_us2( __global
ushort* p, ushort2 data );
17647void __ovld __conv intel_sub_group_block_write_us4( __global
ushort* p, ushort4 data );
17648void __ovld __conv intel_sub_group_block_write_us8( __global
ushort* p, ushort8 data );
17651#ifdef cl_intel_device_side_avc_motion_estimation
17652#pragma OPENCL EXTENSION cl_intel_device_side_avc_motion_estimation : begin
17656intel_sub_group_avc_mce_get_default_inter_base_multi_reference_penalty(
17658ulong __ovld intel_sub_group_avc_mce_get_default_inter_shape_penalty(
17660uchar __ovld intel_sub_group_avc_mce_get_default_inter_direction_penalty(
17662uint __ovld intel_sub_group_avc_mce_get_default_intra_luma_shape_penalty(
17665intel_sub_group_avc_mce_get_default_inter_motion_vector_cost_table(
17667uchar __ovld intel_sub_group_avc_mce_get_default_intra_luma_mode_penalty(
17670uint2
__ovld intel_sub_group_avc_mce_get_default_high_penalty_cost_table();
17671uint2
__ovld intel_sub_group_avc_mce_get_default_medium_penalty_cost_table();
17672uint2
__ovld intel_sub_group_avc_mce_get_default_low_penalty_cost_table();
17673uint __ovld intel_sub_group_avc_mce_get_default_non_dc_luma_intra_penalty();
17675intel_sub_group_avc_mce_get_default_intra_chroma_mode_base_penalty();
17677intel_sub_group_avc_mce_payload_t
__ovld
17678intel_sub_group_avc_mce_set_inter_base_multi_reference_penalty(
17679 uchar reference_base_penalty, intel_sub_group_avc_mce_payload_t payload);
17680intel_sub_group_avc_mce_payload_t
__ovld
17681intel_sub_group_avc_mce_set_inter_shape_penalty(
17682 ulong packed_shape_penalty, intel_sub_group_avc_mce_payload_t payload);
17683intel_sub_group_avc_mce_payload_t
__ovld
17684intel_sub_group_avc_mce_set_inter_direction_penalty(
17685 uchar direction_cost, intel_sub_group_avc_mce_payload_t payload);
17686intel_sub_group_avc_mce_payload_t
__ovld
17687intel_sub_group_avc_mce_set_motion_vector_cost_function(
17688 ulong packed_cost_center_delta, uint2 packed_cost_table,
17689 uchar cost_precision, intel_sub_group_avc_mce_payload_t payload);
17690intel_sub_group_avc_mce_payload_t
__ovld
17691intel_sub_group_avc_mce_set_ac_only_haar(
17692 intel_sub_group_avc_mce_payload_t payload);
17693intel_sub_group_avc_mce_payload_t
__ovld
17694intel_sub_group_avc_mce_set_source_interlaced_field_polarity(
17695 uchar src_field_polarity, intel_sub_group_avc_mce_payload_t payload);
17696intel_sub_group_avc_mce_payload_t
__ovld
17697intel_sub_group_avc_mce_set_single_reference_interlaced_field_polarity(
17698 uchar ref_field_polarity, intel_sub_group_avc_mce_payload_t payload);
17699intel_sub_group_avc_mce_payload_t
__ovld
17700intel_sub_group_avc_mce_set_dual_reference_interlaced_field_polarities(
17701 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
17702 intel_sub_group_avc_mce_payload_t payload);
17704ulong __ovld intel_sub_group_avc_mce_get_motion_vectors(
17705 intel_sub_group_avc_mce_result_t result);
17706ushort __ovld intel_sub_group_avc_mce_get_inter_distortions(
17707 intel_sub_group_avc_mce_result_t result);
17708ushort __ovld intel_sub_group_avc_mce_get_best_inter_distortion(
17709 intel_sub_group_avc_mce_result_t result);
17710uchar __ovld intel_sub_group_avc_mce_get_inter_major_shape(
17711 intel_sub_group_avc_mce_result_t result);
17712uchar __ovld intel_sub_group_avc_mce_get_inter_minor_shapes(
17713 intel_sub_group_avc_mce_result_t result);
17714uchar __ovld intel_sub_group_avc_mce_get_inter_directions(
17715 intel_sub_group_avc_mce_result_t result);
17716uchar __ovld intel_sub_group_avc_mce_get_inter_motion_vector_count(
17717 intel_sub_group_avc_mce_result_t result);
17718uint __ovld intel_sub_group_avc_mce_get_inter_reference_ids(
17719 intel_sub_group_avc_mce_result_t result);
17721intel_sub_group_avc_mce_get_inter_reference_interlaced_field_polarities(
17722 uint packed_reference_ids,
uint packed_reference_parameter_field_polarities,
17723 intel_sub_group_avc_mce_result_t result);
17726intel_sub_group_avc_ime_payload_t
__ovld
17727intel_sub_group_avc_ime_initialize(
17728 ushort2 src_coord,
uchar partition_mask,
uchar sad_adjustment);
17729intel_sub_group_avc_ime_payload_t
__ovld
17730intel_sub_group_avc_ime_set_single_reference(
17731 short2 ref_offset,
uchar search_window_config,
17732 intel_sub_group_avc_ime_payload_t payload);
17733intel_sub_group_avc_ime_payload_t
__ovld
17734intel_sub_group_avc_ime_set_dual_reference(
17735 short2 fwd_ref_offset, short2 bwd_ref_offset,
uchar search_window_config,
17736 intel_sub_group_avc_ime_payload_t payload);
17737intel_sub_group_avc_ime_payload_t
__ovld
17738intel_sub_group_avc_ime_set_max_motion_vector_count(
17739 uchar max_motion_vector_count, intel_sub_group_avc_ime_payload_t payload);
17740intel_sub_group_avc_ime_payload_t
__ovld
17741intel_sub_group_avc_ime_set_unidirectional_mix_disable(
17742 intel_sub_group_avc_ime_payload_t payload);
17743intel_sub_group_avc_ime_payload_t
__ovld
17744intel_sub_group_avc_ime_set_early_search_termination_threshold(
17745 uchar threshold, intel_sub_group_avc_ime_payload_t payload);
17746intel_sub_group_avc_ime_payload_t
__ovld
17747intel_sub_group_avc_ime_set_weighted_sad(
17748 uint packed_sad_weights, intel_sub_group_avc_ime_payload_t payload);
17750__attribute__((deprecated(
"If you use the latest Intel driver, please use "
17751 "intel_sub_group_avc_ime_ref_window_size instead",
17752 "intel_sub_group_avc_ime_ref_window_size")))
17754intel_sub_group_ime_ref_window_size(
uchar search_window_config,
char dual_ref);
17755ushort2
__ovld intel_sub_group_avc_ime_ref_window_size(
17756 uchar search_window_config,
char dual_ref);
17757short2
__ovld intel_sub_group_avc_ime_adjust_ref_offset(
17758 short2 ref_offset, ushort2 src_coord, ushort2 ref_window_size,
17759 ushort2 image_size);
17761#if defined(__opencl_c_images)
17762intel_sub_group_avc_ime_result_t
__ovld
17763intel_sub_group_avc_ime_evaluate_with_single_reference(
17764 read_only image2d_t src_image, read_only image2d_t ref_image,
17765 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload);
17766intel_sub_group_avc_ime_result_t
__ovld
17767intel_sub_group_avc_ime_evaluate_with_dual_reference(
17768 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17769 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17770 intel_sub_group_avc_ime_payload_t payload);
17771intel_sub_group_avc_ime_result_single_reference_streamout_t
__ovld
17772intel_sub_group_avc_ime_evaluate_with_single_reference_streamout(
17773 read_only image2d_t src_image, read_only image2d_t ref_image,
17774 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload);
17775intel_sub_group_avc_ime_result_dual_reference_streamout_t
__ovld
17776intel_sub_group_avc_ime_evaluate_with_dual_reference_streamout(
17777 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17778 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17779 intel_sub_group_avc_ime_payload_t payload);
17780intel_sub_group_avc_ime_result_t
__ovld
17781intel_sub_group_avc_ime_evaluate_with_single_reference_streamin(
17782 read_only image2d_t src_image, read_only image2d_t ref_image,
17783 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload,
17784 intel_sub_group_avc_ime_single_reference_streamin_t streamin_components);
17785intel_sub_group_avc_ime_result_t
__ovld
17786intel_sub_group_avc_ime_evaluate_with_dual_reference_streamin(
17787 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17788 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17789 intel_sub_group_avc_ime_payload_t payload,
17790 intel_sub_group_avc_ime_dual_reference_streamin_t streamin_components);
17791intel_sub_group_avc_ime_result_single_reference_streamout_t
__ovld
17792intel_sub_group_avc_ime_evaluate_with_single_reference_streaminout(
17793 read_only image2d_t src_image, read_only image2d_t ref_image,
17794 sampler_t vme_media_sampler, intel_sub_group_avc_ime_payload_t payload,
17795 intel_sub_group_avc_ime_single_reference_streamin_t streamin_components);
17796intel_sub_group_avc_ime_result_dual_reference_streamout_t
__ovld
17797intel_sub_group_avc_ime_evaluate_with_dual_reference_streaminout(
17798 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17799 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17800 intel_sub_group_avc_ime_payload_t payload,
17801 intel_sub_group_avc_ime_dual_reference_streamin_t streamin_components);
17804intel_sub_group_avc_ime_single_reference_streamin_t
__ovld
17805intel_sub_group_avc_ime_get_single_reference_streamin(
17806 intel_sub_group_avc_ime_result_single_reference_streamout_t result);
17807intel_sub_group_avc_ime_dual_reference_streamin_t
__ovld
17808intel_sub_group_avc_ime_get_dual_reference_streamin(
17809 intel_sub_group_avc_ime_result_dual_reference_streamout_t result);
17810intel_sub_group_avc_ime_result_t
__ovld
17811intel_sub_group_avc_ime_strip_single_reference_streamout(
17812 intel_sub_group_avc_ime_result_single_reference_streamout_t result);
17813intel_sub_group_avc_ime_result_t
__ovld
17814intel_sub_group_avc_ime_strip_dual_reference_streamout(
17815 intel_sub_group_avc_ime_result_dual_reference_streamout_t result);
17817uint __ovld intel_sub_group_avc_ime_get_streamout_major_shape_motion_vectors(
17818 intel_sub_group_avc_ime_result_single_reference_streamout_t result,
17819 uchar major_shape);
17820ushort __ovld intel_sub_group_avc_ime_get_streamout_major_shape_distortions(
17821 intel_sub_group_avc_ime_result_single_reference_streamout_t result,
17822 uchar major_shape);
17823uchar __ovld intel_sub_group_avc_ime_get_streamout_major_shape_reference_ids(
17824 intel_sub_group_avc_ime_result_single_reference_streamout_t result,
17825 uchar major_shape);
17826uint __ovld intel_sub_group_avc_ime_get_streamout_major_shape_motion_vectors(
17827 intel_sub_group_avc_ime_result_dual_reference_streamout_t result,
17829ushort __ovld intel_sub_group_avc_ime_get_streamout_major_shape_distortions(
17830 intel_sub_group_avc_ime_result_dual_reference_streamout_t result,
17832uchar __ovld intel_sub_group_avc_ime_get_streamout_major_shape_reference_ids(
17833 intel_sub_group_avc_ime_result_dual_reference_streamout_t result,
17836uchar __ovld intel_sub_group_avc_ime_get_border_reached(
17837 uchar image_select, intel_sub_group_avc_ime_result_t result);
17838uchar __ovld intel_sub_group_avc_ime_get_truncated_search_indication(
17839 intel_sub_group_avc_ime_result_t result);
17841intel_sub_group_avc_ime_get_unidirectional_early_search_termination(
17842 intel_sub_group_avc_ime_result_t result);
17843uint __ovld intel_sub_group_avc_ime_get_weighting_pattern_minimum_motion_vector(
17844 intel_sub_group_avc_ime_result_t result);
17845ushort __ovld intel_sub_group_avc_ime_get_weighting_pattern_minimum_distortion(
17846 intel_sub_group_avc_ime_result_t result);
17849intel_sub_group_avc_ref_payload_t
__ovld
17850intel_sub_group_avc_fme_initialize(
17851 ushort2 src_coord,
ulong motion_vectors,
uchar major_shapes,
17853 uchar sad_adjustment);
17854intel_sub_group_avc_ref_payload_t
__ovld
17855intel_sub_group_avc_bme_initialize(
17856 ushort2 src_coord,
ulong motion_vectors,
uchar major_shapes,
17858 uchar bidirectional_weight,
uchar sad_adjustment);
17860intel_sub_group_avc_ref_payload_t
__ovld
17861intel_sub_group_avc_ref_set_bidirectional_mix_disable(
17862 intel_sub_group_avc_ref_payload_t payload);
17863intel_sub_group_avc_ref_payload_t
__ovld
17864intel_sub_group_avc_ref_set_bilinear_filter_enable(
17865 intel_sub_group_avc_ref_payload_t payload);
17867#if defined(__opencl_c_images)
17868intel_sub_group_avc_ref_result_t
__ovld
17869intel_sub_group_avc_ref_evaluate_with_single_reference(
17870 read_only image2d_t src_image, read_only image2d_t ref_image,
17871 sampler_t vme_media_sampler, intel_sub_group_avc_ref_payload_t payload);
17872intel_sub_group_avc_ref_result_t
__ovld
17873intel_sub_group_avc_ref_evaluate_with_dual_reference(
17874 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17875 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17876 intel_sub_group_avc_ref_payload_t payload);
17877intel_sub_group_avc_ref_result_t
__ovld
17878intel_sub_group_avc_ref_evaluate_with_multi_reference(
17879 read_only image2d_t src_image,
uint packed_reference_ids,
17880 sampler_t vme_media_sampler, intel_sub_group_avc_ref_payload_t payload);
17881intel_sub_group_avc_ref_result_t
__ovld
17882intel_sub_group_avc_ref_evaluate_with_multi_reference(
17883 read_only image2d_t src_image,
uint packed_reference_ids,
17884 uchar packed_reference_field_polarities, sampler_t vme_media_sampler,
17885 intel_sub_group_avc_ref_payload_t payload);
17889intel_sub_group_avc_sic_payload_t
__ovld
17890intel_sub_group_avc_sic_initialize(
17891 ushort2 src_coord);
17892intel_sub_group_avc_sic_payload_t
__ovld
17893intel_sub_group_avc_sic_configure_skc(
17894 uint skip_block_partition_type,
uint skip_motion_vector_mask,
17895 ulong motion_vectors,
uchar bidirectional_weight,
uchar skip_sad_adjustment,
17896 intel_sub_group_avc_sic_payload_t payload);
17897intel_sub_group_avc_sic_payload_t
__ovld intel_sub_group_avc_sic_configure_ipe(
17898 uchar luma_intra_partition_mask,
uchar intra_neighbour_availability,
17899 uchar left_edge_luma_pixels,
uchar upper_left_corner_luma_pixel,
17900 uchar upper_edge_luma_pixels,
uchar upper_right_edge_luma_pixels,
17901 uchar intra_sad_adjustment, intel_sub_group_avc_sic_payload_t payload);
17902intel_sub_group_avc_sic_payload_t
__ovld intel_sub_group_avc_sic_configure_ipe(
17903 uchar luma_intra_partition_mask,
uchar intra_neighbour_availability,
17904 uchar left_edge_luma_pixels,
uchar upper_left_corner_luma_pixel,
17905 uchar upper_edge_luma_pixels,
uchar upper_right_edge_luma_pixels,
17906 ushort left_edge_chroma_pixels,
ushort upper_left_corner_chroma_pixel,
17907 ushort upper_edge_chroma_pixels,
uchar intra_sad_adjustment,
17908 intel_sub_group_avc_sic_payload_t payload);
17910intel_sub_group_avc_sic_get_motion_vector_mask(
17911 uint skip_block_partition_type,
uchar direction);
17913intel_sub_group_avc_sic_payload_t
__ovld
17914intel_sub_group_avc_sic_set_intra_luma_shape_penalty(
17915 uint packed_shape_cost, intel_sub_group_avc_sic_payload_t payload);
17916intel_sub_group_avc_sic_payload_t
__ovld
17917intel_sub_group_avc_sic_set_intra_luma_mode_cost_function(
17918 uchar luma_mode_penalty,
uint luma_packed_neighbor_modes,
17919 uint luma_packed_non_dc_penalty, intel_sub_group_avc_sic_payload_t payload);
17920intel_sub_group_avc_sic_payload_t
__ovld
17921intel_sub_group_avc_sic_set_intra_chroma_mode_cost_function(
17922 uchar chroma_mode_penalty, intel_sub_group_avc_sic_payload_t payload);
17924intel_sub_group_avc_sic_payload_t
__ovld
17925intel_sub_group_avc_sic_set_skc_bilinear_filter_enable(
17926 intel_sub_group_avc_sic_payload_t payload);
17927intel_sub_group_avc_sic_payload_t
__ovld
17928intel_sub_group_avc_sic_set_skc_forward_transform_enable(
17929 ulong packed_sad_coefficients, intel_sub_group_avc_sic_payload_t payload);
17930intel_sub_group_avc_sic_payload_t
__ovld
17931intel_sub_group_avc_sic_set_block_based_raw_skip_sad(
17932 uchar block_based_skip_type,
17933 intel_sub_group_avc_sic_payload_t payload);
17935#if defined(__opencl_c_images)
17936intel_sub_group_avc_sic_result_t
__ovld
17937intel_sub_group_avc_sic_evaluate_ipe(
17938 read_only image2d_t src_image, sampler_t vme_media_sampler,
17939 intel_sub_group_avc_sic_payload_t payload);
17940intel_sub_group_avc_sic_result_t
__ovld
17941intel_sub_group_avc_sic_evaluate_with_single_reference(
17942 read_only image2d_t src_image, read_only image2d_t ref_image,
17943 sampler_t vme_media_sampler, intel_sub_group_avc_sic_payload_t payload);
17944intel_sub_group_avc_sic_result_t
__ovld
17945intel_sub_group_avc_sic_evaluate_with_dual_reference(
17946 read_only image2d_t src_image, read_only image2d_t fwd_ref_image,
17947 read_only image2d_t bwd_ref_image, sampler_t vme_media_sampler,
17948 intel_sub_group_avc_sic_payload_t payload);
17949intel_sub_group_avc_sic_result_t
__ovld
17950intel_sub_group_avc_sic_evaluate_with_multi_reference(
17951 read_only image2d_t src_image,
uint packed_reference_ids,
17952 sampler_t vme_media_sampler, intel_sub_group_avc_sic_payload_t payload);
17953intel_sub_group_avc_sic_result_t
__ovld
17954intel_sub_group_avc_sic_evaluate_with_multi_reference(
17955 read_only image2d_t src_image,
uint packed_reference_ids,
17956 uchar packed_reference_field_polarities, sampler_t vme_media_sampler,
17957 intel_sub_group_avc_sic_payload_t payload);
17960uchar __ovld intel_sub_group_avc_sic_get_ipe_luma_shape(
17961 intel_sub_group_avc_sic_result_t result);
17962ushort __ovld intel_sub_group_avc_sic_get_best_ipe_luma_distortion(
17963 intel_sub_group_avc_sic_result_t result);
17964ushort __ovld intel_sub_group_avc_sic_get_best_ipe_chroma_distortion(
17965 intel_sub_group_avc_sic_result_t result);
17966ulong __ovld intel_sub_group_avc_sic_get_packed_ipe_luma_modes(
17967 intel_sub_group_avc_sic_result_t result);
17968uchar __ovld intel_sub_group_avc_sic_get_ipe_chroma_mode(
17969 intel_sub_group_avc_sic_result_t result);
17970uint __ovld intel_sub_group_avc_sic_get_packed_skc_luma_count_threshold(
17971 intel_sub_group_avc_sic_result_t result);
17972ulong __ovld intel_sub_group_avc_sic_get_packed_skc_luma_sum_threshold(
17973 intel_sub_group_avc_sic_result_t result);
17974ushort __ovld intel_sub_group_avc_sic_get_inter_raw_sads(
17975 intel_sub_group_avc_sic_result_t result);
17978intel_sub_group_avc_ime_payload_t
__ovld
17979intel_sub_group_avc_ime_set_inter_base_multi_reference_penalty(
17980 uchar reference_base_penalty, intel_sub_group_avc_ime_payload_t payload);
17981intel_sub_group_avc_ref_payload_t
__ovld
17982intel_sub_group_avc_ref_set_inter_base_multi_reference_penalty(
17983 uchar reference_base_penalty, intel_sub_group_avc_ref_payload_t payload);
17984intel_sub_group_avc_sic_payload_t
__ovld
17985intel_sub_group_avc_sic_set_inter_base_multi_reference_penalty(
17986 uchar reference_base_penalty, intel_sub_group_avc_sic_payload_t payload);
17988intel_sub_group_avc_ime_payload_t
__ovld
17989intel_sub_group_avc_ime_set_inter_shape_penalty(
17990 ulong packed_shape_cost, intel_sub_group_avc_ime_payload_t payload);
17991intel_sub_group_avc_ref_payload_t
__ovld
17992intel_sub_group_avc_ref_set_inter_shape_penalty(
17993 ulong packed_shape_cost, intel_sub_group_avc_ref_payload_t payload);
17994intel_sub_group_avc_sic_payload_t
__ovld
17995intel_sub_group_avc_sic_set_inter_shape_penalty(
17996 ulong packed_shape_cost, intel_sub_group_avc_sic_payload_t payload);
17998intel_sub_group_avc_ime_payload_t
__ovld
17999intel_sub_group_avc_ime_set_inter_direction_penalty(
18000 uchar direction_cost, intel_sub_group_avc_ime_payload_t payload);
18001intel_sub_group_avc_ref_payload_t
__ovld
18002intel_sub_group_avc_ref_set_inter_direction_penalty(
18003 uchar direction_cost, intel_sub_group_avc_ref_payload_t payload);
18004intel_sub_group_avc_sic_payload_t
__ovld
18005intel_sub_group_avc_sic_set_inter_direction_penalty(
18006 uchar direction_cost, intel_sub_group_avc_sic_payload_t payload);
18008intel_sub_group_avc_ime_payload_t
__ovld
18009intel_sub_group_avc_ime_set_motion_vector_cost_function(
18010 ulong packed_cost_center_delta, uint2 packed_cost_table,
18011 uchar cost_precision, intel_sub_group_avc_ime_payload_t payload);
18012intel_sub_group_avc_ref_payload_t
__ovld
18013intel_sub_group_avc_ref_set_motion_vector_cost_function(
18014 ulong packed_cost_center_delta, uint2 packed_cost_table,
18015 uchar cost_precision, intel_sub_group_avc_ref_payload_t payload);
18016intel_sub_group_avc_sic_payload_t
__ovld
18017intel_sub_group_avc_sic_set_motion_vector_cost_function(
18018 ulong packed_cost_center_delta, uint2 packed_cost_table,
18019 uchar cost_precision, intel_sub_group_avc_sic_payload_t payload);
18021intel_sub_group_avc_ime_payload_t
__ovld
18022intel_sub_group_avc_ime_set_source_interlaced_field_polarity(
18023 uchar src_field_polarity, intel_sub_group_avc_ime_payload_t payload);
18024intel_sub_group_avc_ref_payload_t
__ovld
18025intel_sub_group_avc_ref_set_source_interlaced_field_polarity(
18026 uchar src_field_polarity, intel_sub_group_avc_ref_payload_t payload);
18027intel_sub_group_avc_sic_payload_t
__ovld
18028intel_sub_group_avc_sic_set_source_interlaced_field_polarity(
18029 uchar src_field_polarity, intel_sub_group_avc_sic_payload_t payload);
18031intel_sub_group_avc_ime_payload_t
__ovld
18032intel_sub_group_avc_ime_set_single_reference_interlaced_field_polarity(
18033 uchar ref_field_polarity, intel_sub_group_avc_ime_payload_t payload);
18034intel_sub_group_avc_ref_payload_t
__ovld
18035intel_sub_group_avc_ref_set_single_reference_interlaced_field_polarity(
18036 uchar ref_field_polarity, intel_sub_group_avc_ref_payload_t payload);
18037intel_sub_group_avc_sic_payload_t
__ovld
18038intel_sub_group_avc_sic_set_single_reference_interlaced_field_polarity(
18039 uchar ref_field_polarity, intel_sub_group_avc_sic_payload_t payload);
18040intel_sub_group_avc_ime_payload_t
__ovld
18041intel_sub_group_avc_ime_set_dual_reference_interlaced_field_polarities(
18042 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
18043 intel_sub_group_avc_ime_payload_t payload);
18044intel_sub_group_avc_ref_payload_t
__ovld
18045intel_sub_group_avc_ref_set_dual_reference_interlaced_field_polarities(
18046 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
18047 intel_sub_group_avc_ref_payload_t payload);
18048intel_sub_group_avc_sic_payload_t
__ovld
18049intel_sub_group_avc_sic_set_dual_reference_interlaced_field_polarities(
18050 uchar fwd_ref_field_polarity,
uchar bwd_ref_field_polarity,
18051 intel_sub_group_avc_sic_payload_t payload);
18053intel_sub_group_avc_ime_payload_t
__ovld
18054intel_sub_group_avc_ime_set_ac_only_haar(
18055 intel_sub_group_avc_ime_payload_t payload);
18056intel_sub_group_avc_ref_payload_t
__ovld
18057intel_sub_group_avc_ref_set_ac_only_haar(
18058 intel_sub_group_avc_ref_payload_t payload);
18059intel_sub_group_avc_sic_payload_t
__ovld
18060intel_sub_group_avc_sic_set_ac_only_haar(
18061 intel_sub_group_avc_sic_payload_t payload);
18063ulong __ovld intel_sub_group_avc_ime_get_motion_vectors(
18064 intel_sub_group_avc_ime_result_t result);
18065ulong __ovld intel_sub_group_avc_ref_get_motion_vectors(
18066 intel_sub_group_avc_ref_result_t result);
18068ushort __ovld intel_sub_group_avc_ime_get_inter_distortions(
18069 intel_sub_group_avc_ime_result_t result);
18070ushort __ovld intel_sub_group_avc_ref_get_inter_distortions(
18071 intel_sub_group_avc_ref_result_t result);
18072ushort __ovld intel_sub_group_avc_sic_get_inter_distortions(
18073 intel_sub_group_avc_sic_result_t result);
18075ushort __ovld intel_sub_group_avc_ime_get_best_inter_distortion(
18076 intel_sub_group_avc_ime_result_t result);
18077ushort __ovld intel_sub_group_avc_ref_get_best_inter_distortion(
18078 intel_sub_group_avc_ref_result_t result);
18080uchar __ovld intel_sub_group_avc_ime_get_inter_major_shape(
18081 intel_sub_group_avc_ime_result_t result);
18082uchar __ovld intel_sub_group_avc_ref_get_inter_major_shape(
18083 intel_sub_group_avc_ref_result_t result);
18084uchar __ovld intel_sub_group_avc_ime_get_inter_minor_shapes(
18085 intel_sub_group_avc_ime_result_t result);
18086uchar __ovld intel_sub_group_avc_ref_get_inter_minor_shapes(
18087 intel_sub_group_avc_ref_result_t result);
18089uchar __ovld intel_sub_group_avc_ime_get_inter_directions(
18090 intel_sub_group_avc_ime_result_t result);
18091uchar __ovld intel_sub_group_avc_ref_get_inter_directions(
18092 intel_sub_group_avc_ref_result_t result);
18094uchar __ovld intel_sub_group_avc_ime_get_inter_motion_vector_count(
18095 intel_sub_group_avc_ime_result_t result);
18096uchar __ovld intel_sub_group_avc_ref_get_inter_motion_vector_count(
18097 intel_sub_group_avc_ref_result_t result);
18099uint __ovld intel_sub_group_avc_ime_get_inter_reference_ids(
18100 intel_sub_group_avc_ime_result_t result);
18101uint __ovld intel_sub_group_avc_ref_get_inter_reference_ids(
18102 intel_sub_group_avc_ref_result_t result);
18105intel_sub_group_avc_ime_get_inter_reference_interlaced_field_polarities(
18106 uint packed_reference_ids,
uint packed_reference_parameter_field_polarities,
18107 intel_sub_group_avc_ime_result_t result);
18109intel_sub_group_avc_ref_get_inter_reference_interlaced_field_polarities(
18110 uint packed_reference_ids,
uint packed_reference_parameter_field_polarities,
18111 intel_sub_group_avc_ref_result_t result);
18114intel_sub_group_avc_mce_payload_t
__ovld
18115intel_sub_group_avc_ime_convert_to_mce_payload(
18116 intel_sub_group_avc_ime_payload_t payload);
18117intel_sub_group_avc_ime_payload_t
__ovld
18118intel_sub_group_avc_mce_convert_to_ime_payload(
18119 intel_sub_group_avc_mce_payload_t payload);
18120intel_sub_group_avc_mce_payload_t
__ovld
18121intel_sub_group_avc_ref_convert_to_mce_payload(
18122 intel_sub_group_avc_ref_payload_t payload);
18123intel_sub_group_avc_ref_payload_t
__ovld
18124intel_sub_group_avc_mce_convert_to_ref_payload(
18125 intel_sub_group_avc_mce_payload_t payload);
18126intel_sub_group_avc_mce_payload_t
__ovld
18127intel_sub_group_avc_sic_convert_to_mce_payload(
18128 intel_sub_group_avc_sic_payload_t payload);
18129intel_sub_group_avc_sic_payload_t
__ovld
18130intel_sub_group_avc_mce_convert_to_sic_payload(
18131 intel_sub_group_avc_mce_payload_t payload);
18133intel_sub_group_avc_mce_result_t
__ovld
18134intel_sub_group_avc_ime_convert_to_mce_result(
18135 intel_sub_group_avc_ime_result_t result);
18136intel_sub_group_avc_ime_result_t
__ovld
18137intel_sub_group_avc_mce_convert_to_ime_result(
18138 intel_sub_group_avc_mce_result_t result);
18139intel_sub_group_avc_mce_result_t
__ovld
18140intel_sub_group_avc_ref_convert_to_mce_result(
18141 intel_sub_group_avc_ref_result_t result);
18142intel_sub_group_avc_ref_result_t
__ovld
18143intel_sub_group_avc_mce_convert_to_ref_result(
18144 intel_sub_group_avc_mce_result_t result);
18145intel_sub_group_avc_mce_result_t
__ovld
18146intel_sub_group_avc_sic_convert_to_mce_result(
18147 intel_sub_group_avc_sic_result_t result);
18148intel_sub_group_avc_sic_result_t
__ovld
18149intel_sub_group_avc_mce_convert_to_sic_result(
18150 intel_sub_group_avc_mce_result_t result);
18151#pragma OPENCL EXTENSION cl_intel_device_side_avc_motion_estimation : end
18154#ifdef cl_amd_media_ops
18156uint2
__ovld amd_bitalign(uint2, uint2, uint2);
18157uint3
__ovld amd_bitalign(uint3, uint3, uint3);
18158uint4
__ovld amd_bitalign(uint4, uint4, uint4);
18159uint8
__ovld amd_bitalign(uint8, uint8, uint8);
18160uint16
__ovld amd_bitalign(uint16, uint16, uint16);
18163uint2
__ovld amd_bytealign(uint2, uint2, uint2);
18164uint3
__ovld amd_bytealign(uint3, uint3, uint3);
18165uint4
__ovld amd_bytealign(uint4, uint4, uint4);
18166uint8
__ovld amd_bytealign(uint8, uint8, uint8);
18167uint16
__ovld amd_bytealign(uint16, uint16, uint16);
18170uint2
__ovld amd_lerp(uint2, uint2, uint2);
18171uint3
__ovld amd_lerp(uint3, uint3, uint3);
18172uint4
__ovld amd_lerp(uint4, uint4, uint4);
18173uint8
__ovld amd_lerp(uint8, uint8, uint8);
18174uint16
__ovld amd_lerp(uint16, uint16, uint16);
18181uint2
__ovld amd_sadhi(uint2, uint2, uint2);
18182uint3
__ovld amd_sadhi(uint3, uint3, uint3);
18183uint4
__ovld amd_sadhi(uint4, uint4, uint4);
18184uint8
__ovld amd_sadhi(uint8, uint8, uint8);
18185uint16
__ovld amd_sadhi(uint16, uint16, uint16);
18188uint2
__ovld amd_sad(uint2, uint2, uint2);
18189uint3
__ovld amd_sad(uint3, uint3, uint3);
18190uint4
__ovld amd_sad(uint4, uint4, uint4);
18191uint8
__ovld amd_sad(uint8, uint8, uint8);
18192uint16
__ovld amd_sad(uint16, uint16, uint16);
18195float2
__ovld amd_unpack0(uint2);
18196float3
__ovld amd_unpack0(uint3);
18197float4
__ovld amd_unpack0(uint4);
18198float8
__ovld amd_unpack0(uint8);
18199float16
__ovld amd_unpack0(uint16);
18202float2
__ovld amd_unpack1(uint2);
18203float3
__ovld amd_unpack1(uint3);
18204float4
__ovld amd_unpack1(uint4);
18205float8
__ovld amd_unpack1(uint8);
18206float16
__ovld amd_unpack1(uint16);
18209float2
__ovld amd_unpack2(uint2);
18210float3
__ovld amd_unpack2(uint3);
18211float4
__ovld amd_unpack2(uint4);
18212float8
__ovld amd_unpack2(uint8);
18213float16
__ovld amd_unpack2(uint16);
18216float2
__ovld amd_unpack3(uint2);
18217float3
__ovld amd_unpack3(uint3);
18218float4
__ovld amd_unpack3(uint4);
18219float8
__ovld amd_unpack3(uint8);
18220float16
__ovld amd_unpack3(uint16);
18223#ifdef cl_amd_media_ops2
18225int2
__ovld amd_bfe(int2 src0, uint2 src1, uint2 src2);
18226int3
__ovld amd_bfe(int3 src0, uint3 src1, uint3 src2);
18227int4
__ovld amd_bfe(int4 src0, uint4 src1, uint4 src2);
18228int8
__ovld amd_bfe(int8 src0, uint8 src1, uint8 src2);
18229int16
__ovld amd_bfe(int16 src0, uint16 src1, uint16 src2);
18232uint2
__ovld amd_bfe(uint2 src0, uint2 src1, uint2 src2);
18233uint3
__ovld amd_bfe(uint3 src0, uint3 src1, uint3 src2);
18234uint4
__ovld amd_bfe(uint4 src0, uint4 src1, uint4 src2);
18235uint8
__ovld amd_bfe(uint8 src0, uint8 src1, uint8 src2);
18236uint16
__ovld amd_bfe(uint16 src0, uint16 src1, uint16 src2);
18239uint2
__ovld amd_bfm(uint2 src0, uint2 src1);
18240uint3
__ovld amd_bfm(uint3 src0, uint3 src1);
18241uint4
__ovld amd_bfm(uint4 src0, uint4 src1);
18242uint8
__ovld amd_bfm(uint8 src0, uint8 src1);
18243uint16
__ovld amd_bfm(uint16 src0, uint16 src1);
18245float __ovld amd_max3(
float src0,
float src1,
float src2);
18246float2
__ovld amd_max3(float2 src0, float2 src1, float2 src2);
18247float3
__ovld amd_max3(float3 src0, float3 src1, float3 src2);
18248float4
__ovld amd_max3(float4 src0, float4 src1, float4 src2);
18249float8
__ovld amd_max3(float8 src0, float8 src1, float8 src2);
18250float16
__ovld amd_max3(float16 src0, float16 src1, float16 src2);
18252int __ovld amd_max3(
int src0,
int src1,
int src2);
18253int2
__ovld amd_max3(int2 src0, int2 src1, int2 src2);
18254int3
__ovld amd_max3(int3 src0, int3 src1, int3 src2);
18255int4
__ovld amd_max3(int4 src0, int4 src1, int4 src2);
18256int8
__ovld amd_max3(int8 src0, int8 src1, int8 src2);
18257int16
__ovld amd_max3(int16 src0, int16 src1, int16 src2);
18260uint2
__ovld amd_max3(uint2 src0, uint2 src1, uint2 src2);
18261uint3
__ovld amd_max3(uint3 src0, uint3 src1, uint3 src2);
18262uint4
__ovld amd_max3(uint4 src0, uint4 src1, uint4 src2);
18263uint8
__ovld amd_max3(uint8 src0, uint8 src1, uint8 src2);
18264uint16
__ovld amd_max3(uint16 src0, uint16 src1, uint16 src2);
18266float __ovld amd_median3(
float src0,
float src1,
float src2);
18267float2
__ovld amd_median3(float2 src0, float2 src1, float2 src2);
18268float3
__ovld amd_median3(float3 src0, float3 src1, float3 src2);
18269float4
__ovld amd_median3(float4 src0, float4 src1, float4 src2);
18270float8
__ovld amd_median3(float8 src0, float8 src1, float8 src2);
18271float16
__ovld amd_median3(float16 src0, float16 src1, float16 src2);
18273int __ovld amd_median3(
int src0,
int src1,
int src2);
18274int2
__ovld amd_median3(int2 src0, int2 src1, int2 src2);
18275int3
__ovld amd_median3(int3 src0, int3 src1, int3 src2);
18276int4
__ovld amd_median3(int4 src0, int4 src1, int4 src2);
18277int8
__ovld amd_median3(int8 src0, int8 src1, int8 src2);
18278int16
__ovld amd_median3(int16 src0, int16 src1, int16 src2);
18281uint2
__ovld amd_median3(uint2 src0, uint2 src1, uint2 src2);
18282uint3
__ovld amd_median3(uint3 src0, uint3 src1, uint3 src2);
18283uint4
__ovld amd_median3(uint4 src0, uint4 src1, uint4 src2);
18284uint8
__ovld amd_median3(uint8 src0, uint8 src1, uint8 src2);
18285uint16
__ovld amd_median3(uint16 src0, uint16 src1, uint16 src2);
18287float __ovld amd_min3(
float src0,
float src1,
float src);
18288float2
__ovld amd_min3(float2 src0, float2 src1, float2 src);
18289float3
__ovld amd_min3(float3 src0, float3 src1, float3 src);
18290float4
__ovld amd_min3(float4 src0, float4 src1, float4 src);
18291float8
__ovld amd_min3(float8 src0, float8 src1, float8 src);
18292float16
__ovld amd_min3(float16 src0, float16 src1, float16 src);
18294int __ovld amd_min3(
int src0,
int src1,
int src2);
18295int2
__ovld amd_min3(int2 src0, int2 src1, int2 src2);
18296int3
__ovld amd_min3(int3 src0, int3 src1, int3 src2);
18297int4
__ovld amd_min3(int4 src0, int4 src1, int4 src2);
18298int8
__ovld amd_min3(int8 src0, int8 src1, int8 src2);
18299int16
__ovld amd_min3(int16 src0, int16 src1, int16 src2);
18302uint2
__ovld amd_min3(uint2 src0, uint2 src1, uint2 src2);
18303uint3
__ovld amd_min3(uint3 src0, uint3 src1, uint3 src2);
18304uint4
__ovld amd_min3(uint4 src0, uint4 src1, uint4 src2);
18305uint8
__ovld amd_min3(uint8 src0, uint8 src1, uint8 src2);
18306uint16
__ovld amd_min3(uint16 src0, uint16 src1, uint16 src2);
18309ulong2
__ovld amd_mqsad(ulong2 src0, uint2 src1, ulong2 src2);
18310ulong3
__ovld amd_mqsad(ulong3 src0, uint3 src1, ulong3 src2);
18311ulong4
__ovld amd_mqsad(ulong4 src0, uint4 src1, ulong4 src2);
18312ulong8
__ovld amd_mqsad(ulong8 src0, uint8 src1, ulong8 src2);
18313ulong16
__ovld amd_mqsad(ulong16 src0, uint16 src1, ulong16 src2);
18316ulong2
__ovld amd_qsad(ulong2 src0, uint2 src1, ulong2 src2);
18317ulong3
__ovld amd_qsad(ulong3 src0, uint3 src1, ulong3 src2);
18318ulong4
__ovld amd_qsad(ulong4 src0, uint4 src1, ulong4 src2);
18319ulong8
__ovld amd_qsad(ulong8 src0, uint8 src1, ulong8 src2);
18320ulong16
__ovld amd_qsad(ulong16 src0, uint16 src1, ulong16 src2);
18323uint2
__ovld amd_msad(uint2 src0, uint2 src1, uint2 src2);
18324uint3
__ovld amd_msad(uint3 src0, uint3 src1, uint3 src2);
18325uint4
__ovld amd_msad(uint4 src0, uint4 src1, uint4 src2);
18326uint8
__ovld amd_msad(uint8 src0, uint8 src1, uint8 src2);
18327uint16
__ovld amd_msad(uint16 src0, uint16 src1, uint16 src2);
18330uint2
__ovld amd_sadd(uint2 src0, uint2 src1, uint2 src2);
18331uint3
__ovld amd_sadd(uint3 src0, uint3 src1, uint3 src2);
18332uint4
__ovld amd_sadd(uint4 src0, uint4 src1, uint4 src2);
18333uint8
__ovld amd_sadd(uint8 src0, uint8 src1, uint8 src2);
18334uint16
__ovld amd_sadd(uint16 src0, uint16 src1, uint16 src2);
18337uint2
__ovld amd_sadw(uint2 src0, uint2 src1, uint2 src2);
18338uint3
__ovld amd_sadw(uint3 src0, uint3 src1, uint3 src2);
18339uint4
__ovld amd_sadw(uint4 src0, uint4 src1, uint4 src2);
18340uint8
__ovld amd_sadw(uint8 src0, uint8 src1, uint8 src2);
18341uint16
__ovld amd_sadw(uint16 src0, uint16 src1, uint16 src2);
18344#if defined(cl_arm_integer_dot_product_int8)
18346int __ovld arm_dot(char4, char4);
18349#if defined(cl_arm_integer_dot_product_accumulate_int8)
18351int __ovld arm_dot_acc(char4, char4,
int);
18354#if defined(cl_arm_integer_dot_product_accumulate_int16)
18356int __ovld arm_dot_acc(short2, short2,
int);
18359#if defined(cl_arm_integer_dot_product_accumulate_saturate_int8)
18361int __ovld arm_dot_acc_sat(char4, char4,
int);
18365#pragma OPENCL EXTENSION all : disable
18367#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)