Skip to content

Commit 4170972

Browse files
aelovikov-intelaelovikov-intel
authored
Revert "[ABI-Break][SYCL] Remove deprecated property use_primary_context (#13…"
This reverts commit 735f1ee.
1 parent 735f1ee commit 4170972

File tree

10 files changed

+159
-3
lines changed

10 files changed

+159
-3
lines changed

‎sycl/include/sycl/detail/cuda_definitions.hpp

+4
Original file line numberDiff line numberDiff line change
@@ -13,6 +13,10 @@
1313

1414
// Mem Object info: Retrieve the raw CUDA pointer from a cl_mem
1515
#define __SYCL_PI_CUDA_RAW_POINTER (0xFF01)
16+
// Context creation: Use a primary CUDA context instead of a custom one by
17+
// providing a property value of PI_TRUE for the following
18+
// property ID.
19+
#define __SYCL_PI_CONTEXT_PROPERTIES_CUDA_PRIMARY (0xFF02)
1620

1721
// PI Command Queue using Default stream
1822
#define __SYCL_PI_CUDA_USE_DEFAULT_STREAM (0xFF03)

‎sycl/include/sycl/detail/properties_traits.def

+4
Original file line numberDiff line numberDiff line change
@@ -8,6 +8,10 @@ __SYCL_PARAM_TRAITS_SPEC(
88
sycl::ext::oneapi::property::buffer::use_pinned_host_memory)
99
__SYCL_PARAM_TRAITS_SPEC(sycl::property::noinit)
1010
__SYCL_PARAM_TRAITS_SPEC(sycl::property::no_init)
11+
__SYCL_PARAM_TRAITS_SPEC(
12+
sycl::property::context::cuda::use_primary_context) // Deprecated
13+
__SYCL_PARAM_TRAITS_SPEC(
14+
sycl::ext::oneapi::cuda::property::context::use_primary_context) // Deprecated
1115
__SYCL_PARAM_TRAITS_SPEC(sycl::property::queue::in_order)
1216
__SYCL_PARAM_TRAITS_SPEC(sycl::property::reduction::initialize_to_identity)
1317
__SYCL_PARAM_TRAITS_SPEC(sycl::ext::oneapi::property::queue::priority_low)

‎sycl/include/sycl/properties/all_properties.hpp

+1
Original file line numberDiff line numberDiff line change
@@ -11,6 +11,7 @@
1111
#include <sycl/ext/codeplay/experimental/fusion_properties.hpp>
1212
#include <sycl/properties/accessor_properties.hpp>
1313
#include <sycl/properties/buffer_properties.hpp>
14+
#include <sycl/properties/context_properties.hpp>
1415
#include <sycl/properties/image_properties.hpp>
1516
#include <sycl/properties/queue_properties.hpp>
1617
#include <sycl/properties/reduction_properties.hpp>

‎sycl/include/sycl/properties/context_properties.hpp

+49
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,49 @@
1+
//==----------- context_properties.hpp --- SYCL context properties ---------==//
2+
//
3+
// Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
4+
// See https://llvm.org/LICENSE.txt for license information.
5+
// SPDX-License-Identifier: Apache-2.0 WITH LLVM-exception
6+
//
7+
//===----------------------------------------------------------------------===//
8+
9+
#pragma once
10+
11+
#include <sycl/detail/defines_elementary.hpp> // for __SYCL2020_DEPRECATED
12+
#include <sycl/detail/property_helper.hpp> // for DataLessPropKind, Dat...
13+
#include <sycl/properties/property_traits.hpp> // for is_property_of
14+
15+
#include <type_traits> // for true_type
16+
17+
namespace sycl {
18+
inline namespace _V1 {
19+
namespace ext::oneapi::cuda::property::context {
20+
class __SYCL_DEPRECATED("the primary contexts are now always used")
21+
use_primary_context : public ::sycl::detail::DataLessProperty<
22+
::sycl::detail::UsePrimaryContext> {};
23+
} // namespace ext::oneapi::cuda::property::context
24+
25+
namespace property::context {
26+
namespace __SYCL2020_DEPRECATED(
27+
"use 'sycl::ext::oneapi::cuda::property::context' instead") cuda {
28+
class use_primary_context
29+
: public ::sycl::ext::oneapi::cuda::property::context::use_primary_context {
30+
};
31+
// clang-format off
32+
} // namespace cuda
33+
// clang-format on
34+
} // namespace property::context
35+
36+
// Forward declaration
37+
class context;
38+
39+
// Context property trait specializations
40+
template <>
41+
struct is_property_of<property::context::cuda::use_primary_context, context>
42+
: std::true_type {};
43+
44+
template <>
45+
struct is_property_of<ext::oneapi::cuda::property::context::use_primary_context,
46+
context> : std::true_type {};
47+
48+
} // namespace _V1
49+
} // namespace sycl

