search

intel / llvm

Intel staging area for llvm.org contribution. Home for Intel LLVM-based projects.
Other
1.26k stars 738 forks source link

syclcompat/launch/launch_policy_lmem.cpp failing in 24.31.30508.7 driver uplift #15275

Open sarnex opened 2 months ago

sarnex commented 2 months ago

Describe the bug

Same failures on Linux DG2.

https://github.com/intel/llvm/actions/runs/10675865498/job/29588794136?pr=15260

********************
Failed Tests (2):
  SYCL :: syclcompat/launch/launch_policy_lmem.cpp

********************
FAIL: SYCL :: syclcompat/launch/launch_policy_lmem.cpp (2218 of 2221)
******************** TEST 'SYCL :: syclcompat/launch/launch_policy_lmem.cpp' FAILED ********************
Exit Code: -6

Command Output (stdout):
--
# RUN: at line 23
/__w/llvm/llvm/toolchain/bin//clang++  -Werror  -Wno-error=#warnings -Wno-error=deprecated-declarations -fsycl -fsycl-targets=spir64  /__w/llvm/llvm/llvm/sycl/test-e2e/syclcompat/launch/launch_policy_lmem.cpp -fsycl-device-code-split=per_kernel -o /__w/llvm/llvm/build-e2e/syclcompat/launch/Output/launch_policy_lmem.cpp.tmp.out
# executed command: /__w/llvm/llvm/toolchain/bin//clang++ -Werror '-Wno-error=#warnings' -Wno-error=deprecated-declarations -fsycl -fsycl-targets=spir64 /__w/llvm/llvm/llvm/sycl/test-e2e/syclcompat/launch/launch_policy_lmem.cpp -fsycl-device-code-split=per_kernel -o /__w/llvm/llvm/build-e2e/syclcompat/launch/Output/launch_policy_lmem.cpp.tmp.out
# .---command stderr------------
# | In file included from /__w/llvm/llvm/llvm/sycl/test-e2e/syclcompat/launch/launch_policy_lmem.cpp:30:
# | In file included from /__w/llvm/llvm/toolchain/bin/../include/syclcompat/launch.hpp:32:
# | /__w/llvm/llvm/toolchain/bin/../include/syclcompat/device.hpp:421:2: warning: "Querying the number of bytes of free memory is not supported" [-W#warnings]
# |   421 | #warning "Querying the number of bytes of free memory is not supported"
# |       |  ^
# | 1 warning generated.
# | In file included from /__w/llvm/llvm/llvm/sycl/test-e2e/syclcompat/launch/launch_policy_lmem.cpp:30:
# | In file included from /__w/llvm/llvm/toolchain/bin/../include/syclcompat/launch.hpp:32:
# | /__w/llvm/llvm/toolchain/bin/../include/syclcompat/device.hpp:421:2: warning: "Querying the number of bytes of free memory is not supported" [-W#warnings]
# |   421 | #warning "Querying the number of bytes of free memory is not supported"
# |       |  ^
# | 1 warning generated.
# `-----------------------------
# RUN: at line 24
env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  /__w/llvm/llvm/build-e2e/syclcompat/launch/Output/launch_policy_lmem.cpp.tmp.out
# executed command: env ONEAPI_DEVICE_SELECTOR=level_zero:gpu /__w/llvm/llvm/build-e2e/syclcompat/launch/Output/launch_policy_lmem.cpp.tmp.out
# .---command stdout------------
# | void test_dynamic_mem_no_arg_launch()
# | void test_dynamic_mem_no_arg_launch_q()
# | void test_basic_dt_launch() [T = int]
# | void test_basic_dt_launch() [T = unsigned int]
# | void test_basic_dt_launch() [T = short]
# | void test_basic_dt_launch() [T = unsigned short]
# | void test_basic_dt_launch() [T = long]
# | void test_basic_dt_launch() [T = unsigned long]
# | void test_basic_dt_launch() [T = long long]
# | void test_basic_dt_launch() [T = unsigned long long]
# | void test_basic_dt_launch() [T = float]
# | void test_basic_dt_launch() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_basic_dt_launch() [T = sycl::detail::half_impl::half]
# | void test_basic_dt_launch_q() [T = int]
# | void test_basic_dt_launch_q() [T = unsigned int]
# | void test_basic_dt_launch_q() [T = short]
# | void test_basic_dt_launch_q() [T = unsigned short]
# | void test_basic_dt_launch_q() [T = long]
# | void test_basic_dt_launch_q() [T = unsigned long]
# | void test_basic_dt_launch_q() [T = long long]
# | void test_basic_dt_launch_q() [T = unsigned long long]
# | void test_basic_dt_launch_q() [T = float]
# | void test_basic_dt_launch_q() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_basic_dt_launch_q() [T = sycl::detail::half_impl::half]
# | void test_arg_launch() [T = int]
# | void test_arg_launch() [T = unsigned int]
# | void test_arg_launch() [T = short]
# | void test_arg_launch() [T = unsigned short]
# | void test_arg_launch() [T = long]
# | void test_arg_launch() [T = unsigned long]
# | void test_arg_launch() [T = long long]
# | void test_arg_launch() [T = unsigned long long]
# | void test_arg_launch() [T = float]
# | void test_arg_launch() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_arg_launch() [T = sycl::detail::half_impl::half]
# | void test_arg_launch_q() [T = int]
# | void test_arg_launch_q() [T = unsigned int]
# | void test_arg_launch_q() [T = short]
# | void test_arg_launch_q() [T = unsigned short]
# | void test_arg_launch_q() [T = long]
# | void test_arg_launch_q() [T = unsigned long]
# | void test_arg_launch_q() [T = long long]
# | void test_arg_launch_q() [T = unsigned long long]
# | void test_arg_launch_q() [T = float]
# | void test_arg_launch_q() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_arg_launch_q() [T = sycl::detail::half_impl::half]
# | void test_local_mem_usage() [T = int]
# | void test_local_mem_usage() [T = unsigned int]
# | void test_local_mem_usage() [T = short]
# | void test_local_mem_usage() [T = unsigned short]
# | void test_local_mem_usage() [T = long]
# | void test_local_mem_usage() [T = unsigned long]
# | void test_local_mem_usage() [T = long long]
# | void test_local_mem_usage() [T = unsigned long long]
# | void test_local_mem_usage() [T = float]
# | void test_local_mem_usage() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_local_mem_usage() [T = sycl::detail::half_impl::half]
# | void test_local_mem_usage_q() [T = int]
# | void test_local_mem_usage_q() [T = unsigned int]
# | void test_local_mem_usage_q() [T = short]
# | void test_local_mem_usage_q() [T = unsigned short]
# | void test_local_mem_usage_q() [T = long]
# | void test_local_mem_usage_q() [T = unsigned long]
# | void test_local_mem_usage_q() [T = long long]
# | void test_local_mem_usage_q() [T = unsigned long long]
# | void test_local_mem_usage_q() [T = float]
# | void test_local_mem_usage_q() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_local_mem_usage_q() [T = sycl::detail::half_impl::half]
# | void test_memsize_no_arg_launch() [T = int]
# | void test_memsize_no_arg_launch() [T = unsigned int]
# | void test_memsize_no_arg_launch() [T = short]
# | void test_memsize_no_arg_launch() [T = unsigned short]
# | void test_memsize_no_arg_launch() [T = long]
# | void test_memsize_no_arg_launch() [T = unsigned long]
# | void test_memsize_no_arg_launch_q() [T = int]
# | void test_memsize_no_arg_launch_q() [T = unsigned int]
# | void test_memsize_no_arg_launch_q() [T = short]
# | void test_memsize_no_arg_launch_q() [T = unsigned short]
# | void test_memsize_no_arg_launch_q() [T = long]
# | void test_memsize_no_arg_launch_q() [T = unsigned long]
# `-----------------------------
# .---command stderr------------
# | ZE_LOADER_DEBUG_TRACE:Using Loader Library Path: 
# | ZE_LOADER_DEBUG_TRACE:Tracing Layer Library Path: libze_tracing_layer.so.1
# `-----------------------------
# RUN: at line 24
env ONEAPI_DEVICE_SELECTOR=opencl:gpu  /__w/llvm/llvm/build-e2e/syclcompat/launch/Output/launch_policy_lmem.cpp.tmp.out
# executed command: env ONEAPI_DEVICE_SELECTOR=opencl:gpu /__w/llvm/llvm/build-e2e/syclcompat/launch/Output/launch_policy_lmem.cpp.tmp.out
# .---command stdout------------
# | void test_dynamic_mem_no_arg_launch()
# | void test_dynamic_mem_no_arg_launch_q()
# | void test_basic_dt_launch() [T = int]
# | void test_basic_dt_launch() [T = unsigned int]
# | void test_basic_dt_launch() [T = short]
# | void test_basic_dt_launch() [T = unsigned short]
# | void test_basic_dt_launch() [T = long]
# | void test_basic_dt_launch() [T = unsigned long]
# | void test_basic_dt_launch() [T = long long]
# | void test_basic_dt_launch() [T = unsigned long long]
# | void test_basic_dt_launch() [T = float]
# | void test_basic_dt_launch() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_basic_dt_launch() [T = sycl::detail::half_impl::half]
# | void test_basic_dt_launch_q() [T = int]
# | void test_basic_dt_launch_q() [T = unsigned int]
# | void test_basic_dt_launch_q() [T = short]
# | void test_basic_dt_launch_q() [T = unsigned short]
# | void test_basic_dt_launch_q() [T = long]
# | void test_basic_dt_launch_q() [T = unsigned long]
# | void test_basic_dt_launch_q() [T = long long]
# | void test_basic_dt_launch_q() [T = unsigned long long]
# | void test_basic_dt_launch_q() [T = float]
# | void test_basic_dt_launch_q() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_basic_dt_launch_q() [T = sycl::detail::half_impl::half]
# | void test_arg_launch() [T = int]
# | void test_arg_launch() [T = unsigned int]
# | void test_arg_launch() [T = short]
# | void test_arg_launch() [T = unsigned short]
# | void test_arg_launch() [T = long]
# | void test_arg_launch() [T = unsigned long]
# | void test_arg_launch() [T = long long]
# | void test_arg_launch() [T = unsigned long long]
# | void test_arg_launch() [T = float]
# | void test_arg_launch() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_arg_launch() [T = sycl::detail::half_impl::half]
# | void test_arg_launch_q() [T = int]
# | void test_arg_launch_q() [T = unsigned int]
# | void test_arg_launch_q() [T = short]
# | void test_arg_launch_q() [T = unsigned short]
# | void test_arg_launch_q() [T = long]
# | void test_arg_launch_q() [T = unsigned long]
# | void test_arg_launch_q() [T = long long]
# | void test_arg_launch_q() [T = unsigned long long]
# | void test_arg_launch_q() [T = float]
# | void test_arg_launch_q() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_arg_launch_q() [T = sycl::detail::half_impl::half]
# | void test_local_mem_usage() [T = int]
# | void test_local_mem_usage() [T = unsigned int]
# | void test_local_mem_usage() [T = short]
# | void test_local_mem_usage() [T = unsigned short]
# | void test_local_mem_usage() [T = long]
# | void test_local_mem_usage() [T = unsigned long]
# | void test_local_mem_usage() [T = long long]
# | void test_local_mem_usage() [T = unsigned long long]
# | void test_local_mem_usage() [T = float]
# | void test_local_mem_usage() [T = double]
# |   sycl::aspect::fp64 not supported by the SYCL device.
# | void test_local_mem_usage() [T = sycl::detail::half_impl::half]
# | void test_local_mem_usage_q() [T = int]
# `-----------------------------
# .---command stderr------------
# | ZE_LOADER_DEBUG_TRACE:Using Loader Library Path: 
# | ZE_LOADER_DEBUG_TRACE:Tracing Layer Library Path: libze_tracing_layer.so.1
# | terminate called after throwing an instance of 'sycl::_V1::exception'
# |   what():  Native API failed. Native API returns: 40 (UR_RESULT_ERROR_OUT_OF_RESOURCES)
# `-----------------------------
# error: command failed with exit status: -6

--

********************

To reproduce

No response

Environment

No response

Additional context

No response

sarnex commented 2 months ago

This is XPASSing in the nightly somehow

https://github.com/intel/llvm/actions/runs/10731711170/job/29762580737