OpenCL: Как передать параметр с размером больше max_parameter_size?

Question

Из любопытства, чтобы найти максимальный размер параметра, который я могу передать при вызове ядра OpenCL, я обнаружил, что могу передать массив размером больше максимального размера. Вот что происходит: (кстати, я использую pyopencl)

>>> plat = cl.get_platforms() 
>>> dev = plat[0].get_devices(cl.device_type.ALL) 
>>> dev[0] 
<pyopencl.Device 'Juniper' on 'AMD Accelerated Parallel Processing' at 0x58fde60> 
>>> dev[0].max_parameter_size 
1024 

На поиск Google, я узнал, что 1024 в байтах. (я забыл, где это было сказано, я думаю, что в форуме Nvidia.)

Теперь я побежал этот сценарий:

import pyopencl as cl 
import numpy as np 

plat = cl.get_platforms() 
dev = plat[0].get_devices(cl.device_type.ALL) 
ctx = ctx = cl.Context([ dev[0] ]) 
cq = cl.CommandQueue(ctx) 

kernel = """ 
__kernel void test(__global int* A, __global int* B){ 
const int id = get_global_id(0); 
B[ id ] = A[ id ]; 
barrier(CLK_GLOBAL_MEM_FENCE); 
} 
""" 

prg = cl.Program(ctx, kernel).build() 

A = np.ones((2**18,), dtype = np.int32) 
B = np.zeros_like(A) 

A_buf = cl.Buffer(ctx, cl.mem_flags.READ_ONLY|cl.mem_flags.COPY_HOST_PTR, hostbuf = A) 
B_buf = cl.Buffer(ctx, cl.mem_flags.WRITE_ONLY, B.nbytes) 

перед вызовом ядра, я сделал следующее:

>>> A.nonzero()[0].shape 
(262144,) 
>>> B.nonzero()[0].shape 
(0,) 

Тогда я назвал ядро ​​и проверены на ненулевых элементов в B:

>>> prg.test(cq, A.shape, A_buf, B_buf).wait() 
>>> cl.enqueue_copy(cq, B, B_buf) 
>>> B.nonzero()[0].shape 
(262144,) 

Так, кл Раньше я могу отправить и прочитать массив размером более cl.max_parameter_size. Как это возможно? или Где я иду не так?

Answer 1

CL_DEVICE_MAX_PARAMETER_SIZE относится к максимальному размеру параметра ядра, переданного clSetKernelArg. См. CL_DEVICE_MAX_MEM_ALLOC_SIZE и CL_DEVICE_GLOBAL_MEM_SIZE в clGetDeviceInfo.