Skip to content

Tests failing on BMG Windows #17165

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
Open
sarnex opened this issue Feb 25, 2025 · 1 comment
Open

Tests failing on BMG Windows #17165

sarnex opened this issue Feb 25, 2025 · 1 comment
Labels
bug Something isn't working confirmed sycl-graph

Comments

@sarnex
Copy link
Contributor

sarnex commented Feb 25, 2025 •
edited
Loading

Describe the bug

sycl/test-e2e/Adapters/level_zero_eager_init.cpp

FAIL: SYCL :: Adapters/level_zero_eager_init.cpp (53 of 2262)
******************** TEST 'SYCL :: Adapters/level_zero_eager_init.cpp' FAILED ********************
Exit Code: 3221226505

Command Output (stdout):
--
# RUN: at line 3
D:/github/_work/llvm/llvm/install/bin/clang++.exe  -Werror -fsycl -fsycl-targets=spir64  D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Adapters\level_zero_eager_init.cpp -Wno-error=deprecated-declarations  -LD:\github\level-zero_win-sdk\lib -lze_loader  -ID:\github\level-zero_win-sdk\include -o D:\github\_work\llvm\llvm\build-e2e\Adapters\Output\level_zero_eager_init.cpp.tmp.out
# executed command: D:/github/_work/llvm/llvm/install/bin/clang++.exe -Werror -fsycl -fsycl-targets=spir64 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Adapters\level_zero_eager_init.cpp' -Wno-error=deprecated-declarations '-LD:\github\level-zero_win-sdk\lib' -lze_loader '-ID:\github\level-zero_win-sdk\include' -o 'D:\github\_work\llvm\llvm\build-e2e\Adapters\Output\level_zero_eager_init.cpp.tmp.out'
# .---command stderr------------
# | D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Adapters\level_zero_eager_init.cpp:48:20: warning: 'cl_int' is deprecated: use sycl::opencl::cl_int instead [-Wdeprecated-declarations]
# |    48 |   std::array<sycl::cl_int, array_size> A = {{1, 2, 3, 4}}, B = {{1, 2, 3, 4}},
# |       |                    ^
# | C:\github\_work\llvm\llvm\install\bin\..\include\sycl/aliases.hpp:112:5: note: 'cl_int' has been explicitly marked deprecated here
# |   112 |     __SYCL2020_DEPRECATED("use sycl::opencl::cl_int instead") = std::int32_t;
# |       |     ^
# | C:\github\_work\llvm\llvm\install\bin\..\include\sycl/detail/defines_elementary.hpp:62:40: note: expanded from macro '__SYCL2020_DEPRECATED'
# |    62 | #define __SYCL2020_DEPRECATED(message) __SYCL_DEPRECATED(message)
# |       |                                        ^
# | C:\github\_work\llvm\llvm\install\bin\..\include\sycl/detail/defines_elementary.hpp:53:38: note: expanded from macro '__SYCL_DEPRECATED'
# |    53 | #define __SYCL_DEPRECATED(message) [[deprecated(message)]]
# |       |                                      ^
# | 1 warning generated.
# | D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Adapters\level_zero_eager_init.cpp:48:20: warning: 'cl_int' is deprecated: use sycl::opencl::cl_int instead [-Wdeprecated-declarations]
# |    48 |   std::array<sycl::cl_int, array_size> A = {{1, 2, 3, 4}}, B = {{1, 2, 3, 4}},
# |       |                    ^
# | C:\github\_work\llvm\llvm\install\bin\..\include\sycl/aliases.hpp:112:5: note: 'cl_int' has been explicitly marked deprecated here
# |   112 |     __SYCL2020_DEPRECATED("use sycl::opencl::cl_int instead") = std::int32_t;
# |       |     ^
# | C:\github\_work\llvm\llvm\install\bin\..\include\sycl/detail/defines_elementary.hpp:62:40: note: expanded from macro '__SYCL2020_DEPRECATED'
# |    62 | #define __SYCL2020_DEPRECATED(message) __SYCL_DEPRECATED(message)
# |       |                                        ^
# | C:\github\_work\llvm\llvm\install\bin\..\include\sycl/detail/defines_elementary.hpp:53:38: note: expanded from macro '__SYCL_DEPRECATED'
# |    53 | #define __SYCL_DEPRECATED(message) [[deprecated(message)]]
# |       |                                      ^
# | 1 warning generated.
# `-----------------------------
# RUN: at line 4
env UR_L0_DEBUG=1 SYCL_EAGER_INIT=1 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Adapters\Output\level_zero_eager_init.cpp.tmp.out 2>&1 | d:\github\_work\llvm\llvm\install\bin\filecheck.exe D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Adapters\level_zero_eager_init.cpp
# executed command: env UR_L0_DEBUG=1 SYCL_EAGER_INIT=1 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Adapters\Output\level_zero_eager_init.cpp.tmp.out'
# note: command had no output on stdout or stderr
# error: command failed with exit status: 0xc0000409
# executed command: 'd:\github\_work\llvm\llvm\install\bin\filecheck.exe' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Adapters\level_zero_eager_init.cpp'

--

and

Seems all graph and matrix tests fail, in addition to one DeviceLib

link

********************
Failed Tests (118):
  SYCL :: Adapters/level_zero_eager_init.cpp
  SYCL :: DeviceLib/std_complex_math_fp64_test.cpp
  SYCL :: Graph/Update/Explicit/whole_update_double_buffer.cpp
  SYCL :: Graph/Update/Explicit/whole_update_host_task.cpp
  SYCL :: Graph/Update/Explicit/whole_update_host_task_accessor.cpp
  SYCL :: Graph/Update/Explicit/whole_update_local_acc.cpp
  SYCL :: Graph/Update/Explicit/whole_update_local_acc_multi.cpp
  SYCL :: Graph/Update/Explicit/whole_update_raw_arg.cpp
  SYCL :: Graph/Update/Explicit/whole_update_subgraph.cpp
  SYCL :: Graph/Update/Explicit/whole_update_usm.cpp
  SYCL :: Graph/Update/Explicit/whole_update_work_group_memory.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_before_finalize.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_multiple_exec_graphs.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_ordering.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_ptr.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_ptr_3D.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_ptr_double_update.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_ptr_multiple_nodes.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_ptr_multiple_params.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_ptr_subgraph.cpp
  SYCL :: Graph/Update/FreeFunctionKernels/update_with_indices_scalar.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_double_buffer.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_host_task.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_host_task_accessor.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_local_acc.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_local_acc_multi.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_raw_arg.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_subgraph.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_usm.cpp
  SYCL :: Graph/Update/RecordReplay/whole_update_work_group_memory.cpp
  SYCL :: Graph/Update/dyn_cgf_accessor.cpp
  SYCL :: Graph/Update/dyn_cgf_accessor_deps.cpp
  SYCL :: Graph/Update/dyn_cgf_accessor_deps2.cpp
  SYCL :: Graph/Update/dyn_cgf_accessor_spv.cpp
  SYCL :: Graph/Update/dyn_cgf_different_arg_nums.cpp
  SYCL :: Graph/Update/dyn_cgf_event_deps.cpp
  SYCL :: Graph/Update/dyn_cgf_get_active_index.cpp
  SYCL :: Graph/Update/dyn_cgf_host_task_accessor.cpp
  SYCL :: Graph/Update/dyn_cgf_host_task_usm.cpp
  SYCL :: Graph/Update/dyn_cgf_ndrange.cpp
  SYCL :: Graph/Update/dyn_cgf_ndrange_3D.cpp
  SYCL :: Graph/Update/dyn_cgf_overwrite_range.cpp
  SYCL :: Graph/Update/dyn_cgf_parameters.cpp
  SYCL :: Graph/Update/dyn_cgf_shared_nodes.cpp
  SYCL :: Graph/Update/dyn_cgf_usm.cpp
  SYCL :: Graph/Update/dyn_cgf_with_all_dyn_params.cpp
  SYCL :: Graph/Update/dyn_cgf_with_different_type_dyn_params.cpp
  SYCL :: Graph/Update/dyn_cgf_with_some_dyn_params.cpp
  SYCL :: Graph/Update/regression_padded_parameter.cpp
  SYCL :: Graph/Update/update_before_finalize.cpp
  SYCL :: Graph/Update/update_nd_range.cpp
  SYCL :: Graph/Update/update_ndrange_to_range.cpp
  SYCL :: Graph/Update/update_nullptr.cpp
  SYCL :: Graph/Update/update_range.cpp
  SYCL :: Graph/Update/update_range_to_ndrange.cpp
  SYCL :: Graph/Update/update_with_indices_accessor.cpp
  SYCL :: Graph/Update/update_with_indices_accessor_double_update.cpp
  SYCL :: Graph/Update/update_with_indices_accessor_multiple_nodes_different_indices.cpp
  SYCL :: Graph/Update/update_with_indices_accessor_ordering.cpp
  SYCL :: Graph/Update/update_with_indices_accessor_spv.cpp
  SYCL :: Graph/Update/update_with_indices_multiple_exec_graphs.cpp
  SYCL :: Graph/Update/update_with_indices_ordering.cpp
  SYCL :: Graph/Update/update_with_indices_ptr.cpp
  SYCL :: Graph/Update/update_with_indices_ptr_3D.cpp
  SYCL :: Graph/Update/update_with_indices_ptr_double_update.cpp
  SYCL :: Graph/Update/update_with_indices_ptr_multiple_nodes.cpp
  SYCL :: Graph/Update/update_with_indices_ptr_multiple_nodes_different_indices.cpp
  SYCL :: Graph/Update/update_with_indices_ptr_multiple_params.cpp
  SYCL :: Graph/Update/update_with_indices_ptr_subgraph.cpp
  SYCL :: Graph/Update/update_with_indices_scalar.cpp
  SYCL :: Graph/Update/update_with_raw_kernel_arg.cpp
  SYCL :: Graph/Update/whole_update_barrier_node.cpp
  SYCL :: Graph/Update/whole_update_dynamic_cgf.cpp
  SYCL :: Graph/Update/whole_update_dynamic_param.cpp
  SYCL :: Graph/Update/whole_update_empty_node.cpp
  SYCL :: Graph/Update/whole_update_kernel_type_mismatch.cpp
  SYCL :: Graph/Update/work_group_static_memory_with_dyn_cgf_and_dyn_params.cpp
  SYCL :: Matrix/SG32/element_wise_abc.cpp
  SYCL :: Matrix/SG32/element_wise_all_ops.cpp
  SYCL :: Matrix/SG32/element_wise_all_ops_half.cpp
  SYCL :: Matrix/SG32/element_wise_all_ops_int8.cpp
  SYCL :: Matrix/SG32/element_wise_all_ops_int8_packed.cpp
  SYCL :: Matrix/SG32/element_wise_all_ops_tf32.cpp
  SYCL :: Matrix/SG32/element_wise_all_sizes.cpp
  SYCL :: Matrix/SG32/element_wise_ops.cpp
  SYCL :: Matrix/SG32/joint_matrix_apply_bf16.cpp
  SYCL :: Matrix/SG32/joint_matrix_apply_two_matrices.cpp
  SYCL :: Matrix/SG32/joint_matrix_bf16_fill_k_cache.cpp
  SYCL :: Matrix/SG32/joint_matrix_bf16_fill_k_cache_SLM.cpp
  SYCL :: Matrix/SG32/joint_matrix_bf16_fill_k_cache_init.cpp
  SYCL :: Matrix/SG32/joint_matrix_bf16_fill_k_cache_unroll.cpp
  SYCL :: Matrix/SG32/joint_matrix_bf16_fill_k_cache_unroll_init.cpp
  SYCL :: Matrix/SG32/joint_matrix_down_convert.cpp
  SYCL :: Matrix/SG32/joint_matrix_tf32.cpp
  SYCL :: Matrix/element_wise_abc.cpp
  SYCL :: Matrix/element_wise_all_ops.cpp
  SYCL :: Matrix/element_wise_all_ops_1d.cpp
  SYCL :: Matrix/element_wise_all_ops_1d_cont.cpp
  SYCL :: Matrix/element_wise_all_ops_half.cpp
  SYCL :: Matrix/element_wise_all_ops_int8.cpp
  SYCL :: Matrix/element_wise_all_ops_int8_packed.cpp
  SYCL :: Matrix/element_wise_all_ops_scalar.cpp
  SYCL :: Matrix/element_wise_all_ops_tf32.cpp
  SYCL :: Matrix/element_wise_all_sizes.cpp
  SYCL :: Matrix/element_wise_ops.cpp
  SYCL :: Matrix/get_coordinate_ops.cpp
  SYCL :: Matrix/joint_matrix_apply_bf16.cpp
  SYCL :: Matrix/joint_matrix_apply_two_matrices.cpp
  SYCL :: Matrix/joint_matrix_bf16_fill_k_cache.cpp
  SYCL :: Matrix/joint_matrix_bf16_fill_k_cache_OOB.cpp
  SYCL :: Matrix/joint_matrix_bf16_fill_k_cache_SLM.cpp
  SYCL :: Matrix/joint_matrix_bf16_fill_k_cache_init.cpp
  SYCL :: Matrix/joint_matrix_bf16_fill_k_cache_prefetch.cpp
  SYCL :: Matrix/joint_matrix_bf16_fill_k_cache_unroll.cpp
  SYCL :: Matrix/joint_matrix_bf16_fill_k_cache_unroll_init.cpp
  SYCL :: Matrix/joint_matrix_down_convert.cpp
  SYCL :: Matrix/joint_matrix_rowmajorA_rowmajorB.cpp
  SYCL :: Matrix/joint_matrix_tf32.cpp

example failures:

********************
FAIL: SYCL :: DeviceLib/std_complex_math_fp64_test.cpp (539 of 2269)
******************** TEST 'SYCL :: DeviceLib/std_complex_math_fp64_test.cpp' FAILED ********************
Exit Code: 2

Command Output (stdout):
--
# RUN: at line 3
D:/github/_work/llvm/llvm/install/bin/clang++.exe  -Werror -fsycl -fsycl-targets=spir64  D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\DeviceLib\std_complex_math_fp64_test.cpp -o D:\github\_work\llvm\llvm\build-e2e\DeviceLib\Output\std_complex_math_fp64_test.cpp.tmp1.out
# executed command: D:/github/_work/llvm/llvm/install/bin/clang++.exe -Werror -fsycl -fsycl-targets=spir64 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\DeviceLib\std_complex_math_fp64_test.cpp' -o 'D:\github\_work\llvm\llvm\build-e2e\DeviceLib\Output\std_complex_math_fp64_test.cpp.tmp1.out'
# RUN: at line 4
env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\DeviceLib\Output\std_complex_math_fp64_test.cpp.tmp1.out
# executed command: env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\DeviceLib\Output\std_complex_math_fp64_test.cpp.tmp1.out'
# .---command stdout------------
# | test array 1 fail at index 37
# | expected: (1.5708,0)
# | actual:   (0,-0)
# | test array 1 fail at index 55
# | expected: (1.5708,0)
# | actual:   (nan,-nan(ind))
# `-----------------------------
# error: command failed with exit status: 2


********************
FAIL: SYCL :: Graph/Update/Explicit/whole_update_local_acc.cpp (1298 of 2269)
******************** TEST 'SYCL :: Graph/Update/Explicit/whole_update_local_acc.cpp' FAILED ********************
Exit Code: 3221226505

Command Output (stdout):
--
# RUN: at line 1
D:/github/_work/llvm/llvm/install/bin/clang++.exe  -Werror -fsycl -fsycl-targets=spir64  D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\Update\Explicit\whole_update_local_acc.cpp -o D:\github\_work\llvm\llvm\build-e2e\Graph\Update\Explicit\Output\whole_update_local_acc.cpp.tmp.out
# executed command: D:/github/_work/llvm/llvm/install/bin/clang++.exe -Werror -fsycl -fsycl-targets=spir64 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\Update\Explicit\whole_update_local_acc.cpp' -o 'D:\github\_work\llvm\llvm\build-e2e\Graph\Update\Explicit\Output\whole_update_local_acc.cpp.tmp.out'
# RUN: at line 2
env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Graph\Update\Explicit\Output\whole_update_local_acc.cpp.tmp.out
# executed command: env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Graph\Update\Explicit\Output\whole_update_local_acc.cpp.tmp.out'
# note: command had no output on stdout or stderr
# error: command failed with exit status: 0xc0000409

--


********************
FAIL: SYCL :: Matrix/SG32/joint_matrix_bf16_fill_k_cache_unroll_init.cpp (1615 of 2269)
******************** TEST 'SYCL :: Matrix/SG32/joint_matrix_bf16_fill_k_cache_unroll_init.cpp' FAILED ********************
Exit Code: 3221226505

Command Output (stdout):
--
# RUN: at line 18
D:/github/_work/llvm/llvm/install/bin/clang++.exe  -Werror -I D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Matrix/Inputs  -fsycl -fsycl-targets=spir64  D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Matrix\SG32\joint_matrix_bf16_fill_k_cache_unroll_init.cpp -mllvm -inline-threshold=5000 -ffp-model=precise -o D:\github\_work\llvm\llvm\build-e2e\Matrix\SG32\Output\joint_matrix_bf16_fill_k_cache_unroll_init.cpp.tmp_gpu.out -DINIT_LIST -DMANUAL_UNROLL -DVNNI
# executed command: D:/github/_work/llvm/llvm/install/bin/clang++.exe -Werror -I 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Matrix/Inputs' -fsycl -fsycl-targets=spir64 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Matrix\SG32\joint_matrix_bf16_fill_k_cache_unroll_init.cpp' -mllvm -inline-threshold=5000 -ffp-model=precise -o 'D:\github\_work\llvm\llvm\build-e2e\Matrix\SG32\Output\joint_matrix_bf16_fill_k_cache_unroll_init.cpp.tmp_gpu.out' -DINIT_LIST -DMANUAL_UNROLL -DVNNI
# RUN: at line 19
env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Matrix\SG32\Output\joint_matrix_bf16_fill_k_cache_unroll_init.cpp.tmp_gpu.out
# executed command: env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Matrix\SG32\Output\joint_matrix_bf16_fill_k_cache_unroll_init.cpp.tmp_gpu.out'
# .---command stdout------------
# | Testing: 8 x 16 x 16 [TM x TN x TK]
# `-----------------------------
# error: command failed with exit status: 0xc0000409

To reproduce

No response

Environment

No response

Additional context

No response
@sarnex sarnex added bug Something isn't working confirmed labels Feb 25, 2025
@sarnex sarnex mentioned this issue Feb 28, 2025
Merged
@sarnex sarnex changed the title Tests failing on BMG Windows Tests failing/slow on BMG Windows Feb 28, 2025
@sarnex sarnex changed the title Tests failing/slow on BMG Windows Tests failingon BMG Windows Feb 28, 2025
@sarnex sarnex changed the title Tests failingon BMG Windows Tests failing on BMG Windows Feb 28, 2025
sarnex added a commit that referenced this issue Mar 6, 2025
@sarnex
[CI] Add Windows BMG testing in precommit (#17105)
2054243 
We got a Windows BMG machine, so add Windows BMG testing.

There are two categories of failures here: consistent failures/timeouts
and really slow tests causing CI to take 30min extra.

I disabled both of these and made two GH issues:
[one](#17165),
[two](#17255).

---------

Signed-off-by: Sarnie, Nick <[email protected]>
@EwanC EwanC mentioned this issue Mar 7, 2025
Merged
@EwanC
Copy link
Contributor

EwanC commented Mar 7, 2025 •
edited
Loading

Noting that additional graph fails outwith Graph/Update were seen in https://github.com/intel/llvm/actions/runs/13702049076/job/38324625461?pr=17105

-- Testing: 2276 tests, 24 workers --
FAIL: SYCL :: Graph/RecordReplay/host_task_successive.cpp (1253 of 2276)
******************** TEST 'SYCL :: Graph/RecordReplay/host_task_successive.cpp' FAILED ********************
Exit Code: 1

Command Output (stdout):
--
# RUN: at line 1
D:/github/_work/llvm/llvm/install/bin/clang++.exe  -Werror -fsycl -fsycl-targets=spir64  D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\host_task_successive.cpp -o D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out
# executed command: D:/github/_work/llvm/llvm/install/bin/clang++.exe -Werror -fsycl -fsycl-targets=spir64 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\host_task_successive.cpp' -o 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out'
# RUN: at line 2
env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out
# executed command: env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out'
# RUN: at line 4
env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=0 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out 2>&1 | d:\github\_work\llvm\llvm\install\bin\filecheck.exe D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\host_task_successive.cpp --implicit-check-not=LEAK
# executed command: env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=0 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out'
# executed command: 'd:\github\_work\llvm\llvm\install\bin\filecheck.exe' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\host_task_successive.cpp' --implicit-check-not=LEAK
# RUN: at line 6
env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=1 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out 2>&1 | d:\github\_work\llvm\llvm\install\bin\filecheck.exe D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\host_task_successive.cpp --implicit-check-not=LEAK
# executed command: env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=1 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\host_task_successive.cpp.tmp.out'
# note: command had no output on stdout or stderr
# error: command failed with exit status: 0xc0000409
# executed command: 'd:\github\_work\llvm\llvm\install\bin\filecheck.exe' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\host_task_successive.cpp' --implicit-check-not=LEAK
# .---command stderr------------
# | command line:1:22: error: IMPLICIT-CHECK-NOT: excluded string found in input
# | -implicit-check-not='LEAK'
# |                      ^
# | <stdin>:3:54: note: found here
# |  zeContextCreate = 1 \---> zeContextDestroy = 0 ---> LEAK = 1
# |                                                      ^~~~
# |
# | Input file: <stdin>
# | Check file: D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\host_task_successive.cpp
# |
# | -dump-input=help explains the following input dump.
# |
# | Input was:
# | <<<<<<
# |           1: Check balance of create/destroy calls
# |           2: ----------------------------------------------------------
# |           3:  zeContextCreate = 1 \---> zeContextDestroy = 0 ---> LEAK = 1
# | not:imp1                                                          !~~~      error: no match expected
# |           4:  zeCommandQueueCreate = 1 \---> zeCommandQueueDestroy = 0 ---> LEAK = 1
# |           5:  zeModuleCreate = 1 \---> zeModuleDestroy = 0 ---> LEAK = 1
# |           6:  zeKernelCreate = 2 \---> zeKernelDestroy = 0 ---> LEAK = 2
# |           7:  zeEventPoolCreate = 2 \---> zeEventPoolDestroy = 0 ---> LEAK = 2
# |           8:  zeCommandListCreateImmediate = 2 |
# |           .
# |           .
# |           .
# | >>>>>>
# `-----------------------------
# error: command failed with exit status: 1

--

********************
FAIL: SYCL :: Graph/RecordReplay/interop-level-zero-launch-kernel.cpp (1264 of 2276)
******************** TEST 'SYCL :: Graph/RecordReplay/interop-level-zero-launch-kernel.cpp' FAILED ********************
Exit Code: 2

Command Output (stdout):
--
# RUN: at line 5
D:/github/_work/llvm/llvm/install/bin/clang++.exe  -Werror -fsycl -fsycl-targets=spir64  D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\interop-level-zero-launch-kernel.cpp  -LD:\github\level-zero_win-sdk\lib -lze_loader  -ID:\github\level-zero_win-sdk\include -o D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out
# executed command: D:/github/_work/llvm/llvm/install/bin/clang++.exe -Werror -fsycl -fsycl-targets=spir64 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\interop-level-zero-launch-kernel.cpp' '-LD:\github\level-zero_win-sdk\lib' -lze_loader '-ID:\github\level-zero_win-sdk\include' -o 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out'
# RUN: at line 6
env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay/../Inputs/Kernels/saxpy.spv
# executed command: env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay/../Inputs/Kernels/saxpy.spv'
# RUN: at line 8
env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=0 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay/../Inputs/Kernels/saxpy.spv 2>&1 | d:\github\_work\llvm\llvm\install\bin\filecheck.exe D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\interop-level-zero-launch-kernel.cpp --implicit-check-not=LEAK
# executed command: env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=0 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay/../Inputs/Kernels/saxpy.spv'
# executed command: 'd:\github\_work\llvm\llvm\install\bin\filecheck.exe' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\interop-level-zero-launch-kernel.cpp' --implicit-check-not=LEAK
# RUN: at line 10
env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=1 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu  D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay/../Inputs/Kernels/saxpy.spv 2>&1 | d:\github\_work\llvm\llvm\install\bin\filecheck.exe D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\interop-level-zero-launch-kernel.cpp --implicit-check-not=LEAK
# executed command: env SYCL_PI_LEVEL_ZERO_USE_IMMEDIATE_COMMANDLISTS=1 env UR_L0_LEAKS_DEBUG=1 SYCL_ENABLE_DEFAULT_CONTEXTS=0 env ONEAPI_DEVICE_SELECTOR=level_zero:gpu 'D:\github\_work\llvm\llvm\build-e2e\Graph\RecordReplay\Output\interop-level-zero-launch-kernel.cpp.tmp.out' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay/../Inputs/Kernels/saxpy.spv'
# executed command: 'd:\github\_work\llvm\llvm\install\bin\filecheck.exe' 'D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\interop-level-zero-launch-kernel.cpp' --implicit-check-not=LEAK
# .---command stderr------------
# | FileCheck error: '<stdin>' is empty.
# | FileCheck command line:  d:\github\_work\llvm\llvm\install\bin\filecheck.exe D:\github\_work\llvm\llvm\llvm\sycl\test-e2e\Graph\RecordReplay\interop-level-zero-launch-kernel.cpp --implicit-check-not=LEAK
# `-----------------------------
# error: command failed with exit status: 2

--

If the RecordReplay tests fail it is likely that other Graph tests could also fail, so disabling all graph tests on Windows BMG until this can be investigated #17348

sarnex pushed a commit that referenced this issue Mar 7, 2025
@EwanC
[SYCL][Graph][E2E] Disable all Graph E2E testing on Windows Battlemage (
acfbc00 
#17348)

We currently only disable the RecordReplay variant of E2E testing on
battlemage, however we have many other tests and the likihood is that if
the RecordReplay tests are failing then other tests will start failing
too.

Disable all Graphs tests until Graph support on Windows battlemage can
be investigated more thoroughly.

See #17165
AlexeySachkov pushed a commit to AlexeySachkov/llvm that referenced this issue Mar 31, 2025
@EwanC @AlexeySachkov
[SYCL][Graph][E2E] Disable all Graph E2E testing on Windows Battlemage (
71e7215 
intel#17348)

We currently only disable the RecordReplay variant of E2E testing on
battlemage, however we have many other tests and the likihood is that if
the RecordReplay tests are failing then other tests will start failing
too.

Disable all Graphs tests until Graph support on Windows battlemage can
be investigated more thoroughly.

See intel#17165
AlexeySachkov pushed a commit to AlexeySachkov/llvm that referenced this issue Mar 31, 2025
@sarnex @AlexeySachkov
[CI] Add Windows BMG testing in precommit (intel#17105)
9dbda19 
We got a Windows BMG machine, so add Windows BMG testing.

There are two categories of failures here: consistent failures/timeouts
and really slow tests causing CI to take 30min extra.

I disabled both of these and made two GH issues:
[one](intel#17165),
[two](intel#17255).

---------

Signed-off-by: Sarnie, Nick <[email protected]>
@AlexeySachkov AlexeySachkov mentioned this issue Mar 31, 2025
Merged
AlexeySachkov added a commit that referenced this issue Apr 1, 2025
@AlexeySachkov
[SYCL][NFC] Cleanup BMG testing on Windows (#17753)
cb4f7ab 
This is a joined cherry-pick of #17347 and #17105
made to align disabled tests between `sycl` and `sycl-rel-6_1_0`
branches to make the pre-commit more stable on the latter.

Descriptions of cherry-picked commits:

---

[SYCL][Graph][E2E] Disable all Graph E2E testing on Windows Battlemage
(#17348)

We currently only disable the RecordReplay variant of E2E testing on
battlemage, however we have many other tests and the likihood is that if
the RecordReplay tests are failing then other tests will start failing
too.

Disable all Graphs tests until Graph support on Windows battlemage can
be investigated more thoroughly.

See #17165

Patch-By: Ewan Crawford <[email protected]>

---

[CI] Add Windows BMG testing in precommit (#17105)

We got a Windows BMG machine, so add Windows BMG testing.

There are two categories of failures here: consistent failures/timeouts
and really slow tests causing CI to take 30min extra.

I disabled both of these and made two GH issues:
[one](#17165),
[two](#17255).

Patch-by: Sarnie, Nick <[email protected]>

---
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 sycl-graph
Projects
None yet
Milestone
No milestone
Development

No branches or pull requests
2 participants
@EwanC @sarnex