Вычисление на массивах переменной длины в OpenCL

Question

Я использую OpenCL (Xcode, Intel GPU), и я пытаюсь реализовать ядро, которое вычисляет скользящие средние и отклонения. Я хочу передать в ядро ​​несколько двойных массивов различной длины. Возможно ли это реализовать, или мне нужно заполнить меньшие массивы нулями, чтобы все массивы имели одинаковый размер?

Я новичок в OpenCL и GPGPU, поэтому, пожалуйста, простите мое незнание любой номенклатуры.

Answer 1

Вы можете передать в ядро ​​любой буфер, ядру не нужно его использовать. Например, если ваше ядро ​​сокращает буфер, во время выполнения вы можете запросить количество рабочих элементов (предметов для уменьшения) с помощью get_global_size(0). Затем вызовите ядро ​​с соответствующими параметрами.

Пример (неоптимизированная):

__kernel reduce_step(__global float* data) 
{ 
    int id = get_global_id(0); 
    int size = get_global_size(0); 
    int size2 = size/2; 
    int size2p = (size+1)/2; 
    if(id<size2) //Only reduce up to size2, the odd element will remain in place 
     data[id] += data[id+size2p]; 
} 

Тогда вы можете назвать это так.

void reduce_me(std::vector<cl_float>& data){ 
    size_t size = data.size(); 

    //Copy to a buffer already created, equal or bigger size than data size 
    // ... TODO, check sizes of buffer or change the buffer set to the kernel args. 
    queue.enqueueWriteBuffer(buffer,CL_FALSE,0,sizeof(cl_float)*size,data.data()); 

    //Reduce until 1024 
    while(size > 1024){ 
     queue.enqueueNDRangeKernel(reduce_kernel,cl::NullRange,cl::NDRange(size),cl::NullRange); 
     size /= 2; 
    } 

    //Read out and trim 
    queue.enqueueReadBuffer(buffer,CL_TRUE,0,sizeof(cl_float)*size,data.data()); 
    data.resize(size); 
}