|
@@ -145,11 +145,75 @@ RI_result debug_tick_func(int verbose, char *string, ...)
|
|
|
return RI_SUCCESS;
|
|
return RI_SUCCESS;
|
|
|
}
|
|
}
|
|
|
|
|
|
|
|
|
|
+const char* code_to_string(cl_int code) {
|
|
|
|
|
+ switch (code) {
|
|
|
|
|
+ case -1: return "CL_DEVICE_NOT_FOUND";
|
|
|
|
|
+ case -2: return "CL_DEVICE_NOT_AVAILABLE";
|
|
|
|
|
+ case -3: return "CL_COMPILER_NOT_AVAILABLE";
|
|
|
|
|
+ case -4: return "CL_MEM_OBJECT_ALLOCATION_FAILURE";
|
|
|
|
|
+ case -5: return "CL_OUT_OF_RESOURCES";
|
|
|
|
|
+ case -6: return "CL_OUT_OF_HOST_MEMORY";
|
|
|
|
|
+ case -7: return "CL_PROFILING_INFO_NOT_AVAILABLE";
|
|
|
|
|
+ case -8: return "CL_MEM_COPY_OVERLAP";
|
|
|
|
|
+ case -9: return "CL_IMAGE_FORMAT_MISMATCH";
|
|
|
|
|
+ case -10: return "CL_IMAGE_FORMAT_NOT_SUPPORTED";
|
|
|
|
|
+ case -11: return "CL_BUILD_PROGRAM_FAILURE";
|
|
|
|
|
+ case -12: return "CL_MAP_FAILURE";
|
|
|
|
|
+ case -13: return "CL_MISALIGNED_SUB_BUFFER_OFFSET";
|
|
|
|
|
+ case -14: return "CL_EXEC_STATUS_ERROR_FOR_EVENTS_IN_WAIT_LIST";
|
|
|
|
|
+ case -15: return "CL_COMPILE_PROGRAM_FAILURE";
|
|
|
|
|
+ case -16: return "CL_LINKER_NOT_AVAILABLE";
|
|
|
|
|
+ case -17: return "CL_LINK_PROGRAM_FAILURE";
|
|
|
|
|
+ case -18: return "CL_DEVICE_PARTITION_FAILED";
|
|
|
|
|
+ case -19: return "CL_KERNEL_ARG_INFO_NOT_AVAILABLE";
|
|
|
|
|
+ case -30: return "CL_INVALID_VALUE";
|
|
|
|
|
+ case -31: return "CL_INVALID_DEVICE_TYPE";
|
|
|
|
|
+ case -32: return "CL_INVALID_PLATFORM";
|
|
|
|
|
+ case -33: return "CL_INVALID_DEVICE";
|
|
|
|
|
+ case -34: return "CL_INVALID_CONTEXT";
|
|
|
|
|
+ case -35: return "CL_INVALID_QUEUE_PROPERTIES";
|
|
|
|
|
+ case -36: return "CL_INVALID_COMMAND_QUEUE";
|
|
|
|
|
+ case -37: return "CL_INVALID_HOST_PTR";
|
|
|
|
|
+ case -38: return "CL_INVALID_MEM_OBJECT";
|
|
|
|
|
+ case -39: return "CL_INVALID_IMAGE_FORMAT_DESCRIPTOR";
|
|
|
|
|
+ case -40: return "CL_INVALID_IMAGE_SIZE";
|
|
|
|
|
+ case -41: return "CL_INVALID_SAMPLER";
|
|
|
|
|
+ case -42: return "CL_INVALID_BINARY";
|
|
|
|
|
+ case -43: return "CL_INVALID_BUILD_OPTIONS";
|
|
|
|
|
+ case -44: return "CL_INVALID_PROGRAM";
|
|
|
|
|
+ case -45: return "CL_INVALID_PROGRAM_EXECUTABLE";
|
|
|
|
|
+ case -46: return "CL_INVALID_KERNEL_NAME";
|
|
|
|
|
+ case -47: return "CL_INVALID_KERNEL_DEFINITION";
|
|
|
|
|
+ case -48: return "CL_INVALID_KERNEL";
|
|
|
|
|
+ case -49: return "CL_INVALID_ARG_INDEX";
|
|
|
|
|
+ case -50: return "CL_INVALID_ARG_VALUE";
|
|
|
|
|
+ case -51: return "CL_INVALID_ARG_SIZE";
|
|
|
|
|
+ case -52: return "CL_INVALID_KERNEL_ARGS";
|
|
|
|
|
+ case -53: return "CL_INVALID_WORK_DIMENSION";
|
|
|
|
|
+ case -54: return "CL_INVALID_WORK_GROUP_SIZE";
|
|
|
|
|
+ case -55: return "CL_INVALID_WORK_ITEM_SIZE";
|
|
|
|
|
+ case -56: return "CL_INVALID_GLOBAL_OFFSET";
|
|
|
|
|
+ case -57: return "CL_INVALID_EVENT_WAIT_LIST";
|
|
|
|
|
+ case -58: return "CL_INVALID_EVENT";
|
|
|
|
|
+ case -59: return "CL_INVALID_OPERATION";
|
|
|
|
|
+ case -60: return "CL_INVALID_GL_OBJECT";
|
|
|
|
|
+ case -61: return "CL_INVALID_BUFFER_SIZE";
|
|
|
|
|
+ case -62: return "CL_INVALID_MIP_LEVEL";
|
|
|
|
|
+ case -63: return "CL_INVALID_GLOBAL_WORK_SIZE";
|
|
|
|
|
+ case -64: return "CL_INVALID_PROPERTY";
|
|
|
|
|
+ case -65: return "CL_INVALID_IMAGE_DESCRIPTOR";
|
|
|
|
|
+ case -66: return "CL_INVALID_COMPILER_OPTIONS";
|
|
|
|
|
+ case -67: return "CL_INVALID_LINKER_OPTIONS";
|
|
|
|
|
+ case -68: return "CL_INVALID_DEVICE_PARTITION_COUNT";
|
|
|
|
|
+ default: return "Unknown OpenCL error code";
|
|
|
|
|
+ }
|
|
|
|
|
+}
|
|
|
|
|
+
|
|
|
RI_result erchk_func(cl_int error, int line, char *file)
|
|
RI_result erchk_func(cl_int error, int line, char *file)
|
|
|
{
|
|
{
|
|
|
if (error != CL_SUCCESS)
|
|
if (error != CL_SUCCESS)
|
|
|
{
|
|
{
|
|
|
- debug(RI_DEBUG_LOW, "OpenCL Error: %d at line %d at file %s", error, line, file);
|
|
|
|
|
|
|
+ debug(RI_DEBUG_LOW, "OpenCL Error: %d (%s) at line %d at file %s", error, code_to_string(error), line, file);
|
|
|
|
|
|
|
|
RI_Stop(0);
|
|
RI_Stop(0);
|
|
|
}
|
|
}
|
|
@@ -1207,6 +1271,11 @@ for (int id_x = -width / 2; id_x < width / 2; id_x++){
|
|
|
// size_t local_size_2d[2] = {sqrt(local_size), sqrt(local_size)};
|
|
// size_t local_size_2d[2] = {sqrt(local_size), sqrt(local_size)};
|
|
|
size_t local_size_2d[2] = {16, 16};
|
|
size_t local_size_2d[2] = {16, 16};
|
|
|
|
|
|
|
|
|
|
+ if (!queue){
|
|
|
|
|
+ debug(RI_DEBUG_LOW, "Invalid Command Queue");
|
|
|
|
|
+ RI_Stop(1);
|
|
|
|
|
+ }
|
|
|
|
|
+
|
|
|
erchk(clEnqueueNDRangeKernel(queue, compiled_kernel_master, 2, NULL, size_2d, NULL, 0, NULL, NULL));
|
|
erchk(clEnqueueNDRangeKernel(queue, compiled_kernel_master, 2, NULL, size_2d, NULL, 0, NULL, NULL));
|
|
|
erchk(clFinish(queue));
|
|
erchk(clFinish(queue));
|
|
|
|
|
|