Add test covergae for clCloneKernel with no args

Clone a kernel with no args and enqueue.
The test uses `test_kernel_empty` kernel program with no arguments.

Signed-off-by: Michael Rizkalla <[email protected]>
Co-authored-by: Vikas Katariya <[email protected]>
Co-authored-by: Ahmed Hesham <[email protected]>

Author: 2 people

test_conformance/api/test_clone_kernel.cpp

@@ -90,7 +90,10 @@ const char* clone_kernel_test_kernel[] = {
     __kernel void set_kernel_exec_info_kernel(int iarg, __global BufPtr* buffer)
     {
         buffer->store[0] = iarg;
-    })"
+    }
+    
+    __kernel void test_kernel_empty(){}
+    )"
 };
 
 typedef struct
@@ -674,6 +677,60 @@ int test_cloned_kernel_exec_info(cl_device_id deviceID, cl_context context,
     }
 }
 
+int test_empty_enqueue_helper(cl_command_queue queue, cl_kernel srcKernel)
+{
+    cl_int error;
+    size_t ndrange1 = 1;
+
+    // enqueue - srcKernel
+    error = clEnqueueNDRangeKernel(queue, srcKernel, 1, NULL, &ndrange1, NULL,
+                                   0, NULL, NULL);
+    test_error(error, "clEnqueueNDRangeKernel failed");
+
+    error = clFinish(queue);
+    test_error(error, "clFinish failed");
+
+    return TEST_PASS;
+}
+
+int test_cloned_kernel_empty_args(cl_device_id deviceID, cl_context context,
+                                  cl_command_queue queue, int num_elements)
+{
+    cl_int error;
+    clProgramWrapper program;
+    clKernelWrapper srcKernel;
+
+    // Create srcKernel to test with
+    error = create_single_kernel_helper(context, &program, &srcKernel, 1,
+                                        clone_kernel_test_kernel,
+                                        "test_kernel_empty");
+    test_error(error,
+               "Unable to create srcKernel for test_cloned_kernel_empty_args");
+
+    // enqueue - srcKernel
+    if (test_empty_enqueue_helper(queue, srcKernel) != 0)
+    {
+        test_fail("test_empty_enqueue_helper failed for srcKernel.\n");
+    }
+
+    // clone the srcKernel
+    clKernelWrapper cloneKernel_1 = clCloneKernel(srcKernel, &error);
+    test_error(error, "clCloneKernel failed for cloneKernel_1");
+
+    if (test_empty_enqueue_helper(queue, cloneKernel_1) != 0)
+    {
+        test_fail("test_empty_enqueue_helper failed for cloneKernel_1.\n");
+    }
+
+    // enqueue - srcKernel again
+    if (test_empty_enqueue_helper(queue, srcKernel) != 0)
+    {
+        test_fail("test_empty_enqueue_helper failed for srcKernel on retry.\n");
+    }
+
+    return TEST_PASS;
+}
+
 REGISTER_TEST_VERSION(clone_kernel, Version(2, 1))
 {
     if (test_buff_image_multiple_args(device, context, queue, num_elements)
@@ -694,5 +751,11 @@ REGISTER_TEST_VERSION(clone_kernel, Version(2, 1))
         test_fail("clCloneKernel test_cloned_kernel_exec_info failed.\n");
     }
 
+    if (test_cloned_kernel_empty_args(device, context, queue, num_elements)
+        == TEST_FAIL)
+    {
+        test_fail("clCloneKernel test_cloned_kernel_empty_args failed.\n");
+    }
+
     return TEST_PASS;
 }