Tests failing on BMG Windows
- Dominant language
- LLVM
- Stars
- 1.5k
- Forks
- 854
- Avg merge
- 3d 17h
- Merged PRs (30d)
- 137
Description
### Describe the bug
[sycl/test-e2e/Adapters/level_zero_eager_init.cpp](https://github.com/intel/llvm/actions/runs/13501790501/job/37733278662)
```
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 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 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](https://github.com/intel/llvm/actions/runs/13571435681/job/37950408884)
```
********************
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_
Contributor guide
Assessment
This issue has not been assessed yet.