Test clCloneKernel with no args

Extend test coverage by clonning kernel with no args and enqueue.
The test uses `test_kernel_empty` kernel program with no arguments.

Signed-off-by: Michael Rizkalla <michael.rizkalla@arm.com>
Co-authored-by: Vikas Katariya <vikas.katariya@arm.com>

Author: MichaelRizkalla-arm

test_conformance/api/test_clone_kernel.cpp

@@ -92,6 +92,7 @@ const char* clone_kernel_test_kernel[] = {
     "{\n"
     "    buffer->store[0] = iarg;\n"
     "}\n"
+    "__kernel void test_kernel_empty(){}\n"
 };
 
 typedef struct
@@ -681,6 +682,60 @@ int test_cloned_kernel_exec_info(cl_device_id deviceID, cl_context context,
     return TEST_PASS;
 }
 
+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) != TEST_PASS)
+    {
+        test_fail("test_empty_enqueue_helper failed for cloneKernel_1.\n");
+    }
+
+    // enqueue - srcKernel again
+    if (test_empty_enqueue_helper(queue, &srcKernel) != TEST_PASS)
+    {
+        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)
@@ -701,5 +756,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_PASS)
+    {
+        test_fail("clCloneKernel test_cloned_kernel_empty_args failed.\n");
+    }
+
     return TEST_PASS;
 }