math.hpp File Reference

#include <sycl/ext/intel/esimd/common.hpp>
#include <sycl/ext/intel/esimd/detail/math_intrin.hpp>
#include <sycl/ext/intel/esimd/detail/operators.hpp>
#include <sycl/ext/intel/esimd/detail/types.hpp>
#include <sycl/ext/intel/esimd/detail/util.hpp>
#include <sycl/ext/intel/esimd/simd.hpp>
#include <sycl/ext/intel/esimd/simd_view.hpp>
#include <sycl/ext/intel/experimental/esimd/detail/math_intrin.hpp>
#include <cstdint>

Include dependency graph for math.hpp:

This graph shows which files directly or indirectly include this file:

Go to the source code of this file.

Classes
struct	sycl::_V1::ext::intel::esimd::detail::esimd_apply_sum< T0, T1, SZ >
struct	sycl::_V1::ext::intel::esimd::detail::esimd_apply_prod< T0, T1, SZ >
struct	sycl::_V1::ext::intel::esimd::detail::esimd_apply_reduced_max< T0, T1, SZ >
struct	sycl::_V1::ext::intel::esimd::detail::esimd_apply_reduced_min< T0, T1, SZ >

Namespaces
	sycl
	sycl::_V1
	sycl::_V1::ext
	sycl::_V1::ext::intel
	sycl::_V1::ext::intel::esimd
	sycl::_V1::ext::intel::esimd::detail

Macros
#define	__ESIMD_UNARY_INTRINSIC_DEF(COND, name, iname)
#define	__ESIMD_EMATH_COND    detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4)
#define	__ESIMD_EMATH_IEEE_COND    detail::is_generic_floating_point_v<T> && (sizeof(T) >= 4)
#define	__ESIMD_BINARY_INTRINSIC_DEF(COND, name, iname)
#define	__ESIMD_INTRINSIC_DEF(name)

Enumerations
enum class	sycl::_V1::ext::intel::esimd::bfn_t : uint8_t { sycl::_V1::ext::intel::esimd::x = 0xAA , sycl::_V1::ext::intel::esimd::y = 0xCC , sycl::_V1::ext::intel::esimd::z = 0xF0 }
	This enum is used to encode all possible logical operations performed on the 3 input operands. More...

Functions
template<typename T0 , typename T1 , int SZ>
__ESIMD_API std::enable_if_t<!detail::is_generic_floating_point_v< T0 >||std::is_same_v< T1, T0 >, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::saturate (simd< T1, SZ > src)
	Conversion of input vector elements of type T1 into vector of elements of type T0 with saturation. More...
template<typename TRes , typename TArg , int SZ>
ESIMD_DETAIL __ESIMD_API std::enable_if_t< !std::is_same< std::remove_const_t< TRes >, std::remove_const_t< TArg > >::value, simd< TRes, SZ > >	sycl::_V1::ext::intel::esimd::abs (simd< TArg, SZ > src0)
	Get absolute value (vector version) More...
template<typename TRes , typename TArg >
__ESIMD_API std::enable_if_t<!std::is_same< std::remove_const_t< TRes >, std::remove_const_t< TArg > >::value &&detail::is_esimd_scalar< TRes >::value &&detail::is_esimd_scalar< TArg >::value, std::remove_const_t< TRes > >	sycl::_V1::ext::intel::esimd::abs (TArg src0)
	Get absolute value (scalar version) More...
template<typename T1 , int SZ>
__ESIMD_API simd< T1, SZ >	sycl::_V1::ext::intel::esimd::abs (simd< T1, SZ > src0)
	Get absolute value (vector version). More...
template<typename T1 >
__ESIMD_API std::enable_if_t< detail::is_esimd_scalar< T1 >::value, std::remove_const_t< T1 > >	sycl::_V1::ext::intel::esimd::abs (T1 src0)
	Get absolute value (scalar version). More...
template<typename T , int SZ, class Sat = saturation_off_tag>
__ESIMD_API	sycl::_V1::ext::intel::esimd::simd< T, SZ > (max)(simd< T
	Selects component-wise the maximum of the two vectors. More...
__ESIMD_API SZ simd< T, SZ > Sat int class simd< T, SZ >()	sycl::_V1::ext::intel::esimd::max (simd< T, SZ > src0, T src1, Sat sat={})
__ESIMD_API simd< T, SZ > Sat class T()	sycl::_V1::ext::intel::esimd::max (T src0, T src1, Sat sat={})
template<typename T , int SZ, class Sat = saturation_off_tag>
__ESIMD_API	sycl::_V1::ext::intel::esimd::simd< T, SZ > (min)(simd< T
	Selects component-wise the minimum of the two vectors. More...
__ESIMD_API SZ simd< T, SZ > Sat int class simd< T, SZ >()	sycl::_V1::ext::intel::esimd::min (simd< T, SZ > src0, T src1, Sat sat={})
__ESIMD_API simd< T, SZ > Sat class T()	sycl::_V1::ext::intel::esimd::min (T src0, T src1, Sat sat={})
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::inv (simd< T, N > src, Sat sat={})
	Inversion - calculates (1/x). More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::inv (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::log2 (simd< T, N > src, Sat sat={})
	Logarithm base 2. More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::log2 (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::exp2 (simd< T, N > src, Sat sat={})
	Exponent base 2. More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::exp2 (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::sqrt (simd< T, N > src, Sat sat={})
	Square root. More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::sqrt (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) >= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::sqrt_ieee (simd< T, N > src, Sat sat={})
	IEEE754-compliant square root. Supports float and double. More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) >= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::sqrt_ieee (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::rsqrt (simd< T, N > src, Sat sat={})
	Square root reciprocal - calculates 1/sqrt(x). More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::rsqrt (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::sin (simd< T, N > src, Sat sat={})
	Sine. More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::sin (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::cos (simd< T, N > src, Sat sat={})
	Cosine. More...
template<typename T , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::cos (T src, Sat sat={})
	Scalar version. More...
template<class T , int N, class U , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::pow (simd< T, N > src0, simd< U, N > src1, Sat sat={})
	Power - calculates src0 in power of src1. More...
template<class T , int N, class U , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::pow (simd< T, N > src0, U src1, Sat sat={})
	(vector, scalar) version. More...
template<class T , class U , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) <= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::pow (T src0, U src1, Sat sat={})
	(scalar, scalar) version. More...
template<class T , int N, class U , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) >= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::div_ieee (simd< T, N > src0, simd< U, N > src1, Sat sat={})
	IEEE754-compliant floating-point division. Supports float and double. More...
template<class T , int N, class U , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) >= 4) >>
__ESIMD_API simd< T, N >	sycl::_V1::ext::intel::esimd::div_ieee (simd< T, N > src0, U src1, Sat sat={})
	(vector, scalar) version. More...
template<class T , class U , class Sat = saturation_off_tag, class = std::enable_if_t< detail::is_generic_floating_point_v<T> && (sizeof(T) >= 4) >>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::div_ieee (T src0, U src1, Sat sat={})
	(scalar, scalar) version. More...
template<class T , int SZ, class Sat = saturation_off_tag>
ESIMD_DETAIL ESIMD_NODEBUG ESIMD_INLINE simd< T, SZ >	sycl::_V1::ext::intel::esimd::log (simd< T, SZ > src0, Sat sat={})
	Computes the natural logarithm of the given argument. More...
template<class T , class Sat = saturation_off_tag>
ESIMD_NODEBUG ESIMD_INLINE T	sycl::_V1::ext::intel::esimd::log (T src0, Sat sat={})
template<class T , int SZ, class Sat = saturation_off_tag>
ESIMD_NODEBUG ESIMD_INLINE simd< T, SZ >	sycl::_V1::ext::intel::esimd::exp (simd< T, SZ > src0, Sat sat={})
	Computes e raised to the power of the given argument. More...
template<class T , class Sat = saturation_off_tag>
ESIMD_NODEBUG ESIMD_INLINE T	sycl::_V1::ext::intel::esimd::exp (T src0, Sat sat={})
template<typename T , int SZ, class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API sycl::ext::intel::esimd ::simd< T, SZ >	sycl::_V1::ext::intel::esimd::rndd (sycl::ext::intel::esimd ::simd< float, SZ > src0, Sat sat={})
	Round-down (also known as floor). More...
template<typename T , class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::rndd (float src0, Sat sat={})
	Scalar version. More...
template<typename T , int SZ, class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API sycl::ext::intel::esimd ::simd< T, SZ >	sycl::_V1::ext::intel::esimd::rndu (sycl::ext::intel::esimd ::simd< float, SZ > src0, Sat sat={})
	Round-up (also known as ceil). More...
template<typename T , class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::rndu (float src0, Sat sat={})
	Scalar version. More...
template<typename T , int SZ, class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API sycl::ext::intel::esimd ::simd< T, SZ >	sycl::_V1::ext::intel::esimd::rnde (sycl::ext::intel::esimd ::simd< float, SZ > src0, Sat sat={})
	Round-to-even (also known as round). More...
template<typename T , class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::rnde (float src0, Sat sat={})
	Scalar version. More...
template<typename T , int SZ, class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API sycl::ext::intel::esimd ::simd< T, SZ >	sycl::_V1::ext::intel::esimd::rndz (sycl::ext::intel::esimd ::simd< float, SZ > src0, Sat sat={})
	Round-to-zero (also known as trunc). More...
template<typename T , class Sat = sycl::ext::intel::esimd ::saturation_off_tag>
__ESIMD_API T	sycl::_V1::ext::intel::esimd::rndz (float src0, Sat sat={})
	Scalar version. More...
template<typename RT , int SZ, class Sat = sycl::ext::intel::esimd::saturation_off_tag>
ESIMD_INLINE sycl::ext::intel::esimd::simd< RT, SZ >	sycl::_V1::ext::intel::esimd::floor (const sycl::ext::intel::esimd::simd< float, SZ > src0, Sat sat={})
	"Floor" operation, vector version - alias of rndd. More...
template<typename RT , class Sat = sycl::ext::intel::esimd::saturation_off_tag>
ESIMD_INLINE RT	sycl::_V1::ext::intel::esimd::floor (float src0, Sat sat={})
	"Floor" operation, scalar version - alias of rndd. More...
template<typename RT , int SZ, class Sat = sycl::ext::intel::esimd::saturation_off_tag>
ESIMD_INLINE sycl::ext::intel::esimd::simd< RT, SZ >	sycl::_V1::ext::intel::esimd::ceil (const sycl::ext::intel::esimd::simd< float, SZ > src0, Sat sat={})
	"Ceiling" operation, vector version - alias of rndu. More...
template<typename RT , class Sat = sycl::ext::intel::esimd::saturation_off_tag>
ESIMD_INLINE RT	sycl::_V1::ext::intel::esimd::ceil (float src0, Sat sat={})
	"Ceiling" operation, scalar version - alias of rndu. More...
template<typename RT , int SZ, class Sat = sycl::ext::intel::esimd::saturation_off_tag>
__ESIMD_API sycl::ext::intel::esimd::simd< RT, SZ >	sycl::_V1::ext::intel::esimd::trunc (const sycl::ext::intel::esimd::simd< float, SZ > &src0, Sat sat={})
	Round to integral value using the round to zero rounding mode (vector version). More...
template<typename RT , class Sat = sycl::ext::intel::esimd::saturation_off_tag>
__ESIMD_API RT	sycl::_V1::ext::intel::esimd::trunc (float src0, Sat sat={})
	Round to integral value using the round to zero rounding mode (scalar version). More...
template<int N>
ESIMD_NODEBUG ESIMD_INLINE std::enable_if_t<(N==8||N==16||N==32), uint >	sycl::_V1::ext::intel::esimd::pack_mask (simd_mask< N > src0)
	Pack a simd_mask into a single unsigned 32-bit integer value. More...
template<int N>
ESIMD_NODEBUG ESIMD_INLINE std::enable_if_t<(N==8||N==16||N==32), simd_mask< N > >	sycl::_V1::ext::intel::esimd::unpack_mask (uint src0)
	Unpack an unsigned 32-bit integer value into a simd_mask. More...
template<int N>
__ESIMD_API std::enable_if_t<(N !=8 &&N !=16 &&N< 32), uint >	sycl::_V1::ext::intel::esimd::pack_mask (simd_mask< N > src0)
	pack_mask specialization when the number of elements N is not 8, 16 or 32. More...
template<typename T , int N>
__ESIMD_API std::enable_if_t<(std::is_same_v< T, ushort >||std::is_same_v< T, uint >)&&(N > 0 &&N<=32), uint >	sycl::_V1::ext::intel::esimd::ballot (simd< T, N > mask)
	Compare source vector elements against zero and return a bitfield combining the comparison result. More...
template<typename T , int N>
ESIMD_NODEBUG ESIMD_INLINE std::enable_if_t< std::is_integral< T >::value &&(sizeof(T)<=4), simd< uint32_t, N > >	sycl::_V1::ext::intel::esimd::cbit (simd< T, N > src)
	Count number of bits set in the source operand per element. More...
template<typename T >
__ESIMD_API std::enable_if_t< std::is_integral< T >::value &&(sizeof(T)<=4), uint32_t >	sycl::_V1::ext::intel::esimd::cbit (T src)
	Scalar version of cbit - both input and output are scalars rather than vectors. More...
template<typename BaseTy , typename RegionTy >
__ESIMD_API std::enable_if_t< std::is_integral< typename simd_view< BaseTy, RegionTy >::element_type >::value &&(sizeof(typename simd_view< BaseTy, RegionTy >::element_type)<=4) &&(simd_view< BaseTy, RegionTy >::length==1), uint32_t >	sycl::_V1::ext::intel::esimd::cbit (simd_view< BaseTy, RegionTy > src)
	Scalar version of cbit, that takes simd_view object as an argument, e.g. More...
template<typename T , int N>
__ESIMD_API std::enable_if_t< std::is_integral< T >::value &&(sizeof(T)==4), simd< T, N > >	sycl::_V1::ext::intel::esimd::fbl (simd< T, N > src)
	Find the per element number of the first bit set in the source operand starting from the least significant bit. More...
template<typename T >
__ESIMD_API std::enable_if_t< std::is_integral< T >::value &&(sizeof(T)==4), T >	sycl::_V1::ext::intel::esimd::fbl (T src)
	Scalar version of fbl - both input and output are scalars rather than vectors. More...
template<typename BaseTy , typename RegionTy >
__ESIMD_API std::enable_if_t< std::is_integral< typename simd_view< BaseTy, RegionTy >::element_type >::value &&(sizeof(typename simd_view< BaseTy, RegionTy >::element_type)==4) &&(simd_view< BaseTy, RegionTy >::length==1), typename simd_view< BaseTy, RegionTy >::element_type >	sycl::_V1::ext::intel::esimd::fbl (simd_view< BaseTy, RegionTy > src)
	Scalar version of fbl, that takes simd_view object as an argument, e.g. More...
template<typename T , int N>
__ESIMD_API std::enable_if_t< std::is_integral< T >::value &&std::is_signed< T >::value &&(sizeof(T)==4), simd< T, N > >	sycl::_V1::ext::intel::esimd::fbh (simd< T, N > src)
	Find the per element number of the first bit set in the source operand starting from the most significant bit (sign bit is skipped). More...
template<typename T , int N>
__ESIMD_API std::enable_if_t< std::is_integral< T >::value &&!std::is_signed< T >::value &&(sizeof(T)==4), simd< T, N > >	sycl::_V1::ext::intel::esimd::fbh (simd< T, N > src)
	Find the per element number of the first bit set in the source operand starting from the most significant bit (sign bit is counted). More...
template<typename T >
__ESIMD_API std::enable_if_t< std::is_integral< T >::value &&(sizeof(T)==4), T >	sycl::_V1::ext::intel::esimd::fbh (T src)
	Scalar version of fbh - both input and output are scalars rather than vectors. More...
template<typename BaseTy , typename RegionTy >
__ESIMD_API std::enable_if_t< std::is_integral< typename simd_view< BaseTy, RegionTy >::element_type >::value &&(sizeof(typename simd_view< BaseTy, RegionTy >::element_type)==4) &&(simd_view< BaseTy, RegionTy >::length==1), typename simd_view< BaseTy, RegionTy >::element_type >	sycl::_V1::ext::intel::esimd::fbh (simd_view< BaseTy, RegionTy > src)
	Scalar version of fbh, that takes simd_view object as an argument, e.g. More...
template<typename T0 , typename T1 , int SZ, class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::shl (simd< T1, SZ > src0, simd< T1, SZ > src1, Sat sat={})
	Shift left operation (vector version) More...
template<typename T0 , typename T1 , int SZ, typename U , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< U >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::shl (simd< T1, SZ > src0, U src1, Sat sat={})
	Shift left operation (vector version) More...
template<typename T0 , typename T1 , typename T2 , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< __ESIMD_DNS::is_esimd_scalar< T0 >::value &&__ESIMD_DNS::is_esimd_scalar< T1 >::value &&__ESIMD_DNS::is_esimd_scalar< T2 >::value &&std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< T2 >::value, std::remove_const_t< T0 > >	sycl::_V1::ext::intel::esimd::shl (T1 src0, T2 src1, Sat sat={})
	Shift left operation (scalar version) More...
template<typename T0 , typename T1 , int SZ, class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::lsr (simd< T1, SZ > src0, simd< T1, SZ > src1, Sat sat={})
	Logical Shift Right (vector version) More...
template<typename T0 , typename T1 , int SZ, typename U , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< U >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::lsr (simd< T1, SZ > src0, U src1, Sat sat={})
	Logical Shift Right (vector version) More...
template<typename T0 , typename T1 , typename T2 , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< __ESIMD_DNS::is_esimd_scalar< T0 >::value &&__ESIMD_DNS::is_esimd_scalar< T1 >::value &&__ESIMD_DNS::is_esimd_scalar< T2 >::value &&std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< T2 >::value, std::remove_const_t< T0 > >	sycl::_V1::ext::intel::esimd::lsr (T1 src0, T2 src1, Sat sat={})
	Logical Shift Right (scalar version) More...
template<typename T0 , typename T1 , int SZ, class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::asr (simd< T1, SZ > src0, simd< T1, SZ > src1, Sat sat={})
	Arithmetical Shift Right (vector version) More...
template<typename T0 , typename T1 , int SZ, typename U , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< U >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::asr (simd< T1, SZ > src0, U src1, Sat sat={})
	Arithmetical Shift Right (vector version) More...
template<typename T0 , typename T1 , typename T2 , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< __ESIMD_DNS::is_esimd_scalar< T0 >::value &&__ESIMD_DNS::is_esimd_scalar< T1 >::value &&__ESIMD_DNS::is_esimd_scalar< T2 >::value &&std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< T2 >::value, std::remove_const_t< T0 > >	sycl::_V1::ext::intel::esimd::asr (T1 src0, T2 src1, Sat sat={})
	Arithmetical Shift Right (scalar version) More...
template<typename T0 , typename T1 , int SZ, class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::shr (simd< T1, SZ > src0, simd< T1, SZ > src1, Sat sat={})
	Shift right operation (vector version) More...
template<typename T0 , typename T1 , int SZ, typename U , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< U >::value, simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::shr (simd< T1, SZ > src0, U src1, Sat sat={})
	Shift right operation (vector version) More...
template<typename T0 , typename T1 , typename T2 , class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< __ESIMD_DNS::is_esimd_scalar< T0 >::value &&__ESIMD_DNS::is_esimd_scalar< T1 >::value &&__ESIMD_DNS::is_esimd_scalar< T2 >::value &&std::is_integral< T0 >::value &&std::is_integral< T1 >::value &&std::is_integral< T2 >::value, std::remove_const_t< T0 > >	sycl::_V1::ext::intel::esimd::shr (T1 src0, T2 src1, Sat sat={})
	Shift right operation (scalar version) More...
template<typename T0 , typename T1 , int SZ>
__ESIMD_API std::enable_if_t< detail::is_type< T0, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T1, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >), simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::rol (simd< T1, SZ > src0, simd< T1, SZ > src1)
	Rotate left operation with two vector inputs. More...
template<typename T0 , typename T1 , int SZ, typename U >
__ESIMD_API std::enable_if_t< detail::is_type< T0, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T1, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< U, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >), simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::rol (simd< T1, SZ > src0, U src1)
	Rotate left operation with a vector and a scalar inputs. More...
template<typename T0 , typename T1 , typename T2 >
__ESIMD_API std::enable_if_t< __ESIMD_DNS::is_esimd_scalar< T0 >::value &&__ESIMD_DNS::is_esimd_scalar< T1 >::value &&__ESIMD_DNS::is_esimd_scalar< T2 >::value &&detail::is_type< T0, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T1, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T2, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >), std::remove_const_t< T0 > >	sycl::_V1::ext::intel::esimd::rol (T1 src0, T2 src1)
	Rotate left operation with two scalar inputs. More...
