ahmed/OpenCL-CTS
1
0
Fork 0
mirror of https://github.com/KhronosGroup/OpenCL-CTS.git synced 2026-03-19 06:09:01 +00:00
Code Issues Packages Projects Releases Wiki Activity

Add helper macros for kernel creation and enqueuing, and add them to SimpleSemaphore1

Browse Source
This commit is contained in:
paulfradgley
2025-10-28 10:46:37 +00:00
committed by GitHub
parent 62972418c3
commit 51af68398c
1 changed files with 45 additions and 2 deletions
Download Patch File Download Diff File Expand all files Collapse all files

47
test_conformance/extensions/cl_khr_semaphore/test_semaphores.cpp
View File

@@ -26,6 +26,42 @@ namespace {
const char* source = "__kernel void empty() {}"; const char* source = "__kernel void empty() {}";
const char* source_write_int = "__kernel void write_int(int* out, int val) { out[0] = val; }"
#define CREATE_KERNEL \
clProgramWrapper program_write_int; \
clKernelWrapper kernel_write_int; \
err = create_single_kernel_helper(context, &program_write_int, &kernel_write_int, 1, \
&source_write_int, "write_int"); \
test_error(err, "Could not create kernel")
#define CREATE_BUFFER \
int int_val = 45; \
clMemWrapper buffer_write_int = clCreateBuffer(context, CL_MEM_READ_WRITE, \
sizeof(cl_int), nullptr, &error); \
test_error(error, "clCreateBuffer failed")
#define ENQUEUE_KERNEL(QUEUE, NUM_LIST, WAITLIST) \
error = clSetKernelArg(kernel_write_int, 0, sizeof(buffer_write_int), &buffer_write_int); \
test_error(error, "clSetKernelArg failed"); \
error = clSetKernelArg(kernel_write_int, 1, sizeof(int), &int_val); \
test_error(error, "clSetKernelArg failed"); \
size_t threads = 1; \
err = clEnqueueNDRangeKernel(QUEUE, kernel_write_int, 1, nullptr, \
&threads, nullptr, NUM_LIST, WAITLIST, nullptr); \
test_error(err, "clEnqueueNDRangeKernel failed")
#define ENQUEUE_KERNEL_WITH_EVENT(QUEUE, NUM_LIST, WAITLIST, EVENT) \
error = clSetKernelArg(kernel_write_int, 0, sizeof(buffer_write_int), &buffer_write_int); \
test_error(error, "clSetKernelArg failed"); \
error = clSetKernelArg(kernel_write_int, 1, sizeof(int), &int_val); \
test_error(error, "clSetKernelArg failed"); \
size_t threads = 1; \
clEventWrapper EVENT; \
err = clEnqueueNDRangeKernel(QUEUE, kernel_write_int, 1, nullptr, \
&threads, nullptr, NUM_LIST, WAITLIST, &EVENT); \
test_error(err, "clEnqueueNDRangeKernel failed")
struct SimpleSemaphore1 : public SemaphoreTestBase struct SimpleSemaphore1 : public SemaphoreTestBase
{ {
SimpleSemaphore1(cl_device_id device, cl_context context, SimpleSemaphore1(cl_device_id device, cl_context context,
@@ -41,6 +77,9 @@ struct SimpleSemaphore1 : public SemaphoreTestBase
context, device, CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE, &err); context, device, CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE, &err);
test_error(err, "Could not create command queue"); test_error(err, "Could not create command queue");
CREATE_KERNEL;
CREATE_BUFFER;
// Create semaphore // Create semaphore
cl_semaphore_properties_khr sema_props[] = { cl_semaphore_properties_khr sema_props[] = {
static_cast<cl_semaphore_properties_khr>(CL_SEMAPHORE_TYPE_KHR), static_cast<cl_semaphore_properties_khr>(CL_SEMAPHORE_TYPE_KHR),
@@ -52,10 +91,12 @@ struct SimpleSemaphore1 : public SemaphoreTestBase
clCreateSemaphoreWithPropertiesKHR(context, sema_props, &err); clCreateSemaphoreWithPropertiesKHR(context, sema_props, &err);
test_error(err, "Could not create semaphore"); test_error(err, "Could not create semaphore");
ENQUEUE_KERNEL_WITH_EVENT(queue, 0, nullptr, write_int_event);
// Signal semaphore // Signal semaphore
clEventWrapper signal_event; clEventWrapper signal_event;
err = clEnqueueSignalSemaphoresKHR(queue, 1, semaphore, nullptr, 0, err = clEnqueueSignalSemaphoresKHR(queue, 1, semaphore, nullptr, 1,
nullptr, &signal_event); &write_int_event, &signal_event);
test_error(err, "Could not signal semaphore"); test_error(err, "Could not signal semaphore");
// Wait semaphore // Wait semaphore
@@ -63,6 +104,8 @@ struct SimpleSemaphore1 : public SemaphoreTestBase
err = clEnqueueWaitSemaphoresKHR(queue, 1, semaphore, nullptr, 0, err = clEnqueueWaitSemaphoresKHR(queue, 1, semaphore, nullptr, 0,
nullptr, &wait_event); nullptr, &wait_event);
test_error(err, "Could not wait semaphore"); test_error(err, "Could not wait semaphore");
ENQUEUE_KERNEL(queue, 1, &wait_event);
// Finish // Finish
err = clFinish(queue); err = clFinish(queue);