[v7.0.0] Assertion `NDR.LocalSize[0] == 0' failed on Pytorch built with dpclang v7.0.0

[dvrogozh]

Describe the bug

Some Pytorch tests are crashing on the following assertion fired from SYCL runtime:

• https://github.com/intel/llvm/blob/v7.0.0/sycl/source/detail/scheduler/commands.cpp#L2225

sycl/source/detail/scheduler/commands.cpp:2225: void sycl::_V1::detail::adjustNDRangePerKernel(NDRDescT&, ur_kernel_handle_t, const device_impl&): Assertion `NDR.LocalSize[0] == 0' failed.

To reproduce

Below assumes that dpclang is installed and configured. For example:

export CMAKE_PREFIX_PATH=~/git/intel-llvm/build/install/
export PKG_CONFIG_PATH=$HOME/git/intel-llvm/build/install/lib/pkgconfig:$PKG_CONFIG_PATH
export LD_LIBRARY_PATH=$HOME/git/intel-llvm/build/install/lib:$LD_LIBRARY_PATH
export PATH=$HOME/git/intel-llvm/build/install/bin:$PATH

Using pre-built pytorch wheels:

1. Work in python 3.10 virtual environment:

uv venv --python 3.10
uv pip install pytest expecttest numpy
source .venv/bin/activate

2. Fetch pytorch sources:

git clone https://github.com/pytorch/pytorch.git && cd pytorch
git reset --hard 240f31ace12a3bbbb34d10666780e1c365cfbb6e
cd third_party
git clone https://github.com/intel/torch-xpu-ops.git && cd torch-xpu-ops
git reset --hard $(cat ../xpu.txt)

3. Install pytorch pre-built with dpclang v7.0.0 by CI job (download and install Torch-XPU-Wheel-4789-31020166365-1-dpclang archive)

uv pip install torch-2.14.0a0+git99731ed-cp310-cp310-linux_x86_64.whl

5. Run the following to reproduce the issue:

$ pytest -rsf third_party/torch-xpu-ops/test/xpu/extended/test_ops_xpu.py::TestCompositeComplianceXPU::test_view_replay_histogram_xpu_float32
=========================================================== test session starts ============================================================
platform linux -- Python 3.12.3, pytest-9.1.1, pluggy-1.6.0
rootdir: /home/dvrogozh/git/pytorch/pytorch
configfile: pytest.ini
plugins: hypothesis-6.165.0
collected 1 item