‎sycl/source/detail/context_impl.cpp

+16-2
Original file line numberDiff line numberDiff line change
@@ -19,6 +19,7 @@
1919
#include <sycl/exception_list.hpp>
2020
#include <sycl/info/info_desc.hpp>
2121
#include <sycl/platform.hpp>
22+
#include <sycl/properties/context_properties.hpp>
2223
#include <sycl/property_list.hpp>
2324

2425
#include <algorithm>
@@ -62,8 +63,21 @@ context_impl::context_impl(const std::vector<sycl::device> Devices,
6263
DeviceIds.push_back(getSyclObjImpl(D)->getHandleRef());
6364
}
6465

65-
getPlugin()->call<PiApiKind::piContextCreate>(
66-
nullptr, DeviceIds.size(), DeviceIds.data(), nullptr, nullptr, &MContext);
66+
if (getBackend() == backend::ext_oneapi_cuda) {
67+
const bool UseCUDAPrimaryContext = MPropList.has_property<
68+
ext::oneapi::cuda::property::context::use_primary_context>();
69+
const pi_context_properties Props[] = {
70+
static_cast<pi_context_properties>(
71+
__SYCL_PI_CONTEXT_PROPERTIES_CUDA_PRIMARY),
72+
static_cast<pi_context_properties>(UseCUDAPrimaryContext), 0};
73+
74+
getPlugin()->call<PiApiKind::piContextCreate>(
75+
Props, DeviceIds.size(), DeviceIds.data(), nullptr, nullptr, &MContext);
76+
} else {
77+
getPlugin()->call<PiApiKind::piContextCreate>(nullptr, DeviceIds.size(),
78+
DeviceIds.data(), nullptr,
79+
nullptr, &MContext);
80+
}
6781

6882
MKernelProgramCache.setContextPtr(this);
6983
}

‎sycl/source/detail/queue_impl.hpp

+1
Original file line numberDiff line numberDiff line change
@@ -27,6 +27,7 @@
2727
#include <sycl/exception_list.hpp>
2828
#include <sycl/ext/codeplay/experimental/fusion_properties.hpp>
2929
#include <sycl/handler.hpp>
30+
#include <sycl/properties/context_properties.hpp>
3031
#include <sycl/properties/queue_properties.hpp>
3132
#include <sycl/property_list.hpp>
3233
#include <sycl/queue.hpp>

‎sycl/test-e2e/Basic/context.cpp

+15-1
Original file line numberDiff line numberDiff line change
@@ -53,7 +53,7 @@ int main() {
5353
assert(Context == WillContextCopy);
5454
}
5555
{
56-
auto AsyncHandler = [](const sycl::exception_list) {};
56+
auto AsyncHandler = [](const sycl::exception_list &EL) {};
5757
sycl::context Context1(sycl::property_list{});
5858
sycl::context Context2(AsyncHandler, sycl::property_list{});
5959
sycl::context Context3(deviceA, sycl::property_list{});
@@ -63,5 +63,19 @@ int main() {
6363
sycl::property_list{});
6464
sycl::context Context7(std::vector<sycl::device>{deviceA},
6565
sycl::property_list{});
66+
sycl::context Context8(
67+
std::vector<sycl::device>{deviceA}, AsyncHandler,
68+
sycl::property_list{
69+
sycl::ext::oneapi::cuda::property::context::use_primary_context{}});
70+
71+
if (!Context8.has_property<sycl::ext::oneapi::cuda::property::context::
72+
use_primary_context>()) {
73+
std::cerr << "Line " << __LINE__ << ": Property was not found"
74+
<< std::endl;
75+
return 1;
76+
}
77+
78+
auto Prop = Context8.get_property<
79+
sycl::ext::oneapi::cuda::property::context::use_primary_context>();
6680
}
6781
}

‎sycl/test/abi/sycl_symbols_linux.dump