template<typename T0 , typename T1 , int SZ>
__ESIMD_API std::enable_if_t< detail::is_type< T0, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T1, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >), simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::ror (simd< T1, SZ > src0, simd< T1, SZ > src1)
	Rotate right operation with two vector inputs. More...
template<typename T0 , typename T1 , int SZ, typename U >
__ESIMD_API std::enable_if_t< detail::is_type< T0, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T1, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< U, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >), simd< T0, SZ > >	sycl::_V1::ext::intel::esimd::ror (simd< T1, SZ > src0, U src1)
	Rotate right operation with a vector and a scalar inputs. More...
template<typename T0 , typename T1 , typename T2 >
__ESIMD_API std::enable_if_t< __ESIMD_DNS::is_esimd_scalar< T0 >::value &&__ESIMD_DNS::is_esimd_scalar< T1 >::value &&__ESIMD_DNS::is_esimd_scalar< T2 >::value &&detail::is_type< T0, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T1, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >) &&detail::is_type< T2, int16_t, uint16_t, int32_t, uint32_t, int64_t, uint64_t >), std::remove_const_t< T0 > >	sycl::_V1::ext::intel::esimd::ror (T1 src0, T2 src1)
	Rotate right operation with two scalar inputs. More...
template<typename T1 , typename T2 , typename T3 , typename T4 , int N, class Sat = saturation_off_tag>
__ESIMD_API std::enable_if_t< detail::is_dword_type< T1 >::value &&detail::is_dword_type< T2 >::value &&detail::is_dword_type< T3 >::value &&detail::is_dword_type< T4 >::value, simd< T1, N > >	sycl::_V1::ext::intel::esimd::dp4a (simd< T2, N > src0, simd< T3, N > src1, simd< T4, N > src2, Sat sat={})
	DP4A. More...
