AI/rocm-systems
2
0
Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность

SWDEV-425967, SWDEV-425968 - Revert "SWDEV-415029 - [ABI Break] Remove hcc symbols"

Просмотр исходного кода 
This reverts commit 403afae98f.

Reason for revert: This causes build failure in hipBLASLt & hipSPARSELt

Change-Id: Ifb1ee519971c6183eb53634d6d8901a9e94cc9cc
Этот коммит содержится в:
Rakesh Roy
2023-10-09 06:31:33 -04:00
родитель a5c353f8f5
Коммит fe5206e50a
16 изменённых файлов: 83 добавлений и 83 удалений
Скачать Patch файл Скачать Diff файл Показать все файлы Свернуть все файлы
catch/unit/memory/hipMemcpy3DAsync_old.cc
+17 -17
Просмотреть файл
@@ -148,7 +148,7 @@ void Memcpy3DAsync<T>::D2H_H2D_DeviceMem_OnDiffDevice() {
myparms.srcPtr = make_hipPitchedPtr(hData, width * sizeof(T),
width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -166,7 +166,7 @@ void Memcpy3DAsync<T>::D2H_H2D_DeviceMem_OnDiffDevice() {
width * sizeof(T),
width, height);
myparms.srcArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToHost;
#else
myparms.kind = hipMemcpyDeviceToHost;
@@ -218,7 +218,7 @@ void Memcpy3DAsync<T>::D2D_DeviceMem_OnDiffDevice() {
width * sizeof(T),
width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -241,7 +241,7 @@ void Memcpy3DAsync<T>::D2D_DeviceMem_OnDiffDevice() {
// Device to Device
myparms.srcArray = arr;
myparms.dstArray = arr2;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -261,7 +261,7 @@ void Memcpy3DAsync<T>::D2D_DeviceMem_OnDiffDevice() {
width * sizeof(T),
width, height);
myparms.srcArray = arr2;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToHost;
#else
myparms.kind = hipMemcpyDeviceToHost;
@@ -294,7 +294,7 @@ void Memcpy3DAsync<T>::NegativeTests() {
myparms.srcPos = make_hipPos(0, 0, 0);
myparms.dstPos = make_hipPos(0, 0, 0);
myparms.extent = make_hipExtent(width , height, depth);
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -406,7 +406,7 @@ void Memcpy3DAsync<T>::NegativeTests() {
myparms.srcPos = make_hipPos(width+1, 0, 0);
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -418,7 +418,7 @@ void Memcpy3DAsync<T>::NegativeTests() {
myparms.srcPos = make_hipPos(0, height+1, 0);
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -430,7 +430,7 @@ void Memcpy3DAsync<T>::NegativeTests() {
myparms.srcPos = make_hipPos(0, 0, depth+1);
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -447,7 +447,7 @@ void Memcpy3DAsync<T>::NegativeTests() {
, 3), hipArrayDefault));
myparms.srcArray = arr;
myparms.dstArray = arr2;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -493,7 +493,7 @@ void Memcpy3DAsync<T>::D2D_SameDeviceMem_StreamDiffDevice() {
// Host to Device
myparms.srcPtr = make_hipPitchedPtr(hData, width * sizeof(T), width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -506,7 +506,7 @@ void Memcpy3DAsync<T>::D2D_SameDeviceMem_StreamDiffDevice() {
SetDefaultData();
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -522,7 +522,7 @@ void Memcpy3DAsync<T>::D2D_SameDeviceMem_StreamDiffDevice() {
myparms.dstPtr = make_hipPitchedPtr(hOutputData,
width * sizeof(T), width, height);
myparms.srcArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToHost;
#else
myparms.kind = hipMemcpyDeviceToHost;
@@ -555,7 +555,7 @@ void Memcpy3DAsync<T>::Extent_Validation() {
myparms.dstPos = make_hipPos(0, 0, 0);
myparms.srcPtr = make_hipPitchedPtr(hData, width * sizeof(T), width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -603,7 +603,7 @@ void Memcpy3DAsync<T>::simple_Memcpy3DAsync() {
// Host to Device
myparms.srcPtr = make_hipPitchedPtr(hData, width * sizeof(T), width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -622,7 +622,7 @@ void Memcpy3DAsync<T>::simple_Memcpy3DAsync() {
SetDefaultData();
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -638,7 +638,7 @@ void Memcpy3DAsync<T>::simple_Memcpy3DAsync() {
myparms.dstPtr = make_hipPitchedPtr(hOutputData,
width * sizeof(T), width, height);
myparms.srcArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToHost;
#else
myparms.kind = hipMemcpyDeviceToHost;
catch/unit/memory/hipMemcpy3D_old.cc
+14 -14
Просмотреть файл
@@ -143,7 +143,7 @@ void Memcpy3D<T>::D2H_H2D_DeviceMem_OnDiffDevice() {
myparms.srcPtr = make_hipPitchedPtr(hData, width * sizeof(T),
width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -160,7 +160,7 @@ void Memcpy3D<T>::D2H_H2D_DeviceMem_OnDiffDevice() {
width * sizeof(T),
width, height);
myparms.srcArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToHost;
#else
myparms.kind = hipMemcpyDeviceToHost;
@@ -206,7 +206,7 @@ void Memcpy3D<T>::D2D_DeviceMem_OnDiffDevice() {
width * sizeof(T),
width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -227,7 +227,7 @@ void Memcpy3D<T>::D2D_DeviceMem_OnDiffDevice() {
SetDefaultData();
myparms.srcArray = arr;
myparms.dstArray = arr2;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -247,7 +247,7 @@ void Memcpy3D<T>::D2D_DeviceMem_OnDiffDevice() {
width * sizeof(T),
width, height);
myparms.srcArray = arr2;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToHost;
#else
myparms.kind = hipMemcpyDeviceToHost;
@@ -276,7 +276,7 @@ void Memcpy3D<T>::NegativeTests() {
myparms.srcPos = make_hipPos(0, 0, 0);
myparms.dstPos = make_hipPos(0, 0, 0);
myparms.extent = make_hipExtent(width , height, depth);
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -388,7 +388,7 @@ void Memcpy3D<T>::NegativeTests() {
myparms.srcPos = make_hipPos(width+1, 0, 0);
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -400,7 +400,7 @@ void Memcpy3D<T>::NegativeTests() {
myparms.srcPos = make_hipPos(0, height+1, 0);
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -412,7 +412,7 @@ void Memcpy3D<T>::NegativeTests() {
myparms.srcPos = make_hipPos(0, 0, depth+1);
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -430,7 +430,7 @@ void Memcpy3D<T>::NegativeTests() {
, 3), hipArrayDefault));
myparms.srcArray = arr;
myparms.dstArray = arr2;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -455,7 +455,7 @@ void Memcpy3D<T>::Extent_Validation() {
myparms.srcPtr = make_hipPitchedPtr(hData, width * sizeof(T),
width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -505,7 +505,7 @@ void Memcpy3D<T>::simple_Memcpy3D() {
myparms.srcPtr = make_hipPitchedPtr(hData, width * sizeof(T),
width, height);
myparms.dstArray = arr;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyHostToDevice;
#else
myparms.kind = hipMemcpyHostToDevice;
@@ -517,7 +517,7 @@ void Memcpy3D<T>::simple_Memcpy3D() {
SetDefaultData();
myparms.srcArray = arr;
myparms.dstArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToDevice;
#else
myparms.kind = hipMemcpyDeviceToDevice;
@@ -532,7 +532,7 @@ void Memcpy3D<T>::simple_Memcpy3D() {
myparms.dstPtr = make_hipPitchedPtr(hOutputData,
width * sizeof(T), width, height);
myparms.srcArray = arr1;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
myparms.kind = cudaMemcpyDeviceToHost;
#else
myparms.kind = hipMemcpyDeviceToHost;
catch/unit/memory/hipMemcpyParam2D.cc
+12 -12
Просмотреть файл
@@ -75,7 +75,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2D_multiDevice-D2D", "[hipMemcpyParam2D]"
// Device to Device
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -83,7 +83,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2D_multiDevice-D2D", "[hipMemcpyParam2D]"
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.dstMemoryType = hipMemoryTypeDevice;
@@ -164,7 +164,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2D_multiDevice-H2D-D2H", "[hipMemcpyParam
} else {
// Host to Device
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.srcMemoryType = hipMemoryTypeHost;
@@ -172,7 +172,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2D_multiDevice-H2D-D2H", "[hipMemcpyParam
desc.srcHost = C_h;
desc.srcDevice = hipDeviceptr_t(C_h);
desc.srcPitch = width;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.dstMemoryType = hipMemoryTypeDevice;
@@ -186,7 +186,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2D_multiDevice-H2D-D2H", "[hipMemcpyParam
// Device to Host
memset(&desc, 0x0, sizeof(hip_Memcpy2D));
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -194,7 +194,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2D_multiDevice-H2D-D2H", "[hipMemcpyParam
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.dstMemoryType = hipMemoryTypeHost;
@@ -250,7 +250,7 @@ TEST_CASE("Unit_hipMemcpyParam2D_ExtentValidation") {
// Device to Host
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -258,7 +258,7 @@ TEST_CASE("Unit_hipMemcpyParam2D_ExtentValidation") {
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.dstMemoryType = hipMemoryTypeHost;
@@ -320,7 +320,7 @@ TEST_CASE("Unit_hipMemcpyParam2D_Negative") {
HIP_CHECK(hipMemset2D(A_d, pitch_A, memsetval, NUM_W, NUM_H));
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -328,7 +328,7 @@ TEST_CASE("Unit_hipMemcpyParam2D_Negative") {
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.dstMemoryType = hipMemoryTypeHost;
@@ -346,7 +346,7 @@ TEST_CASE("Unit_hipMemcpyParam2D_Negative") {
SECTION("Null Pointer to Destination Device Pointer") {
memset(&desc, 0x0, sizeof(hip_Memcpy2D));
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.srcMemoryType = hipMemoryTypeHost;
@@ -354,7 +354,7 @@ TEST_CASE("Unit_hipMemcpyParam2D_Negative") {
desc.srcHost = A_h;
desc.srcDevice = hipDeviceptr_t(A_h);
desc.srcPitch = width;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.dstMemoryType = hipMemoryTypeDevice;
catch/unit/memory/hipMemcpyParam2DAsync.cc
+14 -14
Просмотреть файл
@@ -82,7 +82,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-StreamOnDiffDevice",
HIP_CHECK(hipStreamSynchronize(stream));
// Device to Device
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -90,7 +90,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-StreamOnDiffDevice",
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.dstMemoryType = hipMemoryTypeDevice;
@@ -170,7 +170,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-D2D", "[hipMemcpyPara
// Device to Device
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -178,7 +178,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-D2D", "[hipMemcpyPara
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.dstMemoryType = hipMemoryTypeDevice;
@@ -261,7 +261,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-H2D-D2H", "[hipMemcpy
// Host to Device
hip_Memcpy2D desc = {};
HIP_CHECK(hipStreamCreate(&stream));
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.srcMemoryType = hipMemoryTypeHost;
@@ -269,7 +269,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-H2D-D2H", "[hipMemcpy
desc.srcHost = C_h;
desc.srcDevice = hipDeviceptr_t(C_h);
desc.srcPitch = width;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.dstMemoryType = hipMemoryTypeDevice;
@@ -284,7 +284,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-H2D-D2H", "[hipMemcpy
// Device to Host
memset(&desc, 0x0, sizeof(hip_Memcpy2D));
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -292,7 +292,7 @@ TEMPLATE_TEST_CASE("Unit_hipMemcpyParam2DAsync_multiDevice-H2D-D2H", "[hipMemcpy
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.dstMemoryType = hipMemoryTypeHost;
@@ -353,7 +353,7 @@ TEST_CASE("Unit_hipMemcpyParam2DAsync_ExtentValidation") {
// Device to Host
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -361,7 +361,7 @@ TEST_CASE("Unit_hipMemcpyParam2DAsync_ExtentValidation") {
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.dstMemoryType = hipMemoryTypeHost;
@@ -429,7 +429,7 @@ TEST_CASE("Unit_hipMemcpyParam2DAsync_Negative") {
// Device to Host
hip_Memcpy2D desc = {};
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.srcMemoryType = hipMemoryTypeDevice;
@@ -437,7 +437,7 @@ TEST_CASE("Unit_hipMemcpyParam2DAsync_Negative") {
desc.srcHost = A_d;
desc.srcDevice = hipDeviceptr_t(A_d);
desc.srcPitch = pitch_A;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.dstMemoryType = hipMemoryTypeHost;
@@ -455,7 +455,7 @@ TEST_CASE("Unit_hipMemcpyParam2DAsync_Negative") {
SECTION("Null Pointer to Destination Device Pointer") {
memset(&desc, 0x0, sizeof(hip_Memcpy2D));
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.srcMemoryType = CU_MEMORYTYPE_HOST;
#else
desc.srcMemoryType = hipMemoryTypeHost;
@@ -463,7 +463,7 @@ TEST_CASE("Unit_hipMemcpyParam2DAsync_Negative") {
desc.srcHost = A_h;
desc.srcDevice = hipDeviceptr_t(A_h);
desc.srcPitch = width;
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
desc.dstMemoryType = CU_MEMORYTYPE_DEVICE;
#else
desc.dstMemoryType = hipMemoryTypeDevice;
catch/unit/memory/hipMemcpyWithStream_old.cc
+1 -1
Просмотреть файл
@@ -575,7 +575,7 @@ TEST_CASE("Unit_hipMemcpyWithStream_TestOnMultiGPUwithOneStream") {
TEST_CASE("Unit_hipMemcpyWithStream_TestkindDefault") {
TestkindDefault();
}
#ifndef __HIP_PLATFORM_NVIDIA__
#ifndef __HIP_PLATFORM_NVCC__
TEST_CASE("Unit_hipMemcpyWithStream_TestkindDefaultForDtoD") {
TestkindDefaultForDtoD();
}
catch/unit/memory/hipPtrGetAttribute.cc
+2 -2
Просмотреть файл
@@ -96,7 +96,7 @@ TEST_CASE("Unit_hipPtrGetAttribute_Simple") {
unsigned int datatype;
HIP_CHECK(hipPointerGetAttribute(&datatype, HIP_POINTER_ATTRIBUTE_MEMORY_TYPE,
reinterpret_cast<hipDeviceptr_t>(A_d)));
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
REQUIRE(datatype == CU_MEMORYTYPE_DEVICE);
#else
REQUIRE(datatype == hipMemoryTypeDevice);
@@ -104,7 +104,7 @@ TEST_CASE("Unit_hipPtrGetAttribute_Simple") {
HIP_CHECK(hipPointerGetAttribute(&datatype, HIP_POINTER_ATTRIBUTE_MEMORY_TYPE,
reinterpret_cast<hipDeviceptr_t>(A_Pinned_h)));
#ifdef __HIP_PLATFORM_NVIDIA__
#ifdef __HIP_PLATFORM_NVCC__
REQUIRE(datatype == CU_MEMORYTYPE_HOST);
#else
REQUIRE(datatype == hipMemoryTypeHost);