[E2E][HIP] Several E2E tests failed on HIP in SYCL Nightly testing #12997
Description
Describe the bug
The following E2E tests failed on HIP during SYCL Nightly testing:
https://github.com/intel/llvm/actions/runs/8242960746/job/22543076923
********************
Failed Tests (15):
SYCL :: Basic/large-range.cpp
SYCL :: USM/memops2d/copy2d_device_to_dhost.cpp
SYCL :: USM/memops2d/copy2d_dhost_to_device.cpp
SYCL :: USM/memops2d/copy2d_dhost_to_dhost.cpp
SYCL :: USM/memops2d/copy2d_dhost_to_host.cpp
SYCL :: USM/memops2d/copy2d_host_to_dhost.cpp
SYCL :: USM/memops2d/fill2d.cpp
SYCL :: USM/memops2d/memcpy2d_device_to_dhost.cpp
SYCL :: USM/memops2d/memcpy2d_dhost_to_device.cpp
SYCL :: USM/memops2d/memcpy2d_dhost_to_dhost.cpp
SYCL :: USM/memops2d/memcpy2d_dhost_to_host.cpp
SYCL :: USM/memops2d/memcpy2d_host_to_dhost.cpp
SYCL :: USM/memops2d/memset2d.cpp
SYCL :: syclcompat/memory/memory_management_test3.cpp
SYCL :: syclcompat/util/util_matrix_mem_copy_test.cpp
Basic/large-range.cpp test failed with the following error message:
******************** TEST 'SYCL :: Basic/large-range.cpp' FAILED ********************
Exit Code: -8
Command Output (stdout):
--
# RUN: at line 2
/__w/llvm/llvm/toolchain/bin//clang++ -Xsycl-target-backend=amdgcn-amd-amdhsa --offload-arch=gfx1031 -fsycl -fsycl-targets=amdgcn-amd-amdhsa /__w/llvm/llvm/llvm/sycl/test-e2e/Basic/large-range.cpp -fno-sycl-id-queries-fit-in-int -O2 -o /__w/llvm/llvm/build-e2e/Basic/Output/large-range.cpp.tmp.out
# executed command: /__w/llvm/llvm/toolchain/bin//clang++ -Xsycl-target-backend=amdgcn-amd-amdhsa --offload-arch=gfx1031 -fsycl -fsycl-targets=amdgcn-amd-amdhsa /__w/llvm/llvm/llvm/sycl/test-e2e/Basic/large-range.cpp -fno-sycl-id-queries-fit-in-int -O2 -o /__w/llvm/llvm/build-e2e/Basic/Output/large-range.cpp.tmp.out
# note: command had no output on stdout or stderr
# RUN: at line 3
env SYCL_PARALLEL_FOR_RANGE_ROUNDING_TRACE=1 env ONEAPI_DEVICE_SELECTOR=hip:gpu /__w/llvm/llvm/build-e2e/Basic/Output/large-range.cpp.tmp.out
# executed command: env SYCL_PARALLEL_FOR_RANGE_ROUNDING_TRACE=1 env ONEAPI_DEVICE_SELECTOR=hip:gpu /__w/llvm/llvm/build-e2e/Basic/Output/large-range.cpp.tmp.out
# .---command stdout------------
# | parallel_for range adjusted at dim 0 from 4294967311 to 4294967328
# | parallel_for range adjusted at dim 0 from 4294967328 to 4294967264
# | regular range<1> pass
# | parallel_for range adjusted at dim 1 from 4294967311 to 4294967264
# | regular range<2> pass
# | parallel_for range adjusted at dim 2 from 4294967311 to 4294967264
# | regular range<3> pass
# | parallel_for range adjusted at dim 0 from 4294967311 to 4294967328
# | parallel_for range adjusted at dim 0 from 4294967328 to 4294967264
# | spec constant range<1> pass
# | parallel_for range adjusted at dim 0 from 4294967311 to 4294967328
# | parallel_for range adjusted at dim 0 from 4294967328 to 97152
# `-----------------------------
# .---command stderr------------
# |
# | UR HIP ERROR:
# | Value: 1
# | Name: hipErrorInvalidValue
# | Description: invalid argument
# | Function: urEnqueueKernelLaunch
# | Source Location: /__w/llvm/llvm/build/_deps/unified-runtime-src/source/adapters/hip/enqueue.cpp:9
# |
# `-----------------------------
USM/* and syclcompat/* tests failed with the following error message:
# .---command stderr------------
# | terminate called after throwing an instance of 'sycl::_V1::runtime_error'
# | what(): get_pointer_type() API failed with error: -38 (PI_ERROR_INVALID_MEM_OBJECT) -38 (PI_ERROR_INVALID_MEM_OBJECT)
# `-----------------------------
To reproduce
intel/llvm commit id: ad6085c
Environment
sycl-ls --verbose output:
sycl-ls --verbose
[hip:gpu][hip:0] AMD HIP BACKEND, AMD Radeon RX 6700 XT gfx101 [HIP 60032.83]
Platforms: 1
Platform [#1]:
Version : HIP 60032.83
Name : AMD HIP BACKEND
Vendor : AMD Corporation
Devices : 1
Device [#0]:
Type : gpu
Version : gfx1031
Name : AMD Radeon RX 6700 XT
Vendor : AMD Corporation
Driver : HIP 60032.83
Aspects : gpu fp16 fp6 online_compiler online_linker queue_profiling usm_device_allocations usm_host_allocations ext_intel_pci_address usm_atomic_host_allocations atomic4 ext_intel_device_info_uuid ext_oneapi_native_assert ext_intel_free_memory ext_intel_device_id ext_intel_memory_clock_rate ext_intel_memory_bus_width ext_intel_legacy_imagepi_ext_intel_devicelib_assert ur_exp_command_buffer cl_khr_fp64 cl_khr_fp16 ext_oneapi_graph
info::device::sub_group_sizes: 32
default_selector() : gpu, AMD HIP BACKEND, AMD Radeon RX 600 XT gfx1031 [HIP 60032.3]
accelerator_selector() : No device of requested type available. -1 (PI_ERRO...
cpu_selector() : No device of requested type available. -1 (PI_ERRO...
gpu_selector() : gpu, AMD HIP BACKEND, AMD Radeon RX 6700 XT gfx31 [HIP 60032.83]
custom_selector(gpu) : gpu, AMD HIP BACKEND, AMD Radeon RX 6700 XT gfx1031 [HIP 60032.83]
custom_selector(cpu) : No device of requested type available. -1 (PI_ERRO..
Additional context
No response