DPC++ Runtime
Runtime libraries for oneAPI DPC++
common.hpp File Reference
Include dependency graph for common.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::saturation_on_tag
 Gen hardware supports applying saturation to results of certain operations. More...
 
struct  sycl::_V1::ext::intel::esimd::saturation_off_tag
 This type tag represents "saturation off" behavior. More...
 
struct  sycl::_V1::ext::intel::esimd::detail::LocalAccessorMarker
 
struct  sycl::_V1::ext::intel::esimd::detail::is_saturation_tag< T >
 
class  sycl::_V1::ext::intel::esimd::detail::cache_hint_wrap< Hint >
 
struct  sycl::_V1::ext::intel::esimd::detail::lsc_expand_type< T >
 

Namespaces

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

Typedefs

using sycl::_V1::ext::intel::esimd::uchar = unsigned char
 
using sycl::_V1::ext::intel::esimd::ushort = unsigned short
 
using sycl::_V1::ext::intel::esimd::uint = unsigned int
 
using sycl::_V1::ext::intel::esimd::SurfaceIndex = unsigned int
 Surface index type. More...
 

Enumerations

enum class  sycl::_V1::ext::intel::esimd::rgba_channel : uint8_t { sycl::_V1::ext::intel::esimd::R , sycl::_V1::ext::intel::esimd::G , sycl::_V1::ext::intel::esimd::B , sycl::_V1::ext::intel::esimd::A }
 Represents a pixel's channel. More...
 
enum class  sycl::_V1::ext::intel::esimd::raw_send_eot : uint8_t { sycl::_V1::ext::intel::esimd::not_eot = 0 , sycl::_V1::ext::intel::esimd::eot = 1 }
 Specify if end of thread should be set. More...
 
enum class  sycl::_V1::ext::intel::esimd::raw_send_sendc : uint8_t { sycl::_V1::ext::intel::esimd::not_sendc = 0 , sycl::_V1::ext::intel::esimd::sendc = 1 }
 Specify if sendc should be used. More...
 
enum class  sycl::_V1::ext::intel::esimd::rgba_channel_mask : uint8_t {
  sycl::_V1::ext::intel::esimd::R = detail::chR , sycl::_V1::ext::intel::esimd::G = detail::chG , sycl::_V1::ext::intel::esimd::GR = detail::chG | detail::chR , sycl::_V1::ext::intel::esimd::B = detail::chB ,
  sycl::_V1::ext::intel::esimd::BR = detail::chB | detail::chR , sycl::_V1::ext::intel::esimd::BG = detail::chB | detail::chG , sycl::_V1::ext::intel::esimd::BGR = detail::chB | detail::chG | detail::chR , sycl::_V1::ext::intel::esimd::A = detail::chA ,
  sycl::_V1::ext::intel::esimd::AR = detail::chA | detail::chR , sycl::_V1::ext::intel::esimd::AG = detail::chA | detail::chG , sycl::_V1::ext::intel::esimd::AGR = detail::chA | detail::chG | detail::chR , sycl::_V1::ext::intel::esimd::AB = detail::chA | detail::chB ,
  sycl::_V1::ext::intel::esimd::ABR = detail::chA | detail::chB | detail::chR , sycl::_V1::ext::intel::esimd::ABG = detail::chA | detail::chB | detail::chG , sycl::_V1::ext::intel::esimd::ABGR = detail::chA | detail::chB | detail::chG | detail::chR
}
 Represents a pixel's channel mask - all possible combinations of enabled channels. More...
 
