AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity

P4 to Git Change 1981152 by cpaquot@cpaquot-ocl-lc-lnx on 2019/08/09 20:33:32

Browse Source 
SWDEV-193430 - [HIP] Delay creating HostQueue till commands are enqueued.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#5 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#34 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#31 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#21 edit
This commit is contained in:
foreman
2019-08-09 20:41:13 -04:00
parent 867d521a08
commit 92840c805e
6 changed files with 85 additions and 44 deletions
Download Patch File Download Diff File Expand all files Collapse all files
api/hip/hip_memory.cpp
+7 -7
View File
@@ -177,7 +177,7 @@ hipError_t ihipMemset(void* dst, int value, size_t valueSize, size_t sizeBytes,
queue = hip::getNullStream();
} else {
hip::getNullStream()->finish();
queue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
queue = reinterpret_cast<hip::Stream*>(stream)->asHostQueue();
}
if (memory != nullptr) {
@@ -771,7 +771,7 @@ hipError_t hipMemcpyAsync(void* dst, const void* src, size_t sizeBytes,
queue = hip::getNullStream();
} else {
hip::getNullStream()->finish();
queue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
queue = reinterpret_cast<hip::Stream*>(stream)->asHostQueue();
}
HIP_RETURN(ihipMemcpy(dst, src, sizeBytes, kind, *queue, true));
@@ -789,7 +789,7 @@ hipError_t hipMemcpyHtoDAsync(hipDeviceptr_t dst, void* src, size_t sizeBytes,
queue = hip::getNullStream();
} else {
hip::getNullStream()->finish();
queue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
queue = reinterpret_cast<hip::Stream*>(stream)->asHostQueue();
}
HIP_RETURN(ihipMemcpy(reinterpret_cast<void*>(dst), (const void*) src, sizeBytes, hipMemcpyHostToDevice,
@@ -807,7 +807,7 @@ hipError_t hipMemcpyDtoDAsync(hipDeviceptr_t dst, hipDeviceptr_t src, size_t siz
queue = hip::getNullStream();
} else {
hip::getNullStream()->finish();
queue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
queue = reinterpret_cast<hip::Stream*>(stream)->asHostQueue();
}
HIP_RETURN(ihipMemcpy(reinterpret_cast<void*>(dst), (const void*) src, sizeBytes, hipMemcpyDeviceToDevice,
@@ -825,7 +825,7 @@ hipError_t hipMemcpyDtoHAsync(void* dst, hipDeviceptr_t src, size_t sizeBytes,
queue = hip::getNullStream();
} else {
hip::getNullStream()->finish();
queue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
queue = reinterpret_cast<hip::Stream*>(stream)->asHostQueue();
}
HIP_RETURN(ihipMemcpy(reinterpret_cast<void*>(dst), (const void*) src, sizeBytes, hipMemcpyDeviceToHost,
@@ -928,7 +928,7 @@ hipError_t hipMemcpy2DAsync(void* dst, size_t dpitch, const void* src, size_t sp
queue = hip::getNullStream();
} else {
hip::getNullStream()->finish();
queue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
queue = reinterpret_cast<hip::Stream*>(stream)->asHostQueue();
}
HIP_RETURN(ihipMemcpy2D(dst, dpitch, src, spitch, width, height, kind, *queue, true));
@@ -1355,7 +1355,7 @@ hipError_t hipMemset2DAsync(void* dst, size_t pitch, int value,
queue = hip::getNullStream();
} else {
hip::getNullStream()->finish();
queue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
queue = reinterpret_cast<hip::Stream*>(stream)->asHostQueue();
}
HIP_RETURN(ihipMemset2D(dst, pitch, value, width, height, *queue, true));