This is not comply with the spec. Please check the OpenCL 1.2 spec 5.7.3 which contains the description of the function clGetKernelWorkGroupInfo(). You will find the following for the macro CL_KERNEL_GLOBAL_WORK_SIZE in "Table 5.16 clGetKernelWorkGroupInfo parameter queries".
This provides a mechanism for the application to query the maximum global size that can be used to execute a kernel (i.e. global_work_size argument to clEnqueueNDRangeKernel) on a custom device given by device or a built-in kernel on an OpenCL device given by device. It is not used to get current global work group size. On Tue, Sep 09, 2014 at 09:36:58AM +0800, [email protected] wrote: > From: Luo Xionghu <[email protected]> > > add CL_KERNEL_GLOBAL_WORK_SIZE option for clGetKernelWorkGroupInfo. > > Signed-off-by: Luo Xionghu <[email protected]> > --- > src/cl_api.c | 3 +++ > src/cl_device_id.c | 1 + > src/cl_kernel.h | 2 ++ > 3 files changed, 6 insertions(+) > > diff --git a/src/cl_api.c b/src/cl_api.c > index 2370dc0..07e8954 100644 > --- a/src/cl_api.c > +++ b/src/cl_api.c > @@ -2965,6 +2965,9 @@ clEnqueueNDRangeKernel(cl_command_queue command_queue, > } > } > > + for (i = 0; i < work_dim; ++i) > + kernel->global_work_sz[i] = fixed_global_sz[i]; > + > /* Do device specific checks are enqueue the kernel */ > err = cl_command_queue_ND_range(command_queue, > kernel, > diff --git a/src/cl_device_id.c b/src/cl_device_id.c > index a0f0c99..6bd80a6 100644 > --- a/src/cl_device_id.c > +++ b/src/cl_device_id.c > @@ -573,6 +573,7 @@ cl_get_kernel_workgroup_info(cl_kernel kernel, > } > DECL_FIELD(COMPILE_WORK_GROUP_SIZE, kernel->compile_wg_sz) > DECL_FIELD(PRIVATE_MEM_SIZE, kernel->stack_size) > + DECL_FIELD(GLOBAL_WORK_SIZE, kernel->global_work_sz) > default: > return CL_INVALID_VALUE; > }; > diff --git a/src/cl_kernel.h b/src/cl_kernel.h > index f4ed8d3..85a997d 100644 > --- a/src/cl_kernel.h > +++ b/src/cl_kernel.h > @@ -59,6 +59,8 @@ struct _cl_kernel { > cl_ulong local_mem_sz; /* local memory size specified in kernel args. > */ > size_t compile_wg_sz[3]; /* Required workgroup size by > __attribute__((reqd_work_gro > up_size(X, Y, Z))) qualifier.*/ > + size_t global_work_sz[3]; /* maximum global size that can be used to > execute a kernel > + (i.e. global_work_size argument to > clEnqueueNDRangeKernel.)*/ > size_t stack_size; /* stack size per work item. */ > cl_argument *args; /* To track argument setting */ > uint32_t arg_n:31; /* Number of arguments */ > -- > 1.7.9.5 > > _______________________________________________ > Beignet mailing list > [email protected] > http://lists.freedesktop.org/mailman/listinfo/beignet _______________________________________________ Beignet mailing list [email protected] http://lists.freedesktop.org/mailman/listinfo/beignet