enum class  sycl::_V1::ext::intel::esimd::atomic_op : uint8_t {
  sycl::_V1::ext::intel::esimd::add = 0x0 , sycl::_V1::ext::intel::esimd::sub = 0x1 , sycl::_V1::ext::intel::esimd::inc = 0x2 , sycl::_V1::ext::intel::esimd::dec = 0x3 ,
  sycl::_V1::ext::intel::esimd::umin = 0x4 , sycl::_V1::ext::intel::esimd::umax = 0x5 , sycl::_V1::ext::intel::esimd::xchg = 0x6 , sycl::_V1::ext::intel::esimd::cmpxchg = 0x7 ,
  sycl::_V1::ext::intel::esimd::bit_and = 0x8 , sycl::_V1::ext::intel::esimd::bit_or = 0x9 , sycl::_V1::ext::intel::esimd::bit_xor = 0xa , sycl::_V1::ext::intel::esimd::smin = 0xb ,
  sycl::_V1::ext::intel::esimd::smax = 0xc , sycl::_V1::ext::intel::esimd::fmax = 0x10 , sycl::_V1::ext::intel::esimd::fmin = 0x11 , sycl::_V1::ext::intel::esimd::fcmpxchg = 0x12 ,
  sycl::_V1::ext::intel::esimd::fcmpwr = fcmpxchg , sycl::_V1::ext::intel::esimd::fadd = 0x13 , sycl::_V1::ext::intel::esimd::fsub = 0x14 , sycl::_V1::ext::intel::esimd::load = 0x15 ,
  sycl::_V1::ext::intel::esimd::store = 0x16
}
 Represents an atomic operation. More...
 
enum class  sycl::_V1::ext::intel::esimd::fence_scope : uint8_t {
  sycl::_V1::ext::intel::esimd::group = 0 , sycl::_V1::ext::intel::esimd::local = 1 , sycl::_V1::ext::intel::esimd::tile = 2 , sycl::_V1::ext::intel::esimd::gpu = 3 ,
  sycl::_V1::ext::intel::esimd::gpus = 4 , sycl::_V1::ext::intel::esimd::system = 5 , sycl::_V1::ext::intel::esimd::system_acquire = 6
}
 The scope that fence() operation should apply to. More...
 
enum class  sycl::_V1::ext::intel::esimd::fence_flush_op : uint8_t { sycl::_V1::ext::intel::esimd::none = 0 , sycl::_V1::ext::intel::esimd::evict = 1 , sycl::_V1::ext::intel::esimd::invalidate = 2 , sycl::_V1::ext::intel::esimd::clean = 4 }
 The cache flush operation to apply to caches after fence() is complete. More...
 
enum class  sycl::_V1::ext::intel::esimd::memory_kind : uint8_t { sycl::_V1::ext::intel::esimd::global = 0 , sycl::_V1::ext::intel::esimd::image = 2 , sycl::_V1::ext::intel::esimd::local = 3 }
 The target memory kind for fence() operation. More...
 
enum class  sycl::_V1::ext::intel::esimd::detail::lsc_data_size : uint8_t {
  sycl::_V1::ext::intel::esimd::detail::default_size = 0 , sycl::_V1::ext::intel::esimd::detail::u8 = 1 , sycl::_V1::ext::intel::esimd::detail::u16 = 2 , sycl::_V1::ext::intel::esimd::detail::u32 = 3 ,
  sycl::_V1::ext::intel::esimd::detail::u64 = 4 , sycl::_V1::ext::intel::esimd::detail::u8u32 = 5 , sycl::_V1::ext::intel::esimd::detail::u16u32 = 6 , sycl::_V1::ext::intel::esimd::detail::u16u32h = 7
}
 Data size or format to read or store. More...
 
enum class  sycl::_V1::ext::intel::esimd::detail::lsc_vector_size : uint8_t {
  sycl::_V1::ext::intel::esimd::detail::n1 = 1 , sycl::_V1::ext::intel::esimd::detail::n2 = 2 , sycl::_V1::ext::intel::esimd::detail::n3 = 3 , sycl::_V1::ext::intel::esimd::detail::n4 = 4 ,
  sycl::_V1::ext::intel::esimd::detail::n8 = 5 , sycl::_V1::ext::intel::esimd::detail::n16 = 6 , sycl::_V1::ext::intel::esimd::detail::n32 = 7 , sycl::_V1::ext::intel::esimd::detail::n64 = 8
}
 
enum class  sycl::_V1::ext::intel::esimd::detail::lsc_data_order : uint8_t { sycl::_V1::ext::intel::esimd::detail::nontranspose = 1 , sycl::_V1::ext::intel::esimd::detail::transpose = 2 }
 
enum class  sycl::_V1::ext::intel::esimd::detail::cache_action { sycl::_V1::ext::intel::esimd::detail::prefetch , sycl::_V1::ext::intel::esimd::detail::load , sycl::_V1::ext::intel::esimd::detail::store , sycl::_V1::ext::intel::esimd::detail::atomic }
 

