Базовый адрес объекта памяти OpenCL

Это потому, что в модели OpenCL память хоста и память устройства не пересекаются. Указатель в памяти устройства не будет иметь значения на хосте.

Вы можете сопоставить буфер устройства с памятью хоста с помощью clEnqueueMapBuffer. Сопоставление синхронизирует устройство с хостом, а отключение синхронизирует обратно хост с устройством.

Обновить. Как вы объясняете в комментариях, вы хотите отправить древовидную структуру на графический процессор. Одним из решений было бы хранить все узлы дерева внутри массива, заменяя указатели на узлы индексами в массиве.

Как указал Эрик, необходимо учитывать два набора памяти: память хоста и память устройства. По сути, OpenCL пытается скрыть мельчайшие детали этого взаимодействия, вводя объект-буфер, с которым мы можем взаимодействовать в нашей программе на стороне хоста. Как вы отметили, проблема с этой методологией заключается в том, что она скрывает детали нашего устройства, когда мы хотим сделать что-то более сложное, чем разработчики OpenCL предполагали или допускали в своей области. Решение здесь - помнить, что ядра OpenCL используют C99 и что этот язык позволяет нам без проблем обращаться к указателям. Имея это в виду, мы можем просто потребовать, чтобы указатель хранился в беззнаковой целочисленной переменной, на которую позже можно будет ссылаться.

Ваша реализация была на правильном пути, но для завершения передачи требовалось немного больше синтаксиса C.

Ядро OpenCL:

// Kernel used to obtain pointer from target buffer
__kernel void mem_ptr(__global char * buffer, __global ulong * ptr)
{
    ptr[0] = &buffer[0];
}

// Kernel to demonstrate how to use that pointer again after we extract it.
__kernel void use_ptr(__global ulong * ptr)
{
    char * print_me = (char *)ptr[0];
    /* Code that uses all of our hard work */
    /* ... */
}

Хост-программа:

// Create the buffer that we want the device pointer from (target_buffer) 
//  and a place to store it (ptr_buffer).
cl_mem target_buffer = clCreateBuffer(context, CL_MEM_READ_WRITE, 
                                      MEM_SIZE * sizeof(char), NULL, &ret);
cl_mem ptr_buffer    = clCreateBuffer(context, CL_MEM_READ_WRITE,
                                      1 * sizeof(cl_ulong), NULL, &ret);

/* Setup the rest of our OpenCL program */    
/* .... */

// Setup our kernel arguments from the host...
ret = clSetKernelArg(kernel_mem_ptr, 0, sizeof(cl_mem), (void *)&target_buffer);
ret = clSetKernelArg(kernel_mem_ptr, 1, sizeof(cl_mem), (void *)&ptr_buffer);
ret = clEnqueueTask(command_queue, kernel_mem_ptr, 0, NULL, NULL);

// Now it's just a matter of storing the pointer where we want to use it for later.
ret = clEnqueueCopyBuffer(command_queue, ptr_buffer, dst_buffer, 0, 1 * sizeof(cl_ulong),
                          sizeof(cl_ulong), 0, NULL, NULL);
ret = clEnqueueReadBuffer(command_queue, ptr_buffer, CL_TRUE, 0,
                          1 * sizeof(cl_ulong), buffer_ptrs, 0, NULL, NULL);  

Вот и все. Теперь имейте в виду, что вам не обязательно использовать переменные типа char, которые я использовал; он работает для любого типа. Однако я бы рекомендовал использовать cl_ulong для хранения указателей. Это не имеет значения для устройств с менее чем 4 ГБ доступной памяти. Но для устройств с большим адресным пространством вам нужно использовать cl_ulong. Если вам абсолютно НЕОБХОДИМО сэкономить место на вашем устройстве, но у вас есть устройство с памятью> 4 ГБ, тогда вы можете создать структуру, которая может хранить нижние 32 LSB адреса в типе uint, при этом MSB хранится в мелкий тип.