P4 to Git Change 1159349 by rili@rili_opencl_stg on 2015/06/09 12:52:32

EPR #419313 - Blit Kernel execution split
	                         Enabled flag GPU_ENABLE_LARGE_ALLOCATION
	                         Return error if global work size is larger than 32bits.

	Code Review#7664

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_execute.cpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.cpp#285 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpukernel.hpp#111 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gpuvirtual.cpp#365 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#234 edit


[ROCm/clr commit: aca7118ed4]

projects/clr/opencl/api/opencl/amdocl/cl_execute.cpp

@@ -205,6 +205,14 @@ RUNTIME_ENTRY(cl_int, clEnqueueNDRangeKernel, (
     if (global_work_size == NULL) {
         return CL_INVALID_VALUE;
     }
+    else {
+        // >32bits global work size is not supported.
+        for (cl_uint dim = 0; dim < work_dim; ++dim) {
+            if (global_work_size[dim] > static_cast<size_t>(0xffffffff)) {
+                return CL_INVALID_GLOBAL_WORK_SIZE;
+            }
+        }
+    }
 
     if (local_work_size == NULL) {
         static size_t zeroes[3] = { 0, 0, 0 };