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

P4 to Git Change 1537228 by skudchad@skudchad_test2_win_opencl on 2018/04/05 14:53:31

Browse Source 
SWDEV-145570 - [HIP] -  Add HIP Memory, texture, surface, context api skeletons

	ReviewBoardURL = http://ocltc.amd.com/reviews/r/14565/diff/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#7 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_surface.cpp#1 add
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#1 add


[ROCm/clr commit: 6fc37f7147]
This commit is contained in:
foreman
2018-04-05 15:02:43 -04:00
parent 92c69c53f1
commit 2bf865a669
7 changed files with 496 additions and 136 deletions
Download Patch File Download Diff File Expand all files Collapse all files
projects/clr/hipamd/api/hip/hip_stream.cpp
+32 -12
View File
@@ -24,8 +24,7 @@ THE SOFTWARE.
#include "hip_internal.hpp"
static hipError_t ihipStreamCreateWithFlags(hipStream_t *stream, unsigned int flags)
{
static hipError_t ihipStreamCreateWithFlags(hipStream_t *stream, unsigned int flags) {
assert(flags == 0); // we don't handle flags yet
amd::Device* device = g_context->devices()[0];
@@ -43,24 +42,21 @@ static hipError_t ihipStreamCreateWithFlags(hipStream_t *stream, unsigned int fl
return hipSuccess;
}
hipError_t hipStreamCreateWithFlags(hipStream_t *stream, unsigned int flags)
{
hipError_t hipStreamCreateWithFlags(hipStream_t *stream, unsigned int flags) {
HIP_INIT_API(stream, flags);
return ihipStreamCreateWithFlags(stream, flags);
}
hipError_t hipStreamCreate(hipStream_t *stream)
{
hipError_t hipStreamCreate(hipStream_t *stream) {
HIP_INIT_API(stream);
return ihipStreamCreateWithFlags(stream, hipStreamDefault);
}
hipError_t hipStreamGetFlags(hipStream_t stream, unsigned int *flags)
{
hipError_t hipStreamGetFlags(hipStream_t stream, unsigned int *flags) {
HIP_INIT_API(stream, flags);
assert(0 && "Unimplemented");
@@ -69,8 +65,7 @@ hipError_t hipStreamGetFlags(hipStream_t stream, unsigned int *flags)
}
hipError_t hipStreamSynchronize(hipStream_t stream)
{
hipError_t hipStreamSynchronize(hipStream_t stream) {
HIP_INIT_API(stream);
amd::HostQueue* hostQueue = as_amd(reinterpret_cast<cl_command_queue>(stream))->asHostQueue();
@@ -84,8 +79,7 @@ hipError_t hipStreamSynchronize(hipStream_t stream)
}
hipError_t hipStreamDestroy(hipStream_t stream)
{
hipError_t hipStreamDestroy(hipStream_t stream) {
HIP_INIT_API(stream);
as_amd(reinterpret_cast<cl_command_queue>(stream))->release();
@@ -94,3 +88,29 @@ hipError_t hipStreamDestroy(hipStream_t stream)
}
hipError_t hipStreamWaitEvent(hipStream_t stream, hipEvent_t event, unsigned int flags) {
HIP_INIT_API(stream, event, flags);
assert(0 && "Unimplemented");
return hipErrorUnknown;
}
hipError_t hipStreamQuery(hipStream_t stream) {
HIP_INIT_API(stream);
assert(0 && "Unimplemented");
return hipErrorUnknown;
}
hipError_t hipStreamAddCallback(hipStream_t stream, hipStreamCallback_t callback, void* userData,
unsigned int flags) {
HIP_INIT_API(stream, callback, userData, flags);
assert(0 && "Unimplemented");
return hipErrorUnknown;
}