third_party/torch-xpu-ops/test/xpu/extended/test_ops_xpu.py python3: /home/dvrogozh/git/intel-llvm/sycl/source/detail/scheduler/commands.cpp:2225: void sycl::_V1::detail::adjustNDRangePerKernel(NDRDescT&, ur_kernel_handle_t, const device_impl&): Assertion `NDR.LocalSize[0] == 0' failed.
Fatal Python error: Aborted

Current thread 0x00007d5fe6948140 (most recent call first):
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/opinfo/core.py", line 1263 in __call__
  File "/home/dvrogozh/git/pytorch/pytorch/third_party/torch-xpu-ops/test/xpu/../../../../test/test_ops.py", line 2232 in test_view_replay
  File "/home/dvrogozh/git/pytorch/pytorch/third_party/torch-xpu-ops/test/xpu/extended/test_ops_xpu.py", line 283 in test_view_replay
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/common_device_type.py", line 1450 in test_wrapper
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/common_utils.py", line 2127 in wrapper
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/common_device_type.py", line 627 in instantiated_test
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/common_utils.py", line 3794 in wrapper
  File "/usr/lib/python3.12/unittest/case.py", line 589 in _callTestMethod
  File "/usr/lib/python3.12/unittest/case.py", line 634 in run
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/common_utils.py", line 3953 in _run_custom
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/common_utils.py", line 3986 in run
  File "/home/dvrogozh/git/pytorch/pytorch/torch/testing/_internal/common_device_type.py", line 730 in run
  File "/usr/lib/python3.12/unittest/case.py", line 690 in __call__
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/unittest.py", line 410 in runtest
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/runner.py", line 184 in pytest_runtest_call
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_callers.py", line 121 in _multicall
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_manager.py", line 120 in _hookexec
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_hooks.py", line 512 in __call__
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/runner.py", line 250 in <lambda>
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/runner.py", line 361 in from_call
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/runner.py", line 249 in call_and_report
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/runner.py", line 139 in runtestprotocol
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/runner.py", line 118 in pytest_runtest_protocol
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_callers.py", line 121 in _multicall
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_manager.py", line 120 in _hookexec
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_hooks.py", line 512 in __call__
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/main.py", line 408 in pytest_runtestloop
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_callers.py", line 121 in _multicall
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_manager.py", line 120 in _hookexec
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_hooks.py", line 512 in __call__
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/main.py", line 384 in _main
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/main.py", line 330 in wrap_session
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/main.py", line 377 in pytest_cmdline_main
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_callers.py", line 121 in _multicall
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_manager.py", line 120 in _hookexec
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/pluggy/_hooks.py", line 512 in __call__
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/config/__init__.py", line 229 in _main
  File "/home/dvrogozh/pytorch.xpu.llvm/lib/python3.12/site-packages/_pytest/config/__init__.py", line 253 in _console_main
  File "/home/dvrogozh/pytorch.xpu.llvm/bin/pytest", line 8 in <module>

Extension modules: numpy._core._multiarray_umath, numpy.linalg._umath_linalg, torch._C, torch._C._dynamo.autograd_compiler, torch._C._dynamo.eval_frame, torch._C._dynamo.guards, torch._C._dynamo.utils, torch._C._fft, torch._C._linalg, torch._C._nested, torch._C._nn, torch._C._sparse, torch._C._special, numpy.random._common, numpy.random.bit_generator, numpy.random._bounded_integers, numpy.random._pcg64, numpy.random._generator, numpy.random._mt19937, numpy.random._philox, numpy.random._sfc64, numpy.random.mtrand, psutil._psutil_linux, markupsafe._speedups (total: 24)
Aborted (core dumped)

Alternatively, build pytorch from sources:

cd pytorch
git submodule update --init --recursive
pip install -r requirements.txt
XPU_SYCL_COMPILER=dpclang TORCH_XPU_ARCH_LIST=pvc USE_KINETO=0 USE_ONEMKL_XPU=0 python -m pip install --no-build-isolation -v -e .

Environment

• OS: Linux
• Target device and vendor: Pytorch CI was running on PVC, other devices not tried
• DPC++ version: https://github.com/intel/llvm/releases/tag/v7.0.0
• Dependencies version:

$ sycl-ls --verbose
<LOADER>[INFO]: failed to load adapter 'libur_adapter_cuda.so.0' with error: libur_adapter_cuda.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: failed to load adapter '/home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_cuda.so.0' with error: /home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_cuda.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: failed to load adapter 'libur_adapter_hip.so.0' with error: libur_adapter_hip.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: failed to load adapter '/home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_hip.so.0' with error: /home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_hip.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: loaded adapter 0x0x608a6aae5210 (libur_adapter_level_zero.so.0) from /home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_level_zero.so.0
<LOADER>[INFO]: loaded adapter 0x0x608a6aae82f0 (libur_adapter_level_zero_v2.so.0) from /home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_level_zero_v2.so.0
<LOADER>[INFO]: failed to load adapter 'libur_adapter_native_cpu.so.0' with error: libur_adapter_native_cpu.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: failed to load adapter '/home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_native_cpu.so.0' with error: /home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_native_cpu.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: failed to load adapter 'libur_adapter_offload.so.0' with error: libur_adapter_offload.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: failed to load adapter '/home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_offload.so.0' with error: /home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_offload.so.0: cannot open shared object file: No such file or directory
<LOADER>[INFO]: loaded adapter 0x0x608a6aaeb6c0 (libur_adapter_opencl.so.0) from /home/dvrogozh/git/intel-llvm/build/install/lib/libur_adapter_opencl.so.0
[level_zero:gpu][level_zero:0] Intel(R) oneAPI Unified Runtime over Level-Zero, Intel(R) Data Center GPU Max 1550 12.60.7 [1.6.33578+42]
[level_zero:gpu][level_zero:1] Intel(R) oneAPI Unified Runtime over Level-Zero, Intel(R) Data Center GPU Max 1550 12.60.7 [1.6.33578+42]
[level_zero:gpu][level_zero:2] Intel(R) oneAPI Unified Runtime over Level-Zero, Intel(R) Data Center GPU Max 1550 12.60.7 [1.6.33578+42]
[level_zero:gpu][level_zero:3] Intel(R) oneAPI Unified Runtime over Level-Zero, Intel(R) Data Center GPU Max 1550 12.60.7 [1.6.33578+42]
[opencl:gpu][opencl:0] Intel(R) OpenCL Graphics, Intel(R) Data Center GPU Max 1550 OpenCL 3.0 NEO  [25.18.33578]
[opencl:gpu][opencl:1] Intel(R) OpenCL Graphics, Intel(R) Data Center GPU Max 1550 OpenCL 3.0 NEO  [25.18.33578]
[opencl:gpu][opencl:2] Intel(R) OpenCL Graphics, Intel(R) Data Center GPU Max 1550 OpenCL 3.0 NEO  [25.18.33578]
[opencl:gpu][opencl:3] Intel(R) OpenCL Graphics, Intel(R) Data Center GPU Max 1550 OpenCL 3.0 NEO  [25.18.33578]

Platforms: 2
Platform [#1]:
    Version  : 1.6
    Name     : Intel(R) oneAPI Unified Runtime over Level-Zero
    Vendor   : Intel(R) Corporation
    Devices  : 4
        Device [#0]:
        Type              : gpu
        Version           : 12.60.7
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 1.6.33578+42
        UUID              : 8680d50b-2f00-0000-4d00-000000000001
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_eu_simd_width ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_native_assert ext_intel_gpu_hw_threads_per_eu ext_intel_free_memory ext_intel_device_id ext_intel_memory_clock_rate ext_intel_memory_bus_width ext_oneapi_external_memory_import ext_oneapi_external_semaphore_import ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_limited_graph ext_oneapi_private_alloca ext_oneapi_bindless_sampled_image_fetch_1d_usm ext_oneapi_bindless_sampled_image_fetch_1d ext_oneapi_bindless_sampled_image_fetch_2d_usm ext_oneapi_bindless_sampled_image_fetch_2d ext_oneapi_bindless_sampled_image_fetch_3d ext_oneapi_queue_profiling_tag ext_oneapi_virtual_mem ext_oneapi_image_array ext_oneapi_virtual_functions ext_intel_spill_memory_size ext_intel_current_clock_throttle_reasons ext_intel_power_limits ext_oneapi_async_memory_alloc ext_oneapi_exportable_device_mem ext_oneapi_ipc_memory
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
        Device [#1]:
        Type              : gpu
        Version           : 12.60.7
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 1.6.33578+42
        UUID              : 8680d50b-2f00-0000-4d00-000000000002
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_eu_simd_width ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_native_assert ext_intel_gpu_hw_threads_per_eu ext_intel_free_memory ext_intel_device_id ext_intel_memory_clock_rate ext_intel_memory_bus_width ext_oneapi_external_memory_import ext_oneapi_external_semaphore_import ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_limited_graph ext_oneapi_private_alloca ext_oneapi_bindless_sampled_image_fetch_1d_usm ext_oneapi_bindless_sampled_image_fetch_1d ext_oneapi_bindless_sampled_image_fetch_2d_usm ext_oneapi_bindless_sampled_image_fetch_2d ext_oneapi_bindless_sampled_image_fetch_3d ext_oneapi_queue_profiling_tag ext_oneapi_virtual_mem ext_oneapi_image_array ext_oneapi_virtual_functions ext_intel_spill_memory_size ext_intel_current_clock_throttle_reasons ext_intel_power_limits ext_oneapi_async_memory_alloc ext_oneapi_exportable_device_mem ext_oneapi_ipc_memory
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
        Device [#2]:
        Type              : gpu
        Version           : 12.60.7
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 1.6.33578+42
        UUID              : 8680d50b-2f00-0000-9a00-000000000001
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_eu_simd_width ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_native_assert ext_intel_gpu_hw_threads_per_eu ext_intel_free_memory ext_intel_device_id ext_intel_memory_clock_rate ext_intel_memory_bus_width ext_oneapi_external_memory_import ext_oneapi_external_semaphore_import ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_limited_graph ext_oneapi_private_alloca ext_oneapi_bindless_sampled_image_fetch_1d_usm ext_oneapi_bindless_sampled_image_fetch_1d ext_oneapi_bindless_sampled_image_fetch_2d_usm ext_oneapi_bindless_sampled_image_fetch_2d ext_oneapi_bindless_sampled_image_fetch_3d ext_oneapi_queue_profiling_tag ext_oneapi_virtual_mem ext_oneapi_image_array ext_oneapi_virtual_functions ext_intel_spill_memory_size ext_intel_current_clock_throttle_reasons ext_intel_power_limits ext_oneapi_async_memory_alloc ext_oneapi_exportable_device_mem ext_oneapi_ipc_memory
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
        Device [#3]:
        Type              : gpu
        Version           : 12.60.7
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 1.6.33578+42
        UUID              : 8680d50b-2f00-0000-9a00-000000000002
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_eu_simd_width ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_native_assert ext_intel_gpu_hw_threads_per_eu ext_intel_free_memory ext_intel_device_id ext_intel_memory_clock_rate ext_intel_memory_bus_width ext_oneapi_external_memory_import ext_oneapi_external_semaphore_import ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_limited_graph ext_oneapi_private_alloca ext_oneapi_bindless_sampled_image_fetch_1d_usm ext_oneapi_bindless_sampled_image_fetch_1d ext_oneapi_bindless_sampled_image_fetch_2d_usm ext_oneapi_bindless_sampled_image_fetch_2d ext_oneapi_bindless_sampled_image_fetch_3d ext_oneapi_queue_profiling_tag ext_oneapi_virtual_mem ext_oneapi_image_array ext_oneapi_virtual_functions ext_intel_spill_memory_size ext_intel_current_clock_throttle_reasons ext_intel_power_limits ext_oneapi_async_memory_alloc ext_oneapi_exportable_device_mem ext_oneapi_ipc_memory
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
Platform [#2]:
    Version  : OpenCL 3.0
    Name     : Intel(R) OpenCL Graphics
    Vendor   : Intel(R) Corporation
    Devices  : 4
        Device [#0]:
        Type              : gpu
        Version           : OpenCL 3.0 NEO
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 25.18.33578
        UUID              : 8680d50b-2f00-0000-4d00-000000000001
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_srgb ext_intel_gpu_hw_threads_per_eu ext_intel_device_id ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_private_alloca ext_oneapi_atomic16 ext_oneapi_virtual_functions ext_intel_device_info_node_mask
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
        Device [#1]:
        Type              : gpu
        Version           : OpenCL 3.0 NEO
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 25.18.33578
        UUID              : 8680d50b-2f00-0000-4d00-000000000002
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_srgb ext_intel_gpu_hw_threads_per_eu ext_intel_device_id ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_private_alloca ext_oneapi_atomic16 ext_oneapi_virtual_functions ext_intel_device_info_node_mask
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
        Device [#2]:
        Type              : gpu
        Version           : OpenCL 3.0 NEO
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 25.18.33578
        UUID              : 8680d50b-2f00-0000-9a00-000000000001
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_srgb ext_intel_gpu_hw_threads_per_eu ext_intel_device_id ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_private_alloca ext_oneapi_atomic16 ext_oneapi_virtual_functions ext_intel_device_info_node_mask
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
        Device [#3]:
        Type              : gpu
        Version           : OpenCL 3.0 NEO
        Name              : Intel(R) Data Center GPU Max 1550
        Vendor            : Intel(R) Corporation
        Driver            : 25.18.33578
        UUID              : 8680d50b-2f00-0000-9a00-000000000002
        DeviceID          : 3029
        Num SubDevices    : 0
        Num SubSubDevices : 0
        Aspects           : gpu fp16 fp64 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations usm_shared_allocations ext_intel_pci_address ext_intel_gpu_eu_count ext_intel_gpu_slices ext_intel_gpu_subslices_per_slice ext_intel_gpu_eu_count_per_subslice atomic64 ext_intel_device_info_uuid ext_oneapi_srgb ext_intel_gpu_hw_threads_per_eu ext_intel_device_id ext_intel_esimd ext_oneapi_fragment ext_oneapi_chunk ext_oneapi_tangle ext_intel_matrix ext_oneapi_private_alloca ext_oneapi_atomic16 ext_oneapi_virtual_functions ext_intel_device_info_node_mask
        info::device::sub_group_sizes: 16 32
        Architecture: intel_gpu_pvc
default_selector()      : gpu, Intel(R) oneAPI Unified Runtime over Level-Zero, Intel(R) Data Center GPU Max 1550 12.60.7 [1.6.33578+42]
accelerator_selector()  : No device of requested type available.
cpu_selector()          : No device of requested type available.
gpu_selector()          : gpu, Intel(R) oneAPI Unified Runtime over Level-Zero, Intel(R) Data Center GPU Max 1550 12.60.7 [1.6.33578+42]
custom_selector(gpu)    : gpu, Intel(R) oneAPI Unified Runtime over Level-Zero, Intel(R) Data Center GPU Max 1550 12.60.7 [1.6.33578+42]
custom_selector(cpu)    : No device of requested type available.
custom_selector(acc)    : No device of requested type available.
<LOADER>[INFO]: unloaded adapter 0x0x608a6aae5210
<LOADER>[INFO]: unloaded adapter 0x0x608a6aae82f0
<LOADER>[INFO]: unloaded adapter 0x0x608a6aaeb6c0
<LOADER>[INFO]: ---> urLoaderTearDown() -> UR_RESULT_SUCCESS

Additional context

This test works well and passes if pytorch is built with oneAPI 2026.0. I suspect that some patch is missing on dpclang v7.0.0 vs. DPC++ included in oneAPI.

Tracking on pytorch side as:

• ci/dpclang: some tests from basic UT suite crash torch-xpu-ops#4823

@sarnex, @KseniyaTikhomirova, @KornevNikita

[sarnex]

Can someone from the SYCL runtime team help debug this? I would try but I don't know anything about kernel execution
@sergey-semenov @KseniyaTikhomirova @againull

[dvrogozh]

@sarnex , as a blind shot, can you check if there are any source code differences around the asserted code between v7.0.0 and 2026.0 open and closed source compilers?

[sarnex]

There are going to be hundreds of differences as we support features for unreleased hardware there.

[dvrogozh]

I see. In a meanwhile I did one more experiment and commented out the assertion. And test has passed on dpclang v7.0.0 after that. Thus, this can be common issue across dpclang v7.0.0 and dpc++ 2026.0 if the later is built without assertions. Do you know if dpc++ 2026.0 is built with -DNDEBUG to shut up assertions?

[sarnex]

Yes I think the closed source compiler release binaries are built with assertions disabled