Skip to content

Commit a50ff94

Browse files
aelovikov-intelaelovikov-intel
committed
[SYCL] Remove ESIMD Emulator
1 parent a318776 commit a50ff94

19 files changed

+18
-169
lines changed

‎sycl/doc/GetStartedGuide.md

Lines changed: 0 additions & 27 deletions
Original file line numberDiff line numberDiff line change
@@ -12,7 +12,6 @@ and a wide range of compute accelerators such as GPU and FPGA.
1212
* [Build DPC++ toolchain with support for NVIDIA CUDA](#build-dpc-toolchain-with-support-for-nvidia-cuda)
1313
* [Build DPC++ toolchain with support for HIP AMD](#build-dpc-toolchain-with-support-for-hip-amd)
1414
* [Build DPC++ toolchain with support for HIP NVIDIA](#build-dpc-toolchain-with-support-for-hip-nvidia)
15-
* [Build DPC++ toolchain with support for ESIMD CPU Emulation](#build-dpc-toolchain-with-support-for-esimd-cpu-emulation)
1615
* [Build DPC++ toolchain with support for runtime kernel fusion](#build-dpc-toolchain-with-support-for-runtime-kernel-fusion)
1716
* [Build DPC++ toolchain with a custom Unified Runtime](#build-dpc-toolchain-with-a-custom-unified-runtime)
1817
* [Build Doxygen documentation](#build-doxygen-documentation)
@@ -302,32 +301,6 @@ as well as the CUDA Runtime API to be installed, see
302301
Currently, this has only been tried on Linux, with ROCm 4.2.0 or 4.3.0, with
303302
CUDA 11, and using a GeForce 1060 device.
304303

305-
### Build DPC++ toolchain with support for ESIMD CPU Emulation
306-
307-
There is experimental support for DPC++ for using ESIMD CPU Emulation.
308-
309-
This feature supports ESIMD CPU Emulation using CM_EMU library
310-
[CM Emulation project](https://github.com/intel/cm-cpu-emulation). The library
311-
package will be generated from source codes downloaded from its open source
312-
project and installed in your deploy directory during toolchain build.
313-
314-
To enable support for ESIMD CPU emulation, follow the instructions for the Linux
315-
DPC++ toolchain, but add the `--enable-esimd-emulator`.
316-
317-
Enabling this flag requires following packages installed.
318-
319-
* Ubuntu 22.04
320-
* libva-dev / 2.7.0-2
321-
* libffi-dev / 3.3-4
322-
* libtool
323-
* RHEL 8.\*
324-
* libffi
325-
* libffi-devel
326-
* libva
327-
* libva-devel
328-
329-
Currently, this feature was tested and verified on Ubuntu 22.04 environment.
330-
331304
### Build DPC++ toolchain with support for runtime kernel fusion
332305

333306
Support for the experimental SYCL extension for user-driven kernel fusion at

‎sycl/include/sycl/backend_types.hpp

Lines changed: 2 additions & 7 deletions
Original file line numberDiff line numberDiff line change
@@ -21,8 +21,8 @@ enum class backend : char {
2121
ext_oneapi_level_zero = 2,
2222
ext_oneapi_cuda = 3,
2323
all = 4,
24-
ext_intel_esimd_emulator __SYCL_DEPRECATED(
25-
"esimd emulator is no longer supported") = 5,
24+
// No support anymore:
25+
// ext_intel_esimd_emulator = 5,
2626
ext_oneapi_hip = 6,
2727
ext_oneapi_native_cpu = 7,
2828
};
@@ -50,9 +50,6 @@ inline std::ostream &operator<<(std::ostream &Out, backend be) {
5050
case backend::ext_oneapi_cuda:
5151
Out << "ext_oneapi_cuda";
5252
break;
53-
case backend::ext_intel_esimd_emulator:
54-
Out << "ext_intel_esimd_emulator";
55-
break;
5653
case backend::ext_oneapi_hip:
5754
Out << "ext_oneapi_hip";
5855
break;
@@ -76,8 +73,6 @@ inline std::string_view get_backend_name_no_vendor(backend Backend) {
7673
return "level_zero";
7774
case backend::ext_oneapi_cuda:
7875
return "cuda";
79-
case backend::ext_intel_esimd_emulator:
80-
return "esimd_emulator";
8176
case backend::ext_oneapi_hip:
8277
return "hip";
8378
case backend::ext_oneapi_native_cpu:

‎sycl/include/sycl/detail/pi.h

Lines changed: 2 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -278,7 +278,8 @@ typedef enum {
278278
PI_EXT_PLATFORM_BACKEND_OPENCL = 2, ///< The backend is OpenCL
279279
PI_EXT_PLATFORM_BACKEND_CUDA = 3, ///< The backend is CUDA
280280
PI_EXT_PLATFORM_BACKEND_HIP = 4, ///< The backend is HIP
281-
PI_EXT_PLATFORM_BACKEND_ESIMD = 5, ///< The backend is ESIMD
281+
// Not supported anymore:
282+
// PI_EXT_PLATFORM_BACKEND_ESIMD = 5,
282283
PI_EXT_PLATFORM_BACKEND_NATIVE_CPU = 6, ///< The backend is NATIVE_CPU
283284
} _pi_platform_backend;
284285

‎sycl/include/sycl/detail/pi.hpp

Lines changed: 0 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -70,15 +70,13 @@ bool trace(TraceLevel level);
7070
#define __SYCL_OPENCL_PLUGIN_NAME "pi_opencl.dll"
7171
#define __SYCL_LEVEL_ZERO_PLUGIN_NAME "pi_level_zero.dll"
7272
#define __SYCL_CUDA_PLUGIN_NAME "pi_cuda.dll"
73-
#define __SYCL_ESIMD_EMULATOR_PLUGIN_NAME "pi_esimd_emulator.dll"
7473
#define __SYCL_HIP_PLUGIN_NAME "pi_hip.dll"
7574
#define __SYCL_UR_PLUGIN_NAME "pi_unified_runtime.dll"
7675
#define __SYCL_NATIVE_CPU_PLUGIN_NAME "pi_native_cpu.dll"
7776
#else
7877
#define __SYCL_OPENCL_PLUGIN_NAME "libpi_opencl.dll"
7978
#define __SYCL_LEVEL_ZERO_PLUGIN_NAME "libpi_level_zero.dll"
8079
#define __SYCL_CUDA_PLUGIN_NAME "libpi_cuda.dll"
81-
#define __SYCL_ESIMD_EMULATOR_PLUGIN_NAME "libpi_esimd_emulator.dll"
8280
#define __SYCL_HIP_PLUGIN_NAME "libpi_hip.dll"
8381
#define __SYCL_UR_PLUGIN_NAME "libpi_unified_runtime.dll"
8482
#define __SYCL_NATIVE_CPU_PLUGIN_NAME "libpi_native_cpu.dll"
@@ -87,15 +85,13 @@ bool trace(TraceLevel level);
8785
#define __SYCL_OPENCL_PLUGIN_NAME "libpi_opencl.so"
8886
#define __SYCL_LEVEL_ZERO_PLUGIN_NAME "libpi_level_zero.so"
8987
#define __SYCL_CUDA_PLUGIN_NAME "libpi_cuda.so"
90-
#define __SYCL_ESIMD_EMULATOR_PLUGIN_NAME "libpi_esimd_emulator.so"
9188
#define __SYCL_HIP_PLUGIN_NAME "libpi_hip.so"
9289
#define __SYCL_UR_PLUGIN_NAME "libpi_unified_runtime.so"
9390
#define __SYCL_NATIVE_CPU_PLUGIN_NAME "libpi_native_cpu.so"
9491
#elif defined(__SYCL_RT_OS_DARWIN)
9592
#define __SYCL_OPENCL_PLUGIN_NAME "libpi_opencl.dylib"
9693
#define __SYCL_LEVEL_ZERO_PLUGIN_NAME "libpi_level_zero.dylib"
9794
#define __SYCL_CUDA_PLUGIN_NAME "libpi_cuda.dylib"
98-
#define __SYCL_ESIMD_EMULATOR_PLUGIN_NAME "libpi_esimd_emulator.dylib"
9995
#define __SYCL_HIP_PLUGIN_NAME "libpi_hip.dylib"
10096
#define __SYCL_UR_PLUGIN_NAME "libpi_unified_runtime.dylib"
10197
#define __SYCL_NATIVE_CPU_PLUGIN_NAME "libpi_native_cpu.dylib"

‎sycl/pi_win_proxy_loader/pi_win_proxy_loader.cpp

Lines changed: 0 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -89,15 +89,13 @@ std::wstring getCurrentDSODir() {
8989
#define __SYCL_OPENCL_PLUGIN_NAME "pi_opencl.dll"
9090
#define __SYCL_LEVEL_ZERO_PLUGIN_NAME "pi_level_zero.dll"
9191
#define __SYCL_CUDA_PLUGIN_NAME "pi_cuda.dll"
92-
#define __SYCL_ESIMD_EMULATOR_PLUGIN_NAME "pi_esimd_emulator.dll"
9392
#define __SYCL_HIP_PLUGIN_NAME "pi_hip.dll"
9493
#define __SYCL_UNIFIED_RUNTIME_PLUGIN_NAME "pi_unified_runtime.dll"
9594
#define __SYCL_NATIVE_CPU_PLUGIN_NAME "pi_native_cpu.dll"
9695
#else // llvm-mingw
9796
#define __SYCL_OPENCL_PLUGIN_NAME "libpi_opencl.dll"
9897
#define __SYCL_LEVEL_ZERO_PLUGIN_NAME "libpi_level_zero.dll"
9998
#define __SYCL_CUDA_PLUGIN_NAME "libpi_cuda.dll"
100-
#define __SYCL_ESIMD_EMULATOR_PLUGIN_NAME "libpi_esimd_emulator.dll"
10199
#define __SYCL_HIP_PLUGIN_NAME "libpi_hip.dll"
102100
#define __SYCL_UNIFIED_RUNTIME_PLUGIN_NAME "libpi_unified_runtime.dll"
103101
#define __SYCL_NATIVE_CPU_PLUGIN_NAME "libpi_native_cpu.dll"
@@ -147,7 +145,6 @@ void preloadLibraries() {
147145
loadPlugin(__SYCL_OPENCL_PLUGIN_NAME);
148146
loadPlugin(__SYCL_LEVEL_ZERO_PLUGIN_NAME);
149147
loadPlugin(__SYCL_CUDA_PLUGIN_NAME);
150-
loadPlugin(__SYCL_ESIMD_EMULATOR_PLUGIN_NAME);
151148
loadPlugin(__SYCL_HIP_PLUGIN_NAME);
152149
loadPlugin(__SYCL_UNIFIED_RUNTIME_PLUGIN_NAME);
153150
loadPlugin(__SYCL_NATIVE_CPU_PLUGIN_NAME);

‎sycl/source/CMakeLists.txt

Lines changed: 0 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -255,7 +255,6 @@ set(SYCL_COMMON_SOURCES
255255
"sampler.cpp"
256256
"stream.cpp"
257257
"spirv_ops.cpp"
258-
"esimd_emulator_device_interface.cpp"
259258
"$<$<PLATFORM_ID:Windows>:detail/windows_pi.cpp>"
260259
"$<$<OR:$<PLATFORM_ID:Linux>,$<PLATFORM_ID:Darwin>>:detail/posix_pi.cpp>"
261260
)

‎sycl/source/backend.cpp

Lines changed: 0 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -58,8 +58,6 @@ backend convertBackend(pi_platform_backend PiBackend) {
5858
return backend::ext_oneapi_cuda;
5959
case PI_EXT_PLATFORM_BACKEND_HIP:
6060
return backend::ext_oneapi_hip;
61-
case PI_EXT_PLATFORM_BACKEND_ESIMD:
62-
return backend::ext_intel_esimd_emulator;
6361
case PI_EXT_PLATFORM_BACKEND_NATIVE_CPU:
6462
return backend::ext_oneapi_native_cpu;
6563
}

‎sycl/source/detail/config.cpp

Lines changed: 2 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -163,17 +163,15 @@ void dumpConfig() {
163163

164164
// Array is used by SYCL_DEVICE_FILTER and SYCL_DEVICE_ALLOWLIST and
165165
// ONEAPI_DEVICE_SELECTOR
166-
// TODO: Remove esimd_emulator in the next ABI breaking window.
167166
// TODO: host device type will be removed once sycl_ext_oneapi_filter_selector
168167
// is removed.
169-
const std::array<std::pair<std::string, backend>, 8> &getSyclBeMap() {
170-
static const std::array<std::pair<std::string, backend>, 8> SyclBeMap = {
168+
const std::array<std::pair<std::string, backend>, 7> &getSyclBeMap() {
169+
static const std::array<std::pair<std::string, backend>, 7> SyclBeMap = {
171170
{{"host", backend::host},
172171
{"opencl", backend::opencl},
173172
{"level_zero", backend::ext_oneapi_level_zero},
174173
{"cuda", backend::ext_oneapi_cuda},
175174
{"hip", backend::ext_oneapi_hip},
176-
{"esimd_emulator", backend::ext_intel_esimd_emulator},
177175
{"native_cpu", backend::ext_oneapi_native_cpu},
178176
{"*", backend::all}}};
179177
return SyclBeMap;

‎sycl/source/detail/config.hpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -251,7 +251,7 @@ getSyclDeviceTypeMap() {
251251

252252
// Array is used by SYCL_DEVICE_FILTER and SYCL_DEVICE_ALLOWLIST and
253253
// ONEAPI_DEVICE_SELECTOR
254-
const std::array<std::pair<std::string, backend>, 8> &getSyclBeMap();
254+
const std::array<std::pair<std::string, backend>, 7> &getSyclBeMap();
255255

256256
// ---------------------------------------
257257
// ONEAPI_DEVICE_SELECTOR support

‎sycl/source/detail/device_impl.cpp

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -363,7 +363,7 @@ bool device_impl::has(aspect Aspect) const {
363363
return is_accelerator();
364364
case aspect::custom:
365365
return false;
366-
// TODO: Implement this for FPGA and ESIMD emulators.
366+
// TODO: Implement this for FPGA emulator.
367367
case aspect::emulated:
368368
return false;
369369
case aspect::host_debuggable:

‎sycl/source/detail/pi.cpp

Lines changed: 0 additions & 5 deletions
Original file line numberDiff line numberDiff line change
@@ -68,9 +68,6 @@ template <sycl::backend BE> void *getPluginOpaqueData(void *OpaqueDataParam) {
6868
return ReturnOpaqueData;
6969
}
7070

71-
template __SYCL_EXPORT void *
72-
getPluginOpaqueData<sycl::backend::ext_intel_esimd_emulator>(void *);
73-
7471
namespace pi {
7572

7673
static void initializePlugins(std::vector<PluginPtr> &Plugins);
@@ -510,8 +507,6 @@ template <backend BE> const PluginPtr &getPlugin() {
510507
template __SYCL_EXPORT const PluginPtr &getPlugin<backend::opencl>();
511508
template __SYCL_EXPORT const PluginPtr &
512509
getPlugin<backend::ext_oneapi_level_zero>();
513-
template __SYCL_EXPORT const PluginPtr &
514-
getPlugin<backend::ext_intel_esimd_emulator>();
515510
template __SYCL_EXPORT const PluginPtr &getPlugin<backend::ext_oneapi_cuda>();
516511
template __SYCL_EXPORT const PluginPtr &getPlugin<backend::ext_oneapi_hip>();
517512

‎sycl/source/detail/scheduler/commands.cpp

Lines changed: 3 additions & 16 deletions
Original file line numberDiff line numberDiff line change
@@ -2976,8 +2976,7 @@ pi_int32 ExecCGCommand::enqueueImpQueue() {
29762976
NDRDescT &NDRDesc = ExecKernel->MNDRDesc;
29772977
std::vector<ArgDesc> &Args = ExecKernel->MArgs;
29782978

2979-
if (MQueue->is_host() || (MQueue->getDeviceImplPtr()->getBackend() ==
2980-
backend::ext_intel_esimd_emulator)) {
2979+
if (MQueue->is_host()) {
29812980
for (ArgDesc &Arg : Args)
29822981
if (kernel_param_kind_t::kind_accessor == Arg.MType) {
29832982
Requirement *Req = (Requirement *)(Arg.MPtr);
@@ -2990,20 +2989,8 @@ pi_int32 ExecCGCommand::enqueueImpQueue() {
29902989
Plugin->call<PiApiKind::piEventsWait>(RawEvents.size(), &RawEvents[0]);
29912990
}
29922991

2993-
if (MQueue->is_host()) {
2994-
ExecKernel->MHostKernel->call(NDRDesc,
2995-
getEvent()->getHostProfilingInfo());
2996-
} else {
2997-
assert(MQueue->getDeviceImplPtr()->getBackend() ==
2998-
backend::ext_intel_esimd_emulator);
2999-
if (MEvent != nullptr)
3000-
MEvent->setHostEnqueueTime();
3001-
MQueue->getPlugin()->call<PiApiKind::piEnqueueKernelLaunch>(
3002-
nullptr,
3003-
reinterpret_cast<pi_kernel>(ExecKernel->MHostKernel->getPtr()),
3004-
NDRDesc.Dims, &NDRDesc.GlobalOffset[0], &NDRDesc.GlobalSize[0],
3005-
&NDRDesc.LocalSize[0], 0, nullptr, nullptr);
3006-
}
2992+
ExecKernel->MHostKernel->call(NDRDesc,
2993+
getEvent()->getHostProfilingInfo());
30072994
return PI_SUCCESS;
30082995
}
30092996

‎sycl/source/device_selector.cpp

Lines changed: 0 additions & 11 deletions
Original file line numberDiff line numberDiff line change
@@ -179,13 +179,6 @@ __SYCL_EXPORT int default_selector_v(const device &dev) {
179179
// The default selector doesn't reject any devices.
180180
int Score = 0;
181181

182-
// we give the esimd_emulator device a score of zero to prevent it from being
183-
// chosen among other devices. The same thing is done for gpu_selector_v
184-
// below.
185-
if (dev.get_backend() == backend::ext_intel_esimd_emulator) {
186-
return 0;
187-
}
188-
189182
traceDeviceSelector("info::device_type::automatic");
190183

191184
if (dev.is_gpu())
@@ -209,10 +202,6 @@ __SYCL_EXPORT int default_selector_v(const device &dev) {
209202
__SYCL_EXPORT int gpu_selector_v(const device &dev) {
210203
int Score = detail::REJECT_DEVICE_SCORE;
211204

212-
if (dev.get_backend() == backend::ext_intel_esimd_emulator) {
213-
return 0;
214-
}
215-
216205
traceDeviceSelector("info::device_type::gpu");
217206
if (dev.is_gpu()) {
218207
Score = 1000;

‎sycl/source/esimd_emulator_device_interface.cpp

Lines changed: 0 additions & 38 deletions
This file was deleted.

‎sycl/source/handler.cpp

Lines changed: 4 additions & 34 deletions
Original file line numberDiff line numberDiff line change
@@ -276,40 +276,10 @@ event handler::finalize() {
276276
: nullptr);
277277
Result = PI_SUCCESS;
278278
} else {
279-
if (MQueue->getDeviceImplPtr()->getBackend() ==
280-
backend::ext_intel_esimd_emulator) {
281-
// Capture the host timestamp for profiling (queue time)
282-
if (NewEvent != nullptr)
283-
NewEvent->setHostEnqueueTime();
284-
[&](auto... Args) {
285-
if (MImpl->MKernelIsCooperative) {
286-
MQueue->getPlugin()
287-
->call<
288-
detail::PiApiKind::piextEnqueueCooperativeKernelLaunch>(
289-
Args...);
290-
} else {
291-
MQueue->getPlugin()
292-
->call<detail::PiApiKind::piEnqueueKernelLaunch>(Args...);
293-
}
294-
}(/* queue */
295-
nullptr,
296-
/* kernel */
297-
reinterpret_cast<pi_kernel>(MHostKernel->getPtr()),
298-
/* work_dim */
299-
MNDRDesc.Dims,
300-
/* global_work_offset */ &MNDRDesc.GlobalOffset[0],
301-
/* global_work_size */ &MNDRDesc.GlobalSize[0],
302-
/* local_work_size */ &MNDRDesc.LocalSize[0],
303-
/* num_events_in_wait_list */ 0,
304-
/* event_wait_list */ nullptr,
305-
/* event */ nullptr);
306-
Result = PI_SUCCESS;
307-
} else {
308-
Result = enqueueImpKernel(
309-
MQueue, MNDRDesc, MArgs, KernelBundleImpPtr, MKernel,
310-
MKernelName.c_str(), RawEvents, NewEvent, nullptr,
311-
MImpl->MKernelCacheConfig, MImpl->MKernelIsCooperative);
312-
}
279+
Result = enqueueImpKernel(
280+
MQueue, MNDRDesc, MArgs, KernelBundleImpPtr, MKernel,
281+
MKernelName.c_str(), RawEvents, NewEvent, nullptr,
282+
MImpl->MKernelCacheConfig, MImpl->MKernelIsCooperative);
313283
}
314284
#ifdef XPTI_ENABLE_INSTRUMENTATION
315285
// Emit signal only when event is created

‎sycl/source/kernel_bundle.cpp

Lines changed: 0 additions & 5 deletions
Original file line numberDiff line numberDiff line change
@@ -312,11 +312,6 @@ bool is_compatible(const std::vector<kernel_id> &KernelIDs, const device &Dev) {
312312
const detail::RTDeviceBinaryImage &Img) {
313313
const char *Target = Img.getRawData().DeviceTargetSpec;
314314
auto BE = Dev.get_backend();
315-
// ESIMD emulator backend is only compatible with esimd kernels.
316-
if (BE == sycl::backend::ext_intel_esimd_emulator) {
317-
pi_device_binary_property Prop = Img.getProperty("isEsimdImage");
318-
return (Prop && (detail::DeviceBinaryProperty(Prop).asUint32() != 0));
319-
}
320315
if (strcmp(Target, __SYCL_PI_DEVICE_BINARY_TARGET_SPIRV64) == 0) {
321316
return (BE == sycl::backend::opencl ||
322317
BE == sycl::backend::ext_oneapi_level_zero);

‎sycl/test/abi/sycl_symbols_linux.dump

Lines changed: 0 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -3353,7 +3353,6 @@ _ZN4sycl3_V16detail18stringifyErrorCodeEi
33533353
_ZN4sycl3_V16detail19convertChannelOrderE23_pi_image_channel_order
33543354
_ZN4sycl3_V16detail19convertChannelOrderENS0_19image_channel_orderE
33553355
_ZN4sycl3_V16detail19getImageElementSizeEhNS0_18image_channel_typeE
3356-
_ZN4sycl3_V16detail19getPluginOpaqueDataILNS0_7backendE5EEEPvS4_
33573356
_ZN4sycl3_V16detail19kernel_bundle_plain21ext_oneapi_get_kernelERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE
33583357
_ZN4sycl3_V16detail19kernel_bundle_plain21ext_oneapi_has_kernelERKNSt7__cxx1112basic_stringIcSt11char_traitsIcESaIcEEE
33593358
_ZN4sycl3_V16detail19kernel_bundle_plain32set_specialization_constant_implEPKcPvm
@@ -3378,7 +3377,6 @@ _ZN4sycl3_V16detail22has_kernel_bundle_implERKNS0_7contextERKSt6vectorINS0_6devi
33783377
_ZN4sycl3_V16detail22reduGetPreferredWGSizeERSt10shared_ptrINS1_10queue_implEEm
33793378
_ZN4sycl3_V16detail22removeDuplicateDevicesERKSt6vectorINS0_6deviceESaIS3_EE
33803379
_ZN4sycl3_V16detail23constructorNotificationEPvS2_NS0_6access6targetENS3_4modeERKNS1_13code_locationE
3381-
_ZN4sycl3_V16detail23getESIMDDeviceInterfaceEv
33823380
_ZN4sycl3_V16detail24find_device_intersectionERKSt6vectorINS0_13kernel_bundleILNS0_12bundle_stateE1EEESaIS5_EE
33833381
_ZN4sycl3_V16detail26isDeviceGlobalUsedInKernelEPKv
33843382
_ZN4sycl3_V16detail27getPixelCoordLinearFiltModeENS0_3vecIfLi4EEENS0_15addressing_modeENS0_5rangeILi3EEERS3_
@@ -3394,7 +3392,6 @@ _ZN4sycl3_V16detail2pi9assertionEbPKc
33943392
_ZN4sycl3_V16detail2pi9getPluginILNS0_7backendE1EEERKSt10shared_ptrINS1_6pluginEEv
33953393
_ZN4sycl3_V16detail2pi9getPluginILNS0_7backendE2EEERKSt10shared_ptrINS1_6pluginEEv
33963394
_ZN4sycl3_V16detail2pi9getPluginILNS0_7backendE3EEERKSt10shared_ptrINS1_6pluginEEv
3397-
_ZN4sycl3_V16detail2pi9getPluginILNS0_7backendE5EEERKSt10shared_ptrINS1_6pluginEEv
33983395
_ZN4sycl3_V16detail2pi9getPluginILNS0_7backendE6EEERKSt10shared_ptrINS1_6pluginEEv
33993396
_ZN4sycl3_V16detail30UnsampledImageAccessorBaseHost10getAccDataEv
34003397
_ZN4sycl3_V16detail30UnsampledImageAccessorBaseHost6getPtrEv

0 commit comments

Comments
 (0)