+20
Original file line numberDiff line numberDiff line change
@@ -3795,6 +3795,7 @@ _ZNK4sycl3_V16detail11device_impl8get_infoINS0_3ext8codeplay12experimental4info6
37953795
_ZNK4sycl3_V16detail11device_impl8get_infoINS0_3ext8codeplay12experimental4info6device28max_registers_per_work_groupEEENT_11return_typeEv
37963796
_ZNK4sycl3_V16detail11image_plain10getSamplerEv
37973797
_ZNK4sycl3_V16detail11image_plain11getRowPitchEv
3798+
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEET_v
37983799
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_3ext6oneapi8property5queue12priority_lowEEET_v
37993800
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_3ext6oneapi8property5queue13priority_highEEET_v
38003801
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_3ext6oneapi8property5queue15priority_normalEEET_v
@@ -3808,8 +3809,10 @@ _ZNK4sycl3_V16detail11image_plain12get_propertyINS0_8property6buffer12use_host_p
38083809
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_8property6buffer13context_boundEEET_v
38093810
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_8property6buffer9use_mutexEEET_v
38103811
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_8property6noinitEEET_v
3812+
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_8property7context4cuda19use_primary_contextEEET_v
38113813
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_8property7no_initEEET_v
38123814
_ZNK4sycl3_V16detail11image_plain12get_propertyINS0_8property9reduction22initialize_to_identityEEET_v
3815+
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEEbv
38133816
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_3ext6oneapi8property5queue12priority_lowEEEbv
38143817
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_3ext6oneapi8property5queue13priority_highEEEbv
38153818
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_3ext6oneapi8property5queue15priority_normalEEEbv
@@ -3823,6 +3826,7 @@ _ZNK4sycl3_V16detail11image_plain12has_propertyINS0_8property6buffer12use_host_p
38233826
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_8property6buffer13context_boundEEEbv
38243827
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_8property6buffer9use_mutexEEEbv
38253828
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_8property6noinitEEEbv
3829+
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_8property7context4cuda19use_primary_contextEEEbv
38263830
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_8property7no_initEEEbv
38273831
_ZNK4sycl3_V16detail11image_plain12has_propertyINS0_8property9reduction22initialize_to_identityEEEbv
38283832
_ZNK4sycl3_V16detail11image_plain13getSlicePitchEv
@@ -3838,6 +3842,7 @@ _ZNK4sycl3_V16detail11stream_impl22get_max_statement_sizeEv
38383842
_ZNK4sycl3_V16detail11stream_impl25get_work_item_buffer_sizeEv
38393843
_ZNK4sycl3_V16detail11stream_impl4sizeEv
38403844
_ZNK4sycl3_V16detail11stream_impl8get_sizeEv
3845+
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEET_v
38413846
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_3ext6oneapi8property5queue12priority_lowEEET_v
38423847
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_3ext6oneapi8property5queue13priority_highEEET_v
38433848
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_3ext6oneapi8property5queue15priority_normalEEET_v
@@ -3851,8 +3856,10 @@ _ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_8property6buffer12use_host_
38513856
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_8property6buffer13context_boundEEET_v
38523857
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_8property6buffer9use_mutexEEET_v
38533858
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_8property6noinitEEET_v
3859+
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_8property7context4cuda19use_primary_contextEEET_v
38543860
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_8property7no_initEEET_v
38553861
_ZNK4sycl3_V16detail12buffer_plain12get_propertyINS0_8property9reduction22initialize_to_identityEEET_v
3862+
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEEbv
38563863
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_3ext6oneapi8property5queue12priority_lowEEEbv
38573864
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_3ext6oneapi8property5queue13priority_highEEEbv
38583865
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_3ext6oneapi8property5queue15priority_normalEEEbv
@@ -3866,6 +3873,7 @@ _ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_8property6buffer12use_host_
38663873
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_8property6buffer13context_boundEEEbv
38673874
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_8property6buffer9use_mutexEEEbv
38683875
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_8property6noinitEEEbv
3876+
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_8property7context4cuda19use_primary_contextEEEbv
38693877
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_8property7no_initEEEbv
38703878
_ZNK4sycl3_V16detail12buffer_plain12has_propertyINS0_8property9reduction22initialize_to_identityEEEbv
38713879
_ZNK4sycl3_V16detail12buffer_plain13handleReleaseEv
@@ -4109,6 +4117,7 @@ _ZNK4sycl3_V16kernel8get_infoINS0_4info22kernel_device_specific22compile_sub_gro
41094117
_ZNK4sycl3_V16kernel8get_infoINS0_4info22kernel_device_specific23compile_work_group_sizeEEENS0_6detail35is_kernel_device_specific_info_descIT_E11return_typeERKNS0_6deviceE
41104118
_ZNK4sycl3_V16kernel8get_infoINS0_4info22kernel_device_specific34preferred_work_group_size_multipleEEENS0_6detail35is_kernel_device_specific_info_descIT_E11return_typeERKNS0_6deviceE
41114119
_ZNK4sycl3_V16kernel9getNativeEv
4120+
_ZNK4sycl3_V16stream12get_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEET_v
41124121
_ZNK4sycl3_V16stream12get_propertyINS0_3ext6oneapi8property5queue12priority_lowEEET_v
41134122
_ZNK4sycl3_V16stream12get_propertyINS0_3ext6oneapi8property5queue13priority_highEEET_v
41144123
_ZNK4sycl3_V16stream12get_propertyINS0_3ext6oneapi8property5queue15priority_normalEEET_v
@@ -4122,8 +4131,10 @@ _ZNK4sycl3_V16stream12get_propertyINS0_8property6buffer12use_host_ptrEEET_v
41224131
_ZNK4sycl3_V16stream12get_propertyINS0_8property6buffer13context_boundEEET_v
41234132
_ZNK4sycl3_V16stream12get_propertyINS0_8property6buffer9use_mutexEEET_v
41244133
_ZNK4sycl3_V16stream12get_propertyINS0_8property6noinitEEET_v
4134+
_ZNK4sycl3_V16stream12get_propertyINS0_8property7context4cuda19use_primary_contextEEET_v
41254135
_ZNK4sycl3_V16stream12get_propertyINS0_8property7no_initEEET_v
41264136
_ZNK4sycl3_V16stream12get_propertyINS0_8property9reduction22initialize_to_identityEEET_v
4137+
_ZNK4sycl3_V16stream12has_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEEbv
41274138
_ZNK4sycl3_V16stream12has_propertyINS0_3ext6oneapi8property5queue12priority_lowEEEbv
41284139
_ZNK4sycl3_V16stream12has_propertyINS0_3ext6oneapi8property5queue13priority_highEEEbv
41294140
_ZNK4sycl3_V16stream12has_propertyINS0_3ext6oneapi8property5queue15priority_normalEEEbv
@@ -4137,6 +4148,7 @@ _ZNK4sycl3_V16stream12has_propertyINS0_8property6buffer12use_host_ptrEEEbv
41374148
_ZNK4sycl3_V16stream12has_propertyINS0_8property6buffer13context_boundEEEbv
41384149
_ZNK4sycl3_V16stream12has_propertyINS0_8property6buffer9use_mutexEEEbv
41394150
_ZNK4sycl3_V16stream12has_propertyINS0_8property6noinitEEEbv
4151+
_ZNK4sycl3_V16stream12has_propertyINS0_8property7context4cuda19use_primary_contextEEEbv
41404152
_ZNK4sycl3_V16stream12has_propertyINS0_8property7no_initEEEbv
41414153
_ZNK4sycl3_V16stream12has_propertyINS0_8property9reduction22initialize_to_identityEEEbv
41424154
_ZNK4sycl3_V16stream22get_max_statement_sizeEv
@@ -4148,6 +4160,7 @@ _ZNK4sycl3_V16streamneERKS1_
41484160
_ZNK4sycl3_V17context11get_backendEv
41494161
_ZNK4sycl3_V17context11get_devicesEv
41504162
_ZNK4sycl3_V17context12get_platformEv
4163+
_ZNK4sycl3_V17context12get_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEET_v
41514164
_ZNK4sycl3_V17context12get_propertyINS0_3ext6oneapi8property5queue12priority_lowEEET_v
41524165
_ZNK4sycl3_V17context12get_propertyINS0_3ext6oneapi8property5queue13priority_highEEET_v
41534166
_ZNK4sycl3_V17context12get_propertyINS0_3ext6oneapi8property5queue15priority_normalEEET_v
@@ -4161,8 +4174,10 @@ _ZNK4sycl3_V17context12get_propertyINS0_8property6buffer12use_host_ptrEEET_v
41614174
_ZNK4sycl3_V17context12get_propertyINS0_8property6buffer13context_boundEEET_v
41624175
_ZNK4sycl3_V17context12get_propertyINS0_8property6buffer9use_mutexEEET_v
41634176
_ZNK4sycl3_V17context12get_propertyINS0_8property6noinitEEET_v
4177+
_ZNK4sycl3_V17context12get_propertyINS0_8property7context4cuda19use_primary_contextEEET_v
41644178
_ZNK4sycl3_V17context12get_propertyINS0_8property7no_initEEET_v
41654179
_ZNK4sycl3_V17context12get_propertyINS0_8property9reduction22initialize_to_identityEEET_v
4180+
_ZNK4sycl3_V17context12has_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEEbv
41664181
_ZNK4sycl3_V17context12has_propertyINS0_3ext6oneapi8property5queue12priority_lowEEEbv
41674182
_ZNK4sycl3_V17context12has_propertyINS0_3ext6oneapi8property5queue13priority_highEEEbv
41684183
_ZNK4sycl3_V17context12has_propertyINS0_3ext6oneapi8property5queue15priority_normalEEEbv
@@ -4176,6 +4191,7 @@ _ZNK4sycl3_V17context12has_propertyINS0_8property6buffer12use_host_ptrEEEbv
41764191
_ZNK4sycl3_V17context12has_propertyINS0_8property6buffer13context_boundEEEbv
41774192
_ZNK4sycl3_V17context12has_propertyINS0_8property6buffer9use_mutexEEEbv
41784193
_ZNK4sycl3_V17context12has_propertyINS0_8property6noinitEEEbv
4194+
_ZNK4sycl3_V17context12has_propertyINS0_8property7context4cuda19use_primary_contextEEEbv
41794195
_ZNK4sycl3_V17context12has_propertyINS0_8property7no_initEEEbv
41804196
_ZNK4sycl3_V17context12has_propertyINS0_8property9reduction22initialize_to_identityEEEbv
41814197
_ZNK4sycl3_V17context16get_backend_infoINS0_4info6device15backend_versionEEENS0_6detail20is_backend_info_descIT_E11return_typeEv
@@ -4195,6 +4211,7 @@ _ZNK4sycl3_V17handler15getCommandGraphEv
41954211
_ZNK4sycl3_V17handler17getContextImplPtrEv
41964212
_ZNK4sycl3_V17handler27isStateExplicitKernelBundleEv
41974213
_ZNK4sycl3_V17handler30getOrInsertHandlerKernelBundleEb
4214+
_ZNK4sycl3_V17sampler12get_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEET_v
41984215
_ZNK4sycl3_V17sampler12get_propertyINS0_3ext6oneapi8property5queue12priority_lowEEET_v
41994216
_ZNK4sycl3_V17sampler12get_propertyINS0_3ext6oneapi8property5queue13priority_highEEET_v
42004217
_ZNK4sycl3_V17sampler12get_propertyINS0_3ext6oneapi8property5queue15priority_normalEEET_v
@@ -4208,8 +4225,10 @@ _ZNK4sycl3_V17sampler12get_propertyINS0_8property6buffer12use_host_ptrEEET_v
42084225
_ZNK4sycl3_V17sampler12get_propertyINS0_8property6buffer13context_boundEEET_v
42094226
_ZNK4sycl3_V17sampler12get_propertyINS0_8property6buffer9use_mutexEEET_v
42104227
_ZNK4sycl3_V17sampler12get_propertyINS0_8property6noinitEEET_v
4228+
_ZNK4sycl3_V17sampler12get_propertyINS0_8property7context4cuda19use_primary_contextEEET_v
42114229
_ZNK4sycl3_V17sampler12get_propertyINS0_8property7no_initEEET_v
42124230
_ZNK4sycl3_V17sampler12get_propertyINS0_8property9reduction22initialize_to_identityEEET_v
4231+
_ZNK4sycl3_V17sampler12has_propertyINS0_3ext6oneapi4cuda8property7context19use_primary_contextEEEbv
42134232
_ZNK4sycl3_V17sampler12has_propertyINS0_3ext6oneapi8property5queue12priority_lowEEEbv
42144233
_ZNK4sycl3_V17sampler12has_propertyINS0_3ext6oneapi8property5queue13priority_highEEEbv
42154234
_ZNK4sycl3_V17sampler12has_propertyINS0_3ext6oneapi8property5queue15priority_normalEEEbv
@@ -4223,6 +4242,7 @@ _ZNK4sycl3_V17sampler12has_propertyINS0_8property6buffer12use_host_ptrEEEbv
42234242
_ZNK4sycl3_V17sampler12has_propertyINS0_8property6buffer13context_boundEEEbv
42244243
_ZNK4sycl3_V17sampler12has_propertyINS0_8property6buffer9use_mutexEEEbv
42254244
_ZNK4sycl3_V17sampler12has_propertyINS0_8property6noinitEEEbv
4245+
_ZNK4sycl3_V17sampler12has_propertyINS0_8property7context4cuda19use_primary_contextEEEbv
42264246
_ZNK4sycl3_V17sampler12has_propertyINS0_8property7no_initEEEbv
42274247
_ZNK4sycl3_V17sampler12has_propertyINS0_8property9reduction22initialize_to_identityEEEbv
42284248
_ZNK4sycl3_V17sampler18get_filtering_modeEv

0 commit comments

Comments
 (0)