ТРАССИРОВКА ЛУЧЕЙ НА CUDA Докладчик: Фролов В.А. (ВМиК МГУ, G&M Lab; Nvidia) Научный руководитель: Игнатенко А.В. (ВМиК МГУ, G&M Lab) Лекторы: Боресков А.В. (ВМиК МГУ) Харламов А.А. (ВМиК МГУ, Nvidia) План  OpenGL interoperability  RT – что, зачем и как?  Пересечение луча и треугольника  Ускоряющие структуры  Организация трассировки лучей  Ray marching  Задание OpenGL interop  OpenGL 2.0  VBO, PBO  OpenGL 3.0  VBO, PBO  texture  renderbuffer  OpenGL 4.0  ? OpenGL 2.0 interop  Pack  glReadPixels (…)  glGetTexImage (…)  Unpack  glDrawPixels (…)  glTexImage2D (…)  glTexSubImage2D (…) OpenGL 2.0 interop register, unregister PBO (CUDA) GLuint buffer_id; map, unmap Pointer (CUDA) uint* gpu_values; my_kernel <<< 64, 64>>>(gpu_values); OpenGL 2.0 interop glGenBuffers(1, &pixelBuffer); glBindBuffer (GL_PIXEL_UNPACK_BUFFER, pixelBuffer); glBufferData(GL_PIXEL_UNPACK_BUFFER, w*h*sizeof(int), screen_buffer, GL_STATIC_DRAW); cudaGLRegisterBufferObject (pixelBuffer); cudaGLMapBufferObject ((void**)&my_pointer, pixelBuffer); my_kernel<<<64, 64>>>(my_pointer); cudaGLUnmapBufferObject(pixelBuffer); cudaGLUnregisterBufferObject(pixelBuffer); glBindTexture(GL_TEXTURE_2D, tex_id); glTexImage2D (…, 0, …, w, h, 0, …, ..., (GLvoid*)0); OpenGL 3.0 interop  Старый API  сохраняется  Новый API CUDA Array; cudaArray *arr; cudaGraphicsResource FBO (renderbuffer) Pointer (CUDA) uint* gpu_values; OpenGL 3.0 interop GLuint tex_id; glGenTextures(1, & tex_id); … struct cudaGraphicsResource *tex_resource; cudaGraphicsGLRegisterImage (&tex_resource, tex_id, GL_TEXTURE_2D, cudaGraphicsMapFlagsReadOnly); cudaGraphicsMapResources (1, & tex_resource, 0); cudaArray *array_ptr; cudaGraphicsSubResourceGetMappedArray (&array_ptr, tex_resource, 0, 0); cudaMemcpyToArray(array_ptr,0, 0,dest,size,cudaMemcpyDeviceToDevice); cudaGraphicsUnmapResources(1, & tex_resource, 0); Ray Tracing Фотореалистичный синтез изображений POV-Ray Ray Tracing Фотореалистичный синтез изображений POV-Ray