memcpy2d and copy2d is failing on HIP target

[steffenlarsen]

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 #9843.

[JackAKirk]

Passes on rocm supported cards