Неправильный тип формата текстуры OpenGL для CL/GL-Interop? [закрыто]

Этот вопрос вряд ли поможет кому-либо из будущих посетителей; он относится только к небольшой географической области, конкретному моменту времени или чрезвычайно узкой ситуации, которая в целом не применима к всемирной аудитории Интернета. Чтобы получить помощь в более широком применении этого вопроса, посетите центр помощи.

Закрыто 7 лет назад.

Я пробую OpenCL-OpenGL interop для текстур на моем Geforce 330M с CUDA Toolkit 4.0.

Я хочу захватить кадр, использовать эти данные в качестве входного изображения (Image2D) для ядра OpenCL. Ядро должно обработать данные и записать их в Image2DGL, который является объектом изображения с присоединенной OpenGL текстурой. В основном это выглядит так:

 _______________      RGB        _______________
|               |    uint8*     |               |   CL_RGBA / CL_UNORM_INT8
|   Grabber     | ------------> |   Image2D     | -------------------------.
|   avcodec     |               |   [input]     |                          |
|_______________|               |_______________|                          |
                                                                           |    
                                                                           V
 _______________                 _______________                       _______________
|               |               |               |                     |               |
|   Texture     | ------------> |   Image2DGL   | <-----------------> |    Kernel     |
|_______________|               |   [output]    |                     |_______________|
                                |_______________|
Internal
Format: GL_RGBA
Format: GL_RGBA
Type: ?

Я инициализирую текстуру так:

GLuint tex = 0;

void initTexture( int width, int height )
{
    glGenTextures(1, &tex);
    glBindTexture(GL_TEXTURE_RECTANGLE, tex);
// now here is where I need assistance: The type parameter of the Texture (GL_FLOAT)
    glTexImage2D(GL_TEXTURE_RECTANGLE, 0, GL_RGBA, width, height, 0, GL_RGBA, GL_FLOAT, NULL );
}

EDIT:

Я могу иметь тип GL_UNSIGNED_INT.

Затем я создаю общее изображение (Image2DGL):

texMems.push_back(Image2DGL(clw->context, CL_MEM_READ_WRITE, GL_TEXTURE_RECTANGLE, 0, tex, &err));

Затем я создаю исходное изображение (input image):

ImageFormat format;
format.image_channel_data_type = CL_UNORM_INT8;
format.image_channel_order = CL_RGBA;
srcImgBuffer = Image2D(clw->context, CL_MEM_READ_WRITE, format, width, height, 0, NULL, &err);

В каждом цикле рендеринга я записываю данные в srcImgBuffer:

// write the frame to the image buffer
clw->queue.enqueueWriteImage(srcImgBuffer, CL_TRUE, origin, region, 0, 0, (void*)data, NULL, NULL);

Также я устанавливаю аргументы для ядра:

tex_kernel.setArg(0, texMems[0]);
tex_kernel.setArg(1, srcImgBuffer);
tex_kernel.setArg(2, width);
tex_kernel.setArg(3, height);

До и после я делаю получение и освобождение GL объектов. Тестирование ядра выглядит так:

__kernel void init_texture_kernel(__write_only image2d_t out, __read_only image2d_t in, int w, int h)
{
    const sampler_t smp = CLK_NORMALIZED_COORDS_FALSE | CLK_ADDRESS_CLAMP | CLK_FILTER_NEAREST;

    int2 coords = { get_global_id(0), get_global_id(1) };
    float4 pixel = read_imagef(in, smp, coords);
    float4 test = { (float)coords.x/(float)w , 0, 0, 1};
    write_imagef( out, coords, pixel );
}

Тип данных image_channel_data_type может быть прочитан как float в ядре и интерпретируется как нормализованное значение. Выходное изображение выглядит неправильно, у меня получилась нарезанная картинка (по линиям), очевидно из-за неправильной интерпретации данных. Как я уже говорил, я предполагаю, что ошибка кроется в инициализации типа текстуры. Я попробовал GL_FLOAT (поскольку в ядре я записываю изображение как float).

Results: Image as PPM dump from the decoder (left), Texture output scattered (right)

Слева - PPM из декодера, справа - то, что я получаю на выходе текстуры.

Если кто-то действительно читал до этого места: Есть ли у вас предложения относительно типа текстуры, чтобы решить проблему?

EDIT:

Если я привязываю захваченные кадры к текстуре напрямую, видео воспроизводится нормально. Значит, это должно быть как-то связано с интерфейсом CL-GL.

задан rdoubleui 30 January 2012 в 17:59

0 ответов

Другие вопросы по тегам:

opengl opencl texture2d libavcodec

Неправильный тип формата текстуры OpenGL для CL/GL-Interop? [закрыто]

0 ответов

Похожие вопросы: