memcpy2d and copy2d is failing on HIP target
- Dominant language
- LLVM
- Stars
- 1.5k
- Forks
- 854
- Avg merge
- 3d 17h
- Merged PRs (30d)
- 137
Description
CI is failing 2D USM memory copies between USM device and USM host memory (not non-USM host memory).
Failing tests:
- SYCL :: USM/memops2d/copy2d_device_to_host.cpp
- SYCL :: USM/memops2d/copy2d_host_to_device.cpp
- SYCL :: USM/memops2d/memcpy2d_device_to_host.cpp
- SYCL :: USM/memops2d/memcpy2d_host_to_device.cpp
Example failure output:
```
********************
FAIL: SYCL :: USM/memops2d/copy2d_device_to_host.cpp (1367 of 1431)
******************** TEST 'SYCL :: USM/memops2d/copy2d_device_to_host.cpp' FAILED ********************
Script:
--
: 'RUN: at line 10'; .../llvm/toolchain/bin/clang++ -Xsycl-target-backend=amdgcn-amd-amdhsa --offload-arch=gfx1031 -fsycl -fsycl-targets=amdgcn-amd-amdhsa .../llvm/llvm/sycl/test-e2e/USM/memops2d/copy2d_device_to_host.cpp -o .../llvm/build-e2e/USM/memops2d/Output/copy2d_device_to_host.cpp.tmp.out
: 'RUN: at line 11'; env ONEAPI_DEVICE_SELECTOR=ext_oneapi_hip:gpu .../llvm/build-e2e/USM/memops2d/Output/copy2d_device_to_host.cpp.tmp.out
--
Exit Code: -6
Command Output (stdout):
--
$ ":" "RUN: at line 10"
note: command had no output on stdout or stderr
$ ".../llvm/toolchain/bin/clang++" "-Xsycl-target-backend=amdgcn-amd-amdhsa" "--offload-arch=gfx1031" "-fsycl" "-fsycl-targets=amdgcn-amd-amdhsa" ".../llvm/llvm/sycl/test-e2e/USM/memops2d/copy2d_device_to_host.cpp" "-o" ".../llvm/build-e2e/USM/memops2d/Output/copy2d_device_to_host.cpp.tmp.out"
note: command had no output on stdout or stderr
$ ":" "RUN: at line 11"
note: command had no output on stdout or stderr
$ "env" "ONEAPI_DEVICE_SELECTOR=ext_oneapi_hip:gpu" ".../llvm/build-e2e/USM/memops2d/Output/copy2d_device_to_host.cpp.tmp.out"
# command stderr:
PI HIP ERROR:
Value: 1
Name: hipErrorInvalidValue
Description: invalid argument
Function: hip_piextUSMEnqueueMemcpy2D
Source Location: .../llvm/src/sycl/plugins/hip/pi_hip.cpp:5404
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
what(): Native API failed. Native API returns: -30 (PI_ERROR_INVALID_VALUE) -30 (PI_ERROR_INVALID_VALUE)
error: command failed with exit status: -6
--
```
See for example CI runs for https://github.com/intel/llvm/pull/9843.
Contributor guide
Assessment
This issue has not been assessed yet.