intel / intel/llvm

memcpy2d and copy2d is failing on HIP target

Open
#10,157 1 comment 0 reactions 0 assignees View on GitHub
bug confirmed hip
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

Open the contributing guide

Assessment

This issue has not been assessed yet.

Get new issues in your inbox

A short digest of beginner-friendly GitHub issues.