Functions

constexpr ESIMD_INLINE bool sycl::_V1::ext::intel::esimd::detail::isPowerOf2 (unsigned int n)
 Check if a given 32 bit positive integer is a power of 2 at compile time. More...
 
constexpr ESIMD_INLINE bool sycl::_V1::ext::intel::esimd::detail::isPowerOf2 (unsigned int n, unsigned int limit)
 Check at compile time if given 32 bit positive integer is both: More...
 
constexpr int sycl::_V1::ext::intel::esimd::is_channel_enabled (rgba_channel_mask M, rgba_channel Ch)
 
constexpr int sycl::_V1::ext::intel::esimd::get_num_channels_enabled (rgba_channel_mask M)
 
template<sycl::ext::intel::esimd::atomic_op Op>
constexpr bool sycl::_V1::ext::intel::esimd::detail::has_lsc_equivalent ()
 
template<sycl::ext::intel::esimd::atomic_op Op>
constexpr sycl::ext::intel::esimd::native::lsc::atomic_op sycl::_V1::ext::intel::esimd::detail::to_lsc_atomic_op ()
 
template<sycl::ext::intel::esimd::native::lsc::atomic_op Op>
constexpr sycl::ext::intel::esimd::atomic_op sycl::_V1::ext::intel::esimd::detail::to_atomic_op ()
 
template<sycl::ext::intel::esimd::atomic_op Op>
constexpr int sycl::_V1::ext::intel::esimd::detail::get_num_args ()
 
template<typename T , lsc_data_size DS>
constexpr void sycl::_V1::ext::intel::esimd::detail::check_lsc_data_size ()
 
template<typename T , lsc_data_size DS>
constexpr lsc_data_size sycl::_V1::ext::intel::esimd::detail::finalize_data_size ()
 
template<int VS>
constexpr void sycl::_V1::ext::intel::esimd::detail::check_lsc_vector_size ()
 
template<lsc_vector_size VS>
constexpr uint8_t sycl::_V1::ext::intel::esimd::detail::to_int ()
 
template<int VS>
constexpr lsc_vector_size sycl::_V1::ext::intel::esimd::detail::to_lsc_vector_size ()
 
template<cache_hint Val>
constexpr bool sycl::_V1::ext::intel::esimd::detail::are_all (cache_hint First, cache_hint Second)
 
template<typename PropertyListT >
constexpr bool sycl::_V1::ext::intel::esimd::detail::has_cache_hints ()
 
template<cache_action Action, typename PropertyListT >
void sycl::_V1::ext::intel::esimd::detail::check_cache_hints ()
 
constexpr lsc_data_size sycl::_V1::ext::intel::esimd::detail::expand_data_size (lsc_data_size DS)
 

Variables

static constexpr saturation_off_tag sycl::_V1::ext::intel::esimd::saturation_off {}
 Type tag object representing "saturation off" behavior. More...
 
static constexpr saturation_on_tag sycl::_V1::ext::intel::esimd::saturation_on {}
 Type tag object representing "saturation on" behavior. More...
 
template<class T >
constexpr bool sycl::_V1::ext::intel::esimd::detail::is_saturation_tag_v = is_saturation_tag<T>::value
 
template<rgba_channel Ch>
static constexpr uint8_t sycl::_V1::ext::intel::esimd::detail::ch = 1 << static_cast<int>(Ch)
 
static constexpr uint8_t sycl::_V1::ext::intel::esimd::detail::chR = ch<rgba_channel::R>
 
static constexpr uint8_t sycl::_V1::ext::intel::esimd::detail::chG = ch<rgba_channel::G>
 
static constexpr uint8_t sycl::_V1::ext::intel::esimd::detail::chB = ch<rgba_channel::B>
 
static constexpr uint8_t sycl::_V1::ext::intel::esimd::detail::chA = ch<rgba_channel::A>
 
static constexpr SurfaceIndex sycl::_V1::ext::intel::esimd::detail::SLM_BTI = 254
 
static constexpr SurfaceIndex sycl::_V1::ext::intel::esimd::detail::INVALID_BTI