template<typename T0 , typename T1 , int SZ, template< typename RT, typename T, int N > class OpType>
T0	sycl::_V1::ext::intel::esimd::detail::reduce_single (simd< T1, SZ > v)
template<typename T0 , typename T1 , int N1, int N2, template< typename RT, typename T, int N > class OpType>
T0	sycl::_V1::ext::intel::esimd::detail::reduce_pair (simd< T1, N1 > v1, simd< T1, N2 > v2)
template<typename T0 , typename T1 , int SZ, template< typename RT, typename T, int N > class OpType>
T0	sycl::_V1::ext::intel::esimd::detail::reduce (simd< T1, SZ > v)
template<typename T0 , typename T1 , int SZ>
ESIMD_INLINE ESIMD_NODEBUG T0	sycl::_V1::ext::intel::esimd::detail::sum (simd< T1, SZ > v)
template<typename T0 , typename T1 , int SZ>
ESIMD_INLINE ESIMD_NODEBUG T0	sycl::_V1::ext::intel::esimd::detail::prod (simd< T1, SZ > v)
template<typename T0 , typename T1 , int SZ>
ESIMD_INLINE ESIMD_NODEBUG T0	sycl::_V1::ext::intel::esimd::hmax (simd< T1, SZ > v)
	ESIMD_DETAIL. More...
