Skip to content
New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Jump to bottom

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

Open
sarnex opened this issue Sep 3, 2024 · 1 comment
Open

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

sarnex opened this issue Sep 3, 2024 · 1 comment
Labels
bug Something isn't working confirmed

Comments

@sarnex
Copy link
Contributor

sarnex commented Sep 3, 2024 •
edited
Loading

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 sarnex added bug Something isn't working confirmed labels Sep 3, 2024
@sarnex sarnex mentioned this issue Sep 3, 2024
Merged
@sarnex sarnex changed the title Tests disabled in 24.31.30508.7 driver uplift syclcompat/launch/launch_policy_lmem.cpp failing in 24.31.30508.7 driver uplift Sep 4, 2024
sarnex added a commit that referenced this issue Sep 4, 2024
@sarnex
[SYCL][E2E] XFAIL launch_policy_lmem.cpp (#15276)
a9aa8cb 
Failing in new driver, see #15275.

It will XPASS in this PR, but once this is merged I will immediately
merge the driver update PR.

---------

Signed-off-by: Sarnie, Nick <nick.sarnie@intel.com>
@sarnex
Copy link
Contributor Author

sarnex commented Sep 6, 2024

This is XPASSing in the nightly somehow

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

Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment
Assignees
No one assigned
Labels
bug Something isn't working confirmed
Projects
None yet
Milestone
No milestone
Development

No branches or pull requests
1 participant
@sarnex