86     cl_kernel kernel;  in test_get_kernel_info()  local
93 …if( create_single_kernel_helper( context, &program, &kernel, 1, sample_single_test_kernel, "sample…  in test_get_kernel_info()
98     error = clGetKernelInfo( kernel, CL_KERNEL_FUNCTION_NAME, 0, NULL, &paramSize );  in test_get_kernel_info()
99     test_error( error, "Unable to get kernel function name param size" );  in test_get_kernel_info()
102 …log_error( "ERROR: Kernel function name param returns invalid size (expected %d, got %d)\n", (int)…  in test_get_kernel_info()
106     error = clGetKernelInfo( kernel, CL_KERNEL_FUNCTION_NAME, sizeof( name ), name, NULL );  in test_get_kernel_info()
107     test_error( error, "Unable to get kernel function name" );  in test_get_kernel_info()
110 …log_error( "ERROR: Kernel function name returned invalid value (expected sample_test, got %s)\n", …  in test_get_kernel_info()
115     error = clGetKernelInfo( kernel, CL_KERNEL_NUM_ARGS, 0, NULL, &paramSize );  in test_get_kernel_info()
116     test_error( error, "Unable to get kernel arg count param size" );  in test_get_kernel_info()
119 …log_error( "ERROR: Kernel arg count param returns invalid size (expected %d, got %d)\n", (int)size…  in test_get_kernel_info()
123     error = clGetKernelInfo( kernel, CL_KERNEL_NUM_ARGS, sizeof( numArgs ), &numArgs, NULL );  in test_get_kernel_info()
124     test_error( error, "Unable to get kernel arg count" );  in test_get_kernel_info()
127 … log_error( "ERROR: Kernel arg count returned invalid value (expected %d, got %d)\n", 2, numArgs );  in test_get_kernel_info()
132     error = clGetKernelInfo( kernel, CL_KERNEL_REFERENCE_COUNT, 0, NULL, &paramSize );  in test_get_kernel_info()
133     test_error( error, "Unable to get kernel reference count param size" );  in test_get_kernel_info()
136 …log_error( "ERROR: Kernel reference count param returns invalid size (expected %d, got %d)\n", (in…  in test_get_kernel_info()
140 …error = clGetKernelInfo( kernel, CL_KERNEL_REFERENCE_COUNT, sizeof( numInstances ), &numInstances,…  in test_get_kernel_info()
141     test_error( error, "Unable to get kernel reference count" );  in test_get_kernel_info()
144     error = clGetKernelInfo( kernel, CL_KERNEL_PROGRAM, 0, NULL, &paramSize );  in test_get_kernel_info()
145     test_error( error, "Unable to get kernel program param size" );  in test_get_kernel_info()
148 …log_error( "ERROR: Kernel program param returns invalid size (expected %d, got %d)\n", (int)sizeof…  in test_get_kernel_info()
152     error = clGetKernelInfo( kernel, CL_KERNEL_PROGRAM, sizeof( testProgram ), &testProgram, NULL );  in test_get_kernel_info()
153     test_error( error, "Unable to get kernel program" );  in test_get_kernel_info()
156 …log_error( "ERROR: Kernel program returned invalid value (expected %p, got %p)\n", program, testPr…  in test_get_kernel_info()
160     error = clGetKernelInfo( kernel, CL_KERNEL_CONTEXT, sizeof( testContext ), &testContext, NULL );  in test_get_kernel_info()
161     test_error( error, "Unable to get kernel context" );  in test_get_kernel_info()
164 …log_error( "ERROR: Kernel context returned invalid value (expected %p, got %p)\n", context, testCo…  in test_get_kernel_info()
169     clReleaseKernel( kernel );  in test_get_kernel_info()
178     clKernelWrapper kernel;  in test_execute_kernel_local_sizes()  local
188     /* Create a kernel to test with */  in test_execute_kernel_local_sizes()
189 …if( create_single_kernel_helper( context, &program, &kernel, 1, sample_single_test_kernel, "sample…  in test_execute_kernel_local_sizes()
209     test_error( error, "Unable to set testing kernel data" );  in test_execute_kernel_local_sizes()
212     error = clSetKernelArg( kernel, 0, sizeof( streams[0] ), &streams[0] );  in test_execute_kernel_local_sizes()
213     test_error( error, "Unable to set kernel arguments" );  in test_execute_kernel_local_sizes()
214     error = clSetKernelArg( kernel, 1, sizeof( streams[1] ), &streams[1] );  in test_execute_kernel_local_sizes()
215     test_error( error, "Unable to set kernel arguments" );  in test_execute_kernel_local_sizes()
217     /* Test running the kernel and verifying it */  in test_execute_kernel_local_sizes()
219     error = get_max_common_work_group_size( context, kernel, threads[0], &localThreads[0] );  in test_execute_kernel_local_sizes()
222     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_execute_kernel_local_sizes()
223     test_error( error, "Kernel execution failed" );  in test_execute_kernel_local_sizes()
244     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_execute_kernel_local_sizes()
245     test_error( error, "Kernel execution failed" );  in test_execute_kernel_local_sizes()
266     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_execute_kernel_local_sizes()
267     test_error( error, "Kernel execution failed" );  in test_execute_kernel_local_sizes()
285     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_execute_kernel_local_sizes()
286     test_error( error, "Kernel execution failed" );  in test_execute_kernel_local_sizes()
309     clKernelWrapper kernel;  in test_set_kernel_arg_by_index()  local
319     /* Create a kernel to test with */  in test_set_kernel_arg_by_index()
320 …if( create_single_kernel_helper( context, &program, &kernel, 1, sample_single_test_kernel, "sample…  in test_set_kernel_arg_by_index()
340     test_error( error, "Unable to set testing kernel data" );  in test_set_kernel_arg_by_index()
343     error = clSetKernelArg(kernel, 1, sizeof( streams[1] ), &streams[1]);  in test_set_kernel_arg_by_index()
344     test_error( error, "Unable to set indexed kernel arguments" );  in test_set_kernel_arg_by_index()
345     error = clSetKernelArg(kernel, 0, sizeof( streams[0] ), &streams[0]);  in test_set_kernel_arg_by_index()
346     test_error( error, "Unable to set indexed kernel arguments" );  in test_set_kernel_arg_by_index()
349     /* Test running the kernel and verifying it */  in test_set_kernel_arg_by_index()
352     error = get_max_common_work_group_size( context, kernel, threads[0], &localThreads[0] );  in test_set_kernel_arg_by_index()
355     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_set_kernel_arg_by_index()
356     test_error( error, "Kernel execution failed" );  in test_set_kernel_arg_by_index()
379     clKernelWrapper kernel;  in test_set_kernel_arg_constant()  local
396 …log_error( "ERROR: Unable to test constant argument to kernel: max size of constant buffer is repo…  in test_set_kernel_arg_constant()
400     /* Create a kernel to test with */  in test_set_kernel_arg_constant()
401 …if( create_single_kernel_helper( context, &program, &kernel, 1, sample_const_test_kernel, "sample_…  in test_set_kernel_arg_constant()
428     error = clSetKernelArg(kernel, 0, sizeof( streams[0] ), &streams[0]);  in test_set_kernel_arg_constant()
429     test_error( error, "Unable to set indexed kernel arguments" );  in test_set_kernel_arg_constant()
430     error = clSetKernelArg(kernel, 1, sizeof( streams[1] ), &streams[1]);  in test_set_kernel_arg_constant()
431     test_error( error, "Unable to set indexed kernel arguments" );  in test_set_kernel_arg_constant()
432     error = clSetKernelArg(kernel, 2, sizeof( streams[2] ), &streams[2]);  in test_set_kernel_arg_constant()
433     test_error( error, "Unable to set indexed kernel arguments" );  in test_set_kernel_arg_constant()
436     /* Test running the kernel and verifying it */  in test_set_kernel_arg_constant()
439     error = get_max_common_work_group_size( context, kernel, threads[0], &localThreads[0] );  in test_set_kernel_arg_constant()
442     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_set_kernel_arg_constant()
443     test_error( error, "Kernel execution failed" );  in test_set_kernel_arg_constant()
466     clKernelWrapper kernel;  in test_set_kernel_arg_struct_array()  local
484     /* Create a kernel to test with */  in test_set_kernel_arg_struct_array()
485 …if( create_single_kernel_helper( context, &program, &kernel, 1, sample_struct_array_test_kernel, "…  in test_set_kernel_arg_struct_array()
508     error = clSetKernelArg(kernel, 0, sizeof( streams[0] ), &streams[0]);  in test_set_kernel_arg_struct_array()
509     test_error( error, "Unable to set indexed kernel arguments" );  in test_set_kernel_arg_struct_array()
510     error = clSetKernelArg(kernel, 1, sizeof( streams[1] ), &streams[1]);  in test_set_kernel_arg_struct_array()
511     test_error( error, "Unable to set indexed kernel arguments" );  in test_set_kernel_arg_struct_array()
513     /* Test running the kernel and verifying it */  in test_set_kernel_arg_struct_array()
516     error = get_max_common_work_group_size( context, kernel, threads[0], &localThreads[0] );  in test_set_kernel_arg_struct_array()
519     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_set_kernel_arg_struct_array()
520     test_error( error, "Kernel execution failed" );  in test_set_kernel_arg_struct_array()
543     cl_kernel  kernel[3];  in test_create_kernels_in_program()  local
549     /* Try getting the kernel count */  in test_create_kernels_in_program()
551     test_error( error, "Unable to get kernel count for built program" );  in test_create_kernels_in_program()
554 …log_error( "ERROR: Returned kernel count from clCreateKernelsInProgram is incorrect! (got %d, expe…  in test_create_kernels_in_program()
559     error = clCreateKernelsInProgram( program, 2, kernel, NULL );  in test_create_kernels_in_program()
561     clReleaseKernel( kernel[0] );  in test_create_kernels_in_program()
562     clReleaseKernel( kernel[1] );  in test_create_kernels_in_program()
572     clKernelWrapper kernel;  in test_kernel_global_constant()  local
582     /* Create a kernel to test with */  in test_kernel_global_constant()
583 …if( create_single_kernel_helper( context, &program, &kernel, 1, sample_const_global_test_kernel, "…  in test_kernel_global_constant()
605     error = clSetKernelArg(kernel, 0, sizeof( streams[0] ), &streams[0]);  in test_kernel_global_constant()
606     test_error( error, "Unable to set indexed kernel arguments" );  in test_kernel_global_constant()
607     error = clSetKernelArg(kernel, 1, sizeof( streams[1] ), &streams[1]);  in test_kernel_global_constant()
608     test_error( error, "Unable to set indexed kernel arguments" );  in test_kernel_global_constant()
611     /* Test running the kernel and verifying it */  in test_kernel_global_constant()
614     error = get_max_common_work_group_size( context, kernel, threads[0], &localThreads[0] );  in test_kernel_global_constant()
617     error = clEnqueueNDRangeKernel( queue, kernel, 1, NULL, threads, localThreads, 0, NULL, NULL );  in test_kernel_global_constant()
618     test_error( error, "Kernel execution failed" );  in test_kernel_global_constant()