template<typename T0 , typename T1 , int SZ>
ESIMD_INLINE ESIMD_NODEBUG T0	sycl::_V1::ext::intel::esimd::hmin (simd< T1, SZ > v)
	Performs 'minimum' operation reduction over elements of the input vector, that is, returns the minimal vector element. More...
template<typename T0 , typename T1 , int SZ, typename BinaryOperation >
ESIMD_INLINE ESIMD_NODEBUG T0	sycl::_V1::ext::intel::esimd::reduce (simd< T1, SZ > v, BinaryOperation op)
	Performs reduction over elements of the input vector. More...
static constexpr bfn_t	sycl::_V1::ext::intel::esimd::operator~ (bfn_t x)
static constexpr bfn_t	sycl::_V1::ext::intel::esimd::operator| (bfn_t x, bfn_t y)
static constexpr bfn_t	sycl::_V1::ext::intel::esimd::operator& (bfn_t x, bfn_t y)
static constexpr bfn_t	sycl::_V1::ext::intel::esimd::operator^ (bfn_t x, bfn_t y)
template<bfn_t FuncControl, typename T , int N>
__ESIMD_API std::enable_if_t< std::is_integral_v< T >, sycl::ext::intel::esimd::simd< T, N > >	sycl::_V1::ext::intel::esimd::bfn (sycl::ext::intel::esimd::simd< T, N > src0, sycl::ext::intel::esimd::simd< T, N > src1, sycl::ext::intel::esimd::simd< T, N > src2)
	Performs binary function computation with three vector operands. More...
