Как скопировать сгенерированный CUDA PBO в текстуру с Mipmapping - PullRequest
Новая
       42

Как скопировать сгенерированный CUDA PBO в текстуру с Mipmapping

3 голосов
/ 07 октября 2010

Я пытаюсь скопировать PBO в текстуру с включенным автоматическим отображением, но создается впечатление, что генерируется только текстура верхнего уровня (другими словами, никакого отображения не происходит).

Я строю PBO, используя 

//Generate a buffer ID called a PBO (Pixel Buffer Object)
glGenBuffers(1, pbo);
//Make this the current UNPACK buffer
glBindBuffer(GL_PIXEL_UNPACK_BUFFER, *pbo);
//Allocate data for the buffer. 4-channel 8-bit image
glBufferData(GL_PIXEL_UNPACK_BUFFER, size_tex_data, NULL, GL_DYNAMIC_COPY);
cudaGLRegisterBufferObject(*pbo);

, и строю текстуру, используя 

// Enable Texturing
glEnable(GL_TEXTURE_2D);

// Generate a texture identifier
glGenTextures(1,textureID);

// Make this the current texture (remember that GL is state-based)
glBindTexture( GL_TEXTURE_2D, *textureID);

// Allocate the texture memory. The last parameter is NULL since we only
// want to allocate memory, not initialize it
glTexImage2D(GL_TEXTURE_2D, 0, GL_RGBA_FLOAT32_ATI, size_x, size_y, 0,
GL_RGBA, GL_FLOAT, NULL);

// Must set the filter mode, GL_LINEAR enables interpolation when scaling
glTexParameteri(GL_TEXTURE_2D, GL_TEXTURE_WRAP_S, GL_REPEAT);
glTexParameteri(GL_TEXTURE_2D, GL_TEXTURE_WRAP_T, GL_REPEAT);
glTexParameteri(GL_TEXTURE_2D,GL_TEXTURE_MIN_FILTER,GL_LINEAR_MIPMAP_LINEAR);
glTexParameteri(GL_TEXTURE_2D,GL_TEXTURE_MAG_FILTER,GL_LINEAR);
glTexParameteri(GL_TEXTURE_2D, GL_GENERATE_MIPMAP, GL_TRUE);

Позже в ядре я модифицирую PBO, используя что-то вроде: 

float4* aryPtr = NULL;
cudaGLMapBufferObject((void**)&aryPtr, *pbo);

//Pixel* gpuPixelsRawPtr = thrust::raw_pointer_cast(&gpuPixels[0]);
//... do some cuda stuff to aryPtr ...

//If we don't unmap the PBO then OpenGL won't be able to use it:
cudaGLUnmapBufferObject(*pbo);

Теперь, прежде чем я начну рисовать на экране с использованием текстуры, сгенерированной выше, я вызываю: (обратите внимание, что rtMipmapTex = * textureID выше и rtResultPBO = * pbo выше) 

glEnable(GL_DEPTH);
glEnable(GL_TEXTURE_2D);
glBindTexture(GL_TEXTURE_2D, rtMipmapTex);
glBindBuffer(GL_PIXEL_UNPACK_BUFFER, rtResultPBO);
glTexSubImage2D(GL_TEXTURE_2D, 0, 0, 0, canvasSize.x, canvasSize.y, GL_RGBA, GL_FLOAT, NULL);

Это все отлично работает и корректно отображает текстуру.Но если я изменю эту последнюю строку на 

glTexSubImage2D(GL_TEXTURE_2D, 1, 0, 0, canvasSize.x, canvasSize.y, GL_RGBA, GL_FLOAT, NULL);

, которая, насколько я понимаю, должна показать мне первый уровень вместо текстуры нулевого уровня в пирамиде текстуры, япросто получите чистую белую текстуру.

Как скопировать текстуру из PBO таким образом, чтобы сработало автоматическое отображение?

Спасибо.

1 Ответ

3 голосов
/ 07 октября 2010

Я был идиотом. Приведенный выше код работает отлично, проблема была в том, что 

glTexSubImage2D(GL_TEXTURE_2D, 1, 0, 0, canvasSize.x, canvasSize.y, GL_RGBA, GL_FLOAT, NULL);

не выбирает уровень mipmap из текстуры, он выбирает его из pbo, который не является mipmapped. Вместо этого вы можете отобразить конкретный уровень с отображением: 

glTexEnvi(GL_TEXTURE_FILTER_CONTROL,GL_TEXTURE_LOD_BIAS, 4);
...