diff options
author | Luo <xionghu.luo@intel.com> | 2014-06-13 11:17:35 +0800 |
---|---|---|
committer | Zhigang Gong <zhigang.gong@intel.com> | 2014-06-13 16:58:40 +0800 |
commit | 1c4904c45b348c82d9befa40d7bbca0c7185cf98 (patch) | |
tree | ba009c9d99c05a6009ec5077dd9c702615ac59a7 /utests/runtime_marker_list.cpp | |
parent | f01bbc99fb4e26a4a923bea80f9e78dc5542b9aa (diff) | |
download | beignet-1c4904c45b348c82d9befa40d7bbca0c7185cf98.tar.gz |
add test case runtime_barrier_list and runtime_marker_list.
Reviewed-by: "Yang, Rong R" <rong.r.yang@intel.com>
Signed-off-by: Luo <xionghu.luo@intel.com>
Conflicts:
utests/CMakeLists.txt
Diffstat (limited to 'utests/runtime_marker_list.cpp')
-rw-r--r-- | utests/runtime_marker_list.cpp | 75 |
1 files changed, 75 insertions, 0 deletions
diff --git a/utests/runtime_marker_list.cpp b/utests/runtime_marker_list.cpp new file mode 100644 index 00000000..fc771569 --- /dev/null +++ b/utests/runtime_marker_list.cpp @@ -0,0 +1,75 @@ +#include "utest_helper.hpp" + +#define BUFFERSIZE 32*1024 +void runtime_marker_list(void) +{ + const size_t n = BUFFERSIZE; + cl_int cpu_src[BUFFERSIZE]; + cl_int cpu_src_2[BUFFERSIZE]; + cl_event ev[5]; + cl_int status = 0; + cl_int value = 34; + + // Setup kernel and buffers + OCL_CREATE_KERNEL("compiler_event"); + OCL_CREATE_BUFFER(buf[0], 0, BUFFERSIZE*sizeof(int), NULL); + OCL_CREATE_BUFFER(buf[1], 0, BUFFERSIZE*sizeof(int), NULL); + + for(cl_uint i=0; i<BUFFERSIZE; i++) + { + cpu_src[i] = 3; + cpu_src_2[i] = 5; + } + + OCL_CREATE_USER_EVENT(ev[0]); + + clEnqueueWriteBuffer(queue, buf[0], CL_TRUE, 0, BUFFERSIZE*sizeof(int), (void *)cpu_src, 1, &ev[0], &ev[1]); + + OCL_SET_ARG(0, sizeof(cl_mem), &buf[0]); + OCL_SET_ARG(1, sizeof(int), &value); + + // Run the kernel + globals[0] = n; + locals[0] = 32; + + clEnqueueNDRangeKernel(queue, kernel, 1, NULL, globals, locals, 2, &ev[0], &ev[2]); + + for (cl_uint i = 0; i != sizeof(ev) / sizeof(cl_event); ++i) { + clGetEventInfo(ev[i], CL_EVENT_COMMAND_EXECUTION_STATUS, sizeof(status), &status, NULL); + OCL_ASSERT(status >= CL_SUBMITTED); + } + + + buf_data[0] = clEnqueueMapBuffer(queue, buf[0], CL_TRUE, 0, 0, BUFFERSIZE*sizeof(int), 1, &ev[2], NULL, NULL); + + clEnqueueMarkerWithWaitList(queue, 0, NULL, &ev[3]); + + clEnqueueWriteBuffer(queue, buf[1], CL_TRUE, 0, BUFFERSIZE*sizeof(int), (void *)cpu_src_2, 0, NULL, &ev[4]); + + OCL_FINISH(); + clGetEventInfo(ev[4], CL_EVENT_COMMAND_EXECUTION_STATUS, sizeof(status), &status, NULL); + OCL_ASSERT(status == CL_COMPLETE); + + OCL_SET_USER_EVENT_STATUS(ev[0], CL_COMPLETE); + + clGetEventInfo(ev[0], CL_EVENT_COMMAND_EXECUTION_STATUS, sizeof(status), &status, NULL); + OCL_ASSERT(status == CL_COMPLETE); + + OCL_FINISH(); + + for (cl_uint i = 0; i != sizeof(ev) / sizeof(cl_event); ++i) { + clGetEventInfo(ev[i], CL_EVENT_COMMAND_EXECUTION_STATUS, sizeof(status), &status, NULL); + OCL_ASSERT(status <= CL_COMPLETE); + } + + for (uint32_t i = 0; i < n; ++i) { + OCL_ASSERT(((int*)buf_data[0])[i] == (int)value + 0x3); + } + clEnqueueUnmapMemObject(queue, buf[0], buf_data[0], 0, NULL, NULL); + + for (cl_uint i = 0; i != sizeof(ev) / sizeof(cl_event); ++i) { + clReleaseEvent(ev[i]); + } +} + +MAKE_UTEST_FROM_FUNCTION(runtime_marker_list); |