template<bfn_t FuncControl, typename T >
ESIMD_NODEBUG ESIMD_INLINE std::enable_if_t< __ESIMD_DNS::is_esimd_scalar< T >::value &&std::is_integral_v< T >, T >	sycl::_V1::ext::intel::esimd::bfn (T src0, T src1, T src2)
	Performs binary function computation with three scalar operands. More...
template<int N>
__ESIMD_API sycl::ext::intel::esimd::simd< uint32_t, N >	sycl::_V1::ext::intel::esimd::addc (sycl::ext::intel::esimd::simd< uint32_t, N > &carry, sycl::ext::intel::esimd::simd< uint32_t, N > src0, sycl::ext::intel::esimd::simd< uint32_t, N > src1)
	Performs add with carry of 2 unsigned 32-bit vectors. More...
template<int N>
__ESIMD_API sycl::ext::intel::esimd::simd< uint32_t, N >	sycl::_V1::ext::intel::esimd::addc (sycl::ext::intel::esimd::simd< uint32_t, N > &carry, sycl::ext::intel::esimd::simd< uint32_t, N > src0, uint32_t src1)
	Performs add with carry of a unsigned 32-bit vector and scalar. More...
template<int N>
__ESIMD_API sycl::ext::intel::esimd::simd< uint32_t, N >	sycl::_V1::ext::intel::esimd::addc (sycl::ext::intel::esimd::simd< uint32_t, N > &carry, uint32_t src0, sycl::ext::intel::esimd::simd< uint32_t, N > src1)
	Performs add with carry of a unsigned 32-bit scalar and vector. More...
