Namespaces | |
cuda | |
detail | |
info | |
matrix | |
native | |
simd_abi | |
Typedefs | |
using | global_pointer_t = T * |
template<class T , int N> | |
using | simd = std::experimental::simd< T, simd_abi::native_fixed_size< T, N > > |
template<class T , int N> | |
using | simd_mask = std::experimental::simd_mask< T, simd_abi::native_fixed_size< T, N > > |
Functions | |
template<typename T , typename... Args> | |
annotated_arg (T, Args...) -> annotated_arg< T, typename detail::DeducedProperties< Args... >::type > | |
template<typename T , typename old , typename... ArgT> | |
annotated_arg (annotated_arg< T, old >, properties< std::tuple< ArgT... >>) -> annotated_arg< T, detail::merged_properties_t< old, detail::properties_t< ArgT... >>> | |
template<typename T , typename... Props> | |
class __SYCL_SPECIAL_CLASS | __SYCL_TYPE (annotated_arg) annotated_arg< T * |
annotated_arg (const annotated_arg &)=default | |
annotated_arg & | operator= (annotated_arg &)=default |
annotated_arg (T *_ptr, const property_list_t &PropList=properties{}) noexcept | |
template<typename... PropertyValueTs> | |
annotated_arg (T *_ptr, const PropertyValueTs &...props) noexcept | |
template<typename T2 , typename PropertyList2 > | |
annotated_arg (const annotated_arg< T2, PropertyList2 > &other) noexcept | |
template<typename T2 , typename PropertyListU , typename PropertyListV > | |
annotated_arg (const annotated_arg< T2, PropertyListU > &other, const PropertyListV &proplist) noexcept | |
operator T* () noexcept | |
T & | operator[] (std::ptrdiff_t idx) const noexcept |
template<typename PropertyT > | |
static constexpr bool | has_property () |
template<typename PropertyT > | |
static constexpr auto | get_property () |
annotated_arg (const T &_obj, const property_list_t &PropList=properties{}) noexcept | |
template<typename... PropertyValueTs> | |
annotated_arg (const T &_obj, PropertyValueTs... props) noexcept | |
operator T () noexcept | |
template<typename T > | |
std::enable_if_t< std::is_same< T, bfloat16 >::value, bool > | isnan (T x) |
template<size_t N> | |
sycl::marray< bool, N > | isnan (sycl::marray< bfloat16, N > x) |
template<typename T > | |
std::enable_if_t< std::is_same< T, bfloat16 >::value, T > | fabs (T x) |
template<size_t N> | |
sycl::marray< bfloat16, N > | fabs (sycl::marray< bfloat16, N > x) |
template<typename T > | |
std::enable_if_t< std::is_same< T, bfloat16 >::value, T > | fmin (T x, T y) |
template<size_t N> | |
sycl::marray< bfloat16, N > | fmin (sycl::marray< bfloat16, N > x, sycl::marray< bfloat16, N > y) |
template<typename T > | |
std::enable_if_t< std::is_same< T, bfloat16 >::value, T > | fmax (T x, T y) |
template<size_t N> | |
sycl::marray< bfloat16, N > | fmax (sycl::marray< bfloat16, N > x, sycl::marray< bfloat16, N > y) |
template<typename T > | |
std::enable_if_t< std::is_same< T, bfloat16 >::value, T > | fma (T x, T y, T z) |
template<size_t N> | |
sycl::marray< bfloat16, N > | fma (sycl::marray< bfloat16, N > x, sycl::marray< bfloat16, N > y, sycl::marray< bfloat16, N > z) |
template<typename FormatT , typename... Args> | |
int | printf (const FormatT *__format, Args... args) |
template<architecture... Archs, typename T , typename... Args> | |
constexpr static auto | if_architecture_is (T fnTrue, Args... args) |
template<typename Group , typename T , typename Sorter > | |
std::enable_if< detail::is_sorter< Sorter, Group, T >::value, T >::type | sort_over_group (Group group, T value, Sorter sorter) |
template<typename Group , typename T , typename Compare , size_t Extent> | |
std::enable_if<!detail::is_sorter< Compare, Group, T >::value, T >::type | sort_over_group (experimental::group_with_scratchpad< Group, Extent > exec, T value, Compare comp) |
template<typename Group , typename T , size_t Extent> | |
std::enable_if< sycl::is_group_v< std::decay_t< Group > >, T >::type | sort_over_group (experimental::group_with_scratchpad< Group, Extent > exec, T value) |
template<typename Group , typename Iter , typename Sorter > | |
std::enable_if< detail::is_sorter< Sorter, Group, Iter >::value, void >::type | joint_sort (Group group, Iter first, Iter last, Sorter sorter) |
template<typename Group , typename Iter , typename Compare , size_t Extent> | |
std::enable_if<!detail::is_sorter< Compare, Group, Iter >::value, void >::type | joint_sort (experimental::group_with_scratchpad< Group, Extent > exec, Iter first, Iter last, Compare comp) |
template<typename Group , typename Iter , size_t Extent> | |
std::enable_if< sycl::is_group_v< std::decay_t< Group > >, void >::type | joint_sort (experimental::group_with_scratchpad< Group, Extent > exec, Iter first, Iter last) |
template<class Callable , class... T> | |
__attribute__ ((always_inline)) auto invoke_simd(sycl | |
The invoke_simd free function invokes a SIMD function using all work-items in a sub_group. More... | |
template<typename T , typename ID = T> | |
class | __SYCL2020_DEPRECATED ("Specialization constats extension is deprecated, use SYCL 2020" " specialization constants instead") __SYCL_TYPE(spec_constant) spec_constant |
template<typename GroupHelper , typename T , typename BinaryOperation > | |
sycl::detail::enable_if_t<(is_group_helper_v< GroupHelper >), T > | reduce_over_group (GroupHelper group_helper, T x, BinaryOperation binary_op) |
template<typename GroupHelper , typename V , typename T , typename BinaryOperation > | |
sycl::detail::enable_if_t<(is_group_helper_v< GroupHelper >), T > | reduce_over_group (GroupHelper group_helper, V x, T init, BinaryOperation binary_op) |
template<typename GroupHelper , typename Ptr , typename BinaryOperation > | |
sycl::detail::enable_if_t<(is_group_helper_v< GroupHelper > &&sycl::detail::is_pointer< Ptr >::value), typename std::iterator_traits< Ptr >::value_type > | joint_reduce (GroupHelper group_helper, Ptr first, Ptr last, BinaryOperation binary_op) |
template<typename GroupHelper , typename Ptr , typename T , typename BinaryOperation > | |
sycl::detail::enable_if_t<(is_group_helper_v< GroupHelper > &&sycl::detail::is_pointer< Ptr >::value), T > | joint_reduce (GroupHelper group_helper, Ptr first, Ptr last, T init, BinaryOperation binary_op) |
template<typename PropertyT , typename... A, typename... B> | |
constexpr std::enable_if_t< detail::IsCompileTimeProperty< PropertyT >::value, bool > | operator== (const property_value< PropertyT, A... > &, const property_value< PropertyT, B... > &) |
template<typename PropertyT , typename... A, typename... B> | |
constexpr std::enable_if_t< detail::IsCompileTimeProperty< PropertyT >::value, bool > | operator!= (const property_value< PropertyT, A... > &, const property_value< PropertyT, B... > &) |
sub_group | this_sub_group () |
template<int Dims> | |
group< Dims > | this_group () |
template<int Dims> | |
id< Dims > | this_id () |
template<int Dims> | |
item< Dims > | this_item () |
template<int Dims> | |
nd_item< Dims > | this_nd_item () |
using sycl::_V1::ext::oneapi::experimental::global_pointer_t = typedef T * |
Definition at line 73 of file annotated_arg.hpp.
using sycl::_V1::ext::oneapi::experimental::simd = typedef std::experimental::simd<T, simd_abi::native_fixed_size<T, N> > |
Definition at line 88 of file invoke_simd.hpp.
using sycl::_V1::ext::oneapi::experimental::simd_mask = typedef std::experimental::simd_mask<T, simd_abi::native_fixed_size<T, N> > |
This is basically an alias of the detail::simd_mask_impl class.
Definition at line 92 of file invoke_simd.hpp.
Definition at line 9 of file device_architecture.hpp.
|
strong |
Enumerator | |
---|---|
read | |
write | |
read_write | |
none |
Definition at line 24 of file properties.hpp.
|
strong |
Enumerator | |
---|---|
reprogram | |
reset |
Definition at line 33 of file properties.hpp.
|
strong |
Enumerator | |
---|---|
read_write | |
read | |
write |
Definition at line 58 of file properties.hpp.
Enumerator | |
---|---|
ascending | |
descending |
Definition at line 94 of file group_helpers_sorters.hpp.
sycl::_V1::ext::oneapi::experimental::__attribute__ | ( | (always_inline) | ) |
The invoke_simd free function invokes a SIMD function using all work-items in a sub_group.
The invoke_simd interface marshals data between the SPMD context of the calling kernel and the SIMD context of the callee, converting arguments and return values between scalar and SIMD types as appropriate.
sg | the subgroup simd function is invoked from |
f | represents the invoked simd function. Must be a C++ callable that can be invoked with the same number of arguments specified in the args parameter pack. Callable may be a function object, a lambda, or a function pointer (if the device supports SPV_INTEL_function_pointers). Callable must be an immutable callable with the same type and state for all work-items in the sub-group, otherwise behavior is undefined. |
args | SPMD parameters to the invoked function, which undergo transformation before actual passing to the simd function, as described in the specification. |
Definition at line 332 of file invoke_simd.hpp.
References __builtin_invoke_simd(), sycl::_V1::ext::oneapi::experimental::detail::get_sg_size(), sycl::_V1::ext::oneapi::experimental::detail::simd_func_call_helper(), and sycl::_V1::ext::oneapi::experimental::detail::simd_obj_call_helper().
Referenced by sycl::_V1::ext::oneapi::group_local_memory(), and sycl::_V1::ext::oneapi::group_local_memory_for_overwrite().
class sycl::_V1::ext::oneapi::experimental::__SYCL2020_DEPRECATED | ( | "Specialization constats extension is | deprecated, |
use SYCL 2020" " specialization constants instead" | |||
) |
Definition at line 1 of file spec_constant.hpp.
References __SYCL_INLINE_VER_NAMESPACE.
class __SYCL_SPECIAL_CLASS sycl::_V1::ext::oneapi::experimental::__SYCL_TYPE | ( | annotated_arg | ) |
sycl::_V1::ext::oneapi::experimental::annotated_arg | ( | annotated_arg< T, old > | , |
properties< std::tuple< ArgT... >> | |||
) | -> annotated_arg< T, detail::merged_properties_t< old, detail::properties_t< ArgT... >>> |
|
default |
|
explicitnoexcept |
Definition at line 123 of file annotated_arg.hpp.
|
explicitnoexcept |
Definition at line 142 of file annotated_arg.hpp.
|
noexcept |
Definition at line 200 of file annotated_arg.hpp.
|
noexcept |
Definition at line 211 of file annotated_arg.hpp.
|
noexcept |
Definition at line 96 of file annotated_arg.hpp.
|
noexcept |
Definition at line 107 of file annotated_arg.hpp.
sycl::_V1::ext::oneapi::experimental::annotated_arg | ( | T | , |
Args... | |||
) | -> annotated_arg< T, typename detail::DeducedProperties< Args... >::type > |
sycl::marray<bfloat16, N> sycl::_V1::ext::oneapi::experimental::fabs | ( | sycl::marray< bfloat16, N > | x | ) |
Definition at line 63 of file bfloat16_math.hpp.
References sycl::_V1::ext::oneapi::detail::bfloat16ToBits(), sycl::_V1::ext::oneapi::detail::bitsToBfloat16(), sycl::_V1::detail::memcpy(), and sycl::_V1::ext::oneapi::experimental::detail::to_uint32_t().
std::enable_if_t<std::is_same<T, bfloat16>::value, T> sycl::_V1::ext::oneapi::experimental::fabs | ( | T | x | ) |
Definition at line 50 of file bfloat16_math.hpp.
References sycl::_V1::ext::oneapi::detail::bfloat16ToBits(), and sycl::_V1::ext::oneapi::detail::bitsToBfloat16().
std::enable_if_t<std::is_same<T, bfloat16>::value, T> sycl::_V1::ext::oneapi::experimental::fma | ( | T | x, |
T | y, | ||
T | z | ||
) |
Definition at line 192 of file bfloat16_math.hpp.
References sycl::_V1::ext::oneapi::detail::bfloat16ToBits(), sycl::_V1::ext::oneapi::detail::bitsToBfloat16(), and sycl::_V1::ext::oneapi::fma().
std::enable_if_t<std::is_same<T, bfloat16>::value, T> sycl::_V1::ext::oneapi::experimental::fmax | ( | T | x, |
T | y | ||
) |
Definition at line 140 of file bfloat16_math.hpp.
References sycl::_V1::ext::oneapi::detail::bfloat16ToBits(), sycl::_V1::ext::oneapi::detail::bitsToBfloat16(), sycl::_V1::ext::oneapi::fmax(), and isnan().
std::enable_if_t<std::is_same<T, bfloat16>::value, T> sycl::_V1::ext::oneapi::experimental::fmin | ( | T | x, |
T | y | ||
) |
Definition at line 87 of file bfloat16_math.hpp.
References sycl::_V1::ext::oneapi::detail::bfloat16ToBits(), sycl::_V1::ext::oneapi::detail::bitsToBfloat16(), sycl::_V1::ext::oneapi::fmin(), and isnan().
|
staticconstexpr |
Definition at line 166 of file annotated_arg.hpp.
|
staticconstexpr |
Definition at line 162 of file annotated_arg.hpp.
Referenced by sycl::_V1::detail::getPromotionTarget().
|
staticconstexpr |
Definition at line 507 of file device_architecture.hpp.
sycl::marray<bool, N> sycl::_V1::ext::oneapi::experimental::isnan | ( | sycl::marray< bfloat16, N > | x | ) |
Definition at line 41 of file bfloat16_math.hpp.
std::enable_if_t<std::is_same<T, bfloat16>::value, bool> sycl::_V1::ext::oneapi::experimental::isnan | ( | T | x | ) |
Definition at line 36 of file bfloat16_math.hpp.
References sycl::_V1::ext::oneapi::detail::bfloat16ToBits().
Referenced by sycl::_V1::detail::checkForInfNan(), sycl::_V1::ext::intel::math::hequ(), sycl::_V1::ext::intel::math::hgeu(), sycl::_V1::ext::intel::math::hgtu(), sycl::_V1::ext::intel::math::hisnan(), sycl::_V1::ext::intel::math::hleu(), sycl::_V1::ext::intel::math::hltu(), sycl::_V1::ext::intel::math::hne(), sycl::_V1::ext::intel::math::hneu(), and sycl::_V1::ext::oneapi::bfloat16::~bfloat16().
sycl::detail::enable_if_t<(is_group_helper_v<GroupHelper> && sycl::detail::is_pointer<Ptr>::value), typename std::iterator_traits<Ptr>::value_type> sycl::_V1::ext::oneapi::experimental::joint_reduce | ( | GroupHelper | group_helper, |
Ptr | first, | ||
Ptr | last, | ||
BinaryOperation | binary_op | ||
) |
Definition at line 86 of file user_defined_reductions.hpp.
References sycl::_V1::detail::for_each(), sycl::_V1::group_barrier(), joint_reduce(), and sycl::_V1::ext::oneapi::experimental::detail::reduce_over_group_impl().
sycl::detail::enable_if_t< (is_group_helper_v<GroupHelper> && sycl::detail::is_pointer<Ptr>::value), T> sycl::_V1::ext::oneapi::experimental::joint_reduce | ( | GroupHelper | group_helper, |
Ptr | first, | ||
Ptr | last, | ||
T | init, | ||
BinaryOperation | binary_op | ||
) |
Definition at line 122 of file user_defined_reductions.hpp.
Referenced by joint_reduce().
std::enable_if<sycl::is_group_v<std::decay_t<Group> >, void>::type sycl::_V1::ext::oneapi::experimental::joint_sort | ( | experimental::group_with_scratchpad< Group, Extent > | exec, |
Iter | first, | ||
Iter | last | ||
) |
Definition at line 131 of file group_sort.hpp.
References sycl::_V1::ext::oneapi::experimental::group_with_scratchpad< Group, Extent >::get_group(), and sycl::_V1::ext::oneapi::experimental::group_with_scratchpad< Group, Extent >::get_memory().
Referenced by joint_sort().
std::enable_if<!detail::is_sorter<Compare, Group, Iter>::value, void>::type sycl::_V1::ext::oneapi::experimental::joint_sort | ( | experimental::group_with_scratchpad< Group, Extent > | exec, |
Iter | first, | ||
Iter | last, | ||
Compare | comp | ||
) |
std::enable_if<detail::is_sorter<Sorter, Group, Iter>::value, void>::type sycl::_V1::ext::oneapi::experimental::joint_sort | ( | Group | group, |
Iter | first, | ||
Iter | last, | ||
Sorter | sorter | ||
) |
Definition at line 106 of file group_sort.hpp.
References sycl::_V1::sycl_category().
|
noexcept |
Definition at line 260 of file annotated_arg.hpp.
References obj.
|
noexcept |
Definition at line 157 of file annotated_arg.hpp.
References obj.
|
constexpr |
Definition at line 53 of file property_value.hpp.
|
default |
|
constexpr |
Definition at line 45 of file property_value.hpp.
|
noexcept |
Definition at line 160 of file annotated_arg.hpp.
References obj.
Referenced by sycl::_V1::ext::oneapi::sub_group_mask::find_high(), sycl::_V1::ext::oneapi::sub_group_mask::flip(), sycl::_V1::ext::oneapi::sub_group_mask::reset(), sycl::_V1::ext::oneapi::sub_group_mask::set(), and sycl::_V1::ext::oneapi::sub_group_mask::test().
int sycl::_V1::ext::oneapi::experimental::printf | ( | const FormatT * | __format, |
Args... | args | ||
) |
Definition at line 75 of file builtins.hpp.
Referenced by sycl::_V1::detail::stream_impl::flush().
sycl::detail::enable_if_t<(is_group_helper_v<GroupHelper>), T> sycl::_V1::ext::oneapi::experimental::reduce_over_group | ( | GroupHelper | group_helper, |
T | x, | ||
BinaryOperation | binary_op | ||
) |
Definition at line 48 of file user_defined_reductions.hpp.
References reduce_over_group(), and sycl::_V1::ext::oneapi::experimental::detail::reduce_over_group_impl().
Referenced by sycl::_V1::detail::NDRangeReduction< reduction::strategy::group_reduce_and_last_wg_detection >::run(), sycl::_V1::detail::NDRangeReduction< reduction::strategy::group_reduce_and_atomic_cross_wg >::run(), and sycl::_V1::detail::NDRangeReduction< reduction::strategy::group_reduce_and_multiple_kernels >::run().
sycl::detail::enable_if_t<(is_group_helper_v<GroupHelper>), T> sycl::_V1::ext::oneapi::experimental::reduce_over_group | ( | GroupHelper | group_helper, |
V | x, | ||
T | init, | ||
BinaryOperation | binary_op | ||
) |
Definition at line 65 of file user_defined_reductions.hpp.
Referenced by reduce_over_group().
std::enable_if<sycl::is_group_v<std::decay_t<Group> >, T>::type sycl::_V1::ext::oneapi::experimental::sort_over_group | ( | experimental::group_with_scratchpad< Group, Extent > | exec, |
T | value | ||
) |
Definition at line 96 of file group_sort.hpp.
References sycl::_V1::ext::oneapi::experimental::group_with_scratchpad< Group, Extent >::get_group(), and sycl::_V1::ext::oneapi::experimental::group_with_scratchpad< Group, Extent >::get_memory().
Referenced by sort_over_group().
std::enable_if<!detail::is_sorter<Compare, Group, T>::value, T>::type sycl::_V1::ext::oneapi::experimental::sort_over_group | ( | experimental::group_with_scratchpad< Group, Extent > | exec, |
T | value, | ||
Compare | comp | ||
) |
std::enable_if<detail::is_sorter<Sorter, Group, T>::value, T>::type sycl::_V1::ext::oneapi::experimental::sort_over_group | ( | Group | group, |
T | value, | ||
Sorter | sorter | ||
) |
Definition at line 72 of file group_sort.hpp.
References sycl::_V1::sycl_category().
group<Dims> sycl::_V1::ext::oneapi::experimental::this_group | ( | ) |
Definition at line 553 of file group.hpp.
References sycl::_V1::detail::declptr(), and sycl::_V1::make_error_code().
id<Dims> sycl::_V1::ext::oneapi::experimental::this_id | ( | ) |
Definition at line 364 of file id.hpp.
References sycl::_V1::detail::declptr(), and sycl::_V1::make_error_code().
item<Dims> sycl::_V1::ext::oneapi::experimental::this_item | ( | ) |
Definition at line 156 of file item.hpp.
References sycl::_V1::detail::declptr(), and sycl::_V1::make_error_code().
nd_item<Dims> sycl::_V1::ext::oneapi::experimental::this_nd_item | ( | ) |
Definition at line 206 of file nd_item.hpp.
References sycl::_V1::detail::declptr(), and sycl::_V1::make_error_code().
|
inline |
Definition at line 21 of file sub_group.hpp.
|
inlineconstexpr |
Definition at line 86 of file properties.hpp.
|
inlineconstexpr |
Definition at line 85 of file properties.hpp.
Referenced by sycl::_V1::detail::usm::alignedAllocHost(), and sycl::_V1::detail::usm::alignedAllocInternal().
|
inlineconstexpr |
Definition at line 80 of file properties.hpp.
|
inlineconstexpr |
Definition at line 120 of file properties.hpp.
Referenced by sycl::_V1::queue::submit().
|
inlineconstexpr |
Definition at line 48 of file properties.hpp.
|
inlineconstexpr |
Definition at line 87 of file properties.hpp.
|
inlineconstexpr |
Definition at line 51 of file properties.hpp.
|
inlineconstexpr |
Definition at line 59 of file properties.hpp.
|
inlineconstexpr |
Definition at line 53 of file properties.hpp.
|
inlineconstexpr |
Definition at line 57 of file properties.hpp.
|
inlineconstexpr |
Definition at line 55 of file properties.hpp.
|
inlineconstexpr |
Definition at line 68 of file properties.hpp.
|
inlineconstexpr |
Definition at line 70 of file properties.hpp.
|
inlineconstexpr |
Definition at line 69 of file properties.hpp.
|
inlineconstexpr |
Definition at line 62 of file properties.hpp.
|
inlineconstexpr |
Definition at line 64 of file properties.hpp.
|
inlineconstexpr |
Definition at line 65 of file properties.hpp.
|
inlineconstexpr |
Definition at line 72 of file type_traits.hpp.
|
inlineconstexpr |
Definition at line 88 of file properties.hpp.
|
inlineconstexpr |
Definition at line 89 of file properties.hpp.
T sycl::_V1::ext::oneapi::experimental::obj |
Definition at line 76 of file annotated_arg.hpp.
Referenced by sycl::_V1::detail::get_or_store(), sycl::_V1::detail::getPromotionTarget(), operator T(), operator T*(), and operator[]().
|
inlineconstexpr |
Definition at line 96 of file properties.hpp.
|
inlineconstexpr |
Definition at line 98 of file properties.hpp.
|
inlineconstexpr |
Definition at line 102 of file properties.hpp.
|
inlineconstexpr |
Definition at line 100 of file properties.hpp.
|
inlineconstexpr |
Definition at line 79 of file properties.hpp.
|
inlineconstexpr |
Definition at line 81 of file properties.hpp.
|
inlineconstexpr |
Definition at line 117 of file properties.hpp.
|
inlineconstexpr |
Definition at line 91 of file properties.hpp.
|
inlineconstexpr |
Definition at line 93 of file properties.hpp.
|
inlineconstexpr |
Definition at line 92 of file properties.hpp.
|
inlineconstexpr |
Definition at line 110 of file properties.hpp.
Referenced by sycl::_V1::detail::get_kernel_device_specific_info_host< info::kernel_device_specific::preferred_work_group_size_multiple >().
|
inlineconstexpr |
Definition at line 114 of file properties.hpp.