__ESIMD_API uint32_t	sycl::_V1::ext::intel::esimd::addc (uint32_t &carry, uint32_t src0, uint32_t src1)
	Performs add with carry of a unsigned 32-bit scalars. More...
template<int N>
__ESIMD_API sycl::ext::intel::esimd::simd< uint32_t, N >	sycl::_V1::ext::intel::esimd::subb (sycl::ext::intel::esimd::simd< uint32_t, N > &borrow, sycl::ext::intel::esimd::simd< uint32_t, N > src0, sycl::ext::intel::esimd::simd< uint32_t, N > src1)
	Performs substraction with borrow of 2 unsigned 32-bit vectors. More...
template<int N>
__ESIMD_API sycl::ext::intel::esimd::simd< uint32_t, N >	sycl::_V1::ext::intel::esimd::subb (sycl::ext::intel::esimd::simd< uint32_t, N > &borrow, sycl::ext::intel::esimd::simd< uint32_t, N > src0, uint32_t src1)
	Performs substraction with borrow of unsigned 32-bit vector and scalar. More...
template<int N>
__ESIMD_API sycl::ext::intel::esimd::simd< uint32_t, N >	sycl::_V1::ext::intel::esimd::subb (sycl::ext::intel::esimd::simd< uint32_t, N > &borrow, uint32_t src0, sycl::ext::intel::esimd::simd< uint32_t, N > src1)
	Performs substraction with borrow of unsigned 32-bit scalar and vector. More...
__ESIMD_API uint32_t	sycl::_V1::ext::intel::esimd::subb (uint32_t &borrow, uint32_t src0, uint32_t src1)
	Performs substraction with borrow of 2 unsigned 32-bit scalars. More...
__ESIMD_API uint64_t	sycl::_V1::ext::intel::esimd::rdtsc ()
	rdtsc - get the value of timestamp counter. More...

Variables
__ESIMD_API SZ	sycl::_V1::ext::intel::esimd::src0
__ESIMD_API SZ simd< T, SZ >	sycl::_V1::ext::intel::esimd::src1
__ESIMD_API SZ simd< T, SZ > Sat	sycl::_V1::ext::intel::esimd::sat
__ESIMD_API SZ simd< T, SZ > Sat int	sycl::_V1::ext::intel::esimd::SZ
__ESIMD_API SZ simd< T, SZ > Sat int class	sycl::_V1::ext::intel::esimd::Sat