mirror of
https://github.com/obsproject/obs-studio.git
synced 2024-09-20 13:08:50 +02:00
5780f3f177
Summary: - Prefix all graphics subsystem names with gs_ or GS_ - Unsquish funciton names (for example _setfloat to _set_float) - Changed create functions to be more consistent with the rest of the API elsewhere. For exmaple, instead of gs_create_texture/gs_texture_destroy, it's now gs_texture_create/gs_texture_destroy - Renamed gs_stencil_op enum to gs_stencil_op_type From: To: ----------------------------------------------------------- tvertarray gs_tvertarray vb_data gs_vb_data vbdata_create gs_vbdata_create vbdata_destroy gs_vbdata_destroy shader_param gs_shader_param gs_effect gs_effect effect_technique gs_effect_technique effect_pass gs_effect_pass effect_param gs_effect_param texture_t gs_texture_t stagesurf_t gs_stagesurf_t zstencil_t gs_zstencil_t vertbuffer_t gs_vertbuffer_t indexbuffer_t gs_indexbuffer_t samplerstate_t gs_samplerstate_t swapchain_t gs_swapchain_t texrender_t gs_texrender_t shader_t gs_shader_t sparam_t gs_sparam_t effect_t gs_effect_t technique_t gs_technique_t eparam_t gs_eparam_t device_t gs_device_t graphics_t graphics_t shader_param_type gs_shader_param_type SHADER_PARAM_UNKNOWN GS_SHADER_PARAM_UNKNOWN SHADER_PARAM_BOOL GS_SHADER_PARAM_BOOL SHADER_PARAM_FLOAT GS_SHADER_PARAM_FLOAT SHADER_PARAM_INT GS_SHADER_PARAM_INT SHADER_PARAM_STRING GS_SHADER_PARAM_STRING SHADER_PARAM_VEC2 GS_SHADER_PARAM_VEC2 SHADER_PARAM_VEC3 GS_SHADER_PARAM_VEC3 SHADER_PARAM_VEC4 GS_SHADER_PARAM_VEC4 SHADER_PARAM_MATRIX4X4 GS_SHADER_PARAM_MATRIX4X4 SHADER_PARAM_TEXTURE GS_SHADER_PARAM_TEXTURE shader_param_info gs_shader_param_info shader_type gs_shader_type SHADER_VERTEX GS_SHADER_VERTEX SHADER_PIXEL GS_SHADER_PIXEL shader_destroy gs_shader_destroy shader_numparams gs_shader_get_num_params shader_getparambyidx gs_shader_get_param_by_idx shader_getparambyname gs_shader_get_param_by_name shader_getviewprojmatrix gs_shader_get_viewproj_matrix shader_getworldmatrix gs_shader_get_world_matrix shader_getparaminfo gs_shader_get_param_info shader_setbool gs_shader_set_bool shader_setfloat gs_shader_set_float shader_setint gs_shader_set_int shader_setmatrix3 gs_shader_setmatrix3 shader_setmatrix4 gs_shader_set_matrix4 shader_setvec2 gs_shader_set_vec2 shader_setvec3 gs_shader_set_vec3 shader_setvec4 gs_shader_set_vec4 shader_settexture gs_shader_set_texture shader_setval gs_shader_set_val shader_setdefault gs_shader_set_default effect_property_type gs_effect_property_type EFFECT_NONE GS_EFFECT_NONE EFFECT_BOOL GS_EFFECT_BOOL EFFECT_FLOAT GS_EFFECT_FLOAT EFFECT_COLOR GS_EFFECT_COLOR EFFECT_TEXTURE GS_EFFECT_TEXTURE effect_param_info gs_effect_param_info effect_destroy gs_effect_destroy effect_gettechnique gs_effect_get_technique technique_begin gs_technique_begin technique_end gs_technique_end technique_beginpass gs_technique_begin_pass technique_beginpassbyname gs_technique_begin_pass_by_name technique_endpass gs_technique_end_pass effect_numparams gs_effect_get_num_params effect_getparambyidx gs_effect_get_param_by_idx effect_getparambyname gs_effect_get_param_by_name effect_updateparams gs_effect_update_params effect_getviewprojmatrix gs_effect_get_viewproj_matrix effect_getworldmatrix gs_effect_get_world_matrix effect_getparaminfo gs_effect_get_param_info effect_setbool gs_effect_set_bool effect_setfloat gs_effect_set_float effect_setint gs_effect_set_int effect_setmatrix4 gs_effect_set_matrix4 effect_setvec2 gs_effect_set_vec2 effect_setvec3 gs_effect_set_vec3 effect_setvec4 gs_effect_set_vec4 effect_settexture gs_effect_set_texture effect_setval gs_effect_set_val effect_setdefault gs_effect_set_default texrender_create gs_texrender_create texrender_destroy gs_texrender_destroy texrender_begin gs_texrender_begin texrender_end gs_texrender_end texrender_reset gs_texrender_reset texrender_gettexture gs_texrender_get_texture GS_BUILDMIPMAPS GS_BUILD_MIPMAPS GS_RENDERTARGET GS_RENDER_TARGET gs_device_name gs_get_device_name gs_device_type gs_get_device_type gs_entercontext gs_enter_context gs_leavecontext gs_leave_context gs_getcontext gs_get_context gs_renderstart gs_render_start gs_renderstop gs_render_stop gs_rendersave gs_render_save gs_getinput gs_get_input gs_geteffect gs_get_effect gs_create_effect_from_file gs_effect_create_from_file gs_create_effect gs_effect_create gs_create_vertexshader_from_file gs_vertexshader_create_from_file gs_create_pixelshader_from_file gs_pixelshader_create_from_file gs_create_texture_from_file gs_texture_create_from_file gs_resetviewport gs_reset_viewport gs_set2dmode gs_set_2d_mode gs_set3dmode gs_set_3d_mode gs_create_swapchain gs_swapchain_create gs_getsize gs_get_size gs_getwidth gs_get_width gs_getheight gs_get_height gs_create_texture gs_texture_create gs_create_cubetexture gs_cubetexture_create gs_create_volumetexture gs_voltexture_create gs_create_zstencil gs_zstencil_create gs_create_stagesurface gs_stagesurface_create gs_create_samplerstate gs_samplerstate_create gs_create_vertexshader gs_vertexshader_create gs_create_pixelshader gs_pixelshader_create gs_create_vertexbuffer gs_vertexbuffer_create gs_create_indexbuffer gs_indexbuffer_create gs_gettexturetype gs_get_texture_type gs_load_defaultsamplerstate gs_load_default_samplerstate gs_getvertexshader gs_get_vertex_shader gs_getpixelshader gs_get_pixel_shader gs_getrendertarget gs_get_render_target gs_getzstenciltarget gs_get_zstencil_target gs_setrendertarget gs_set_render_target gs_setcuberendertarget gs_set_cube_render_target gs_beginscene gs_begin_scene gs_draw gs_draw gs_endscene gs_end_scene gs_setcullmode gs_set_cull_mode gs_getcullmode gs_get_cull_mode gs_enable_depthtest gs_enable_depth_test gs_enable_stenciltest gs_enable_stencil_test gs_enable_stencilwrite gs_enable_stencil_write gs_blendfunction gs_blend_function gs_depthfunction gs_depth_function gs_stencilfunction gs_stencil_function gs_stencilop gs_stencil_op gs_setviewport gs_set_viewport gs_getviewport gs_get_viewport gs_setscissorrect gs_set_scissor_rect gs_create_texture_from_iosurface gs_texture_create_from_iosurface gs_create_gdi_texture gs_texture_create_gdi gs_is_compressed_format gs_is_compressed_format gs_num_total_levels gs_get_total_levels texture_setimage gs_texture_set_image cubetexture_setimage gs_cubetexture_set_image swapchain_destroy gs_swapchain_destroy texture_destroy gs_texture_destroy texture_getwidth gs_texture_get_width texture_getheight gs_texture_get_height texture_getcolorformat gs_texture_get_color_format texture_map gs_texture_map texture_unmap gs_texture_unmap texture_isrect gs_texture_is_rect texture_getobj gs_texture_get_obj cubetexture_destroy gs_cubetexture_destroy cubetexture_getsize gs_cubetexture_get_size cubetexture_getcolorformat gs_cubetexture_get_color_format volumetexture_destroy gs_voltexture_destroy volumetexture_getwidth gs_voltexture_get_width volumetexture_getheight gs_voltexture_get_height volumetexture_getdepth gs_voltexture_getdepth volumetexture_getcolorformat gs_voltexture_get_color_format stagesurface_destroy gs_stagesurface_destroy stagesurface_getwidth gs_stagesurface_get_width stagesurface_getheight gs_stagesurface_get_height stagesurface_getcolorformat gs_stagesurface_get_color_format stagesurface_map gs_stagesurface_map stagesurface_unmap gs_stagesurface_unmap zstencil_destroy gs_zstencil_destroy samplerstate_destroy gs_samplerstate_destroy vertexbuffer_destroy gs_vertexbuffer_destroy vertexbuffer_flush gs_vertexbuffer_flush vertexbuffer_getdata gs_vertexbuffer_get_data indexbuffer_destroy gs_indexbuffer_destroy indexbuffer_flush gs_indexbuffer_flush indexbuffer_getdata gs_indexbuffer_get_data indexbuffer_numindices gs_indexbuffer_get_num_indices indexbuffer_gettype gs_indexbuffer_get_type texture_rebind_iosurface gs_texture_rebind_iosurface texture_get_dc gs_texture_get_dc texture_release_dc gs_texture_release_dc
424 lines
9.8 KiB
C
424 lines
9.8 KiB
C
/******************************************************************************
|
|
Copyright (C) 2014 by Zachary Lund <admin@computerquip.com>
|
|
|
|
This program is free software: you can redistribute it and/or modify
|
|
it under the terms of the GNU General Public License as published by
|
|
the Free Software Foundation, either version 2 of the License, or
|
|
(at your option) any later version.
|
|
|
|
This program is distributed in the hope that it will be useful,
|
|
but WITHOUT ANY WARRANTY; without even the implied warranty of
|
|
MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the
|
|
GNU General Public License for more details.
|
|
|
|
You should have received a copy of the GNU General Public License
|
|
along with this program. If not, see <http://www.gnu.org/licenses/>.
|
|
******************************************************************************/
|
|
|
|
#include <X11/Xlib.h>
|
|
|
|
#include <stdio.h>
|
|
|
|
#include "gl-subsystem.h"
|
|
|
|
#include <glad/glad_glx.h>
|
|
|
|
static const int fb_attribs[] = {
|
|
/* Hardcoded for now... */
|
|
GLX_STENCIL_SIZE, 8,
|
|
GLX_DEPTH_SIZE, 24,
|
|
GLX_BUFFER_SIZE, 32, /* Color buffer depth */
|
|
GLX_DOUBLEBUFFER, true,
|
|
GLX_X_RENDERABLE, true,
|
|
GLX_RENDER_TYPE, GLX_RGBA_BIT,
|
|
None
|
|
};
|
|
|
|
static const int ctx_attribs[] = {
|
|
#ifdef _DEBUG
|
|
GLX_CONTEXT_FLAGS_ARB, GLX_CONTEXT_DEBUG_BIT_ARB,
|
|
#endif
|
|
GLX_CONTEXT_PROFILE_MASK_ARB, GLX_CONTEXT_CORE_PROFILE_BIT_ARB,
|
|
GLX_CONTEXT_MAJOR_VERSION_ARB, 3, GLX_CONTEXT_MINOR_VERSION_ARB, 2,
|
|
None,
|
|
};
|
|
|
|
struct gl_windowinfo {
|
|
Display *display;
|
|
uint32_t id;
|
|
uint32_t int_id;
|
|
uint32_t glxid;
|
|
};
|
|
|
|
struct gl_platform {
|
|
GLXContext context;
|
|
GLXFBConfig fbcfg;
|
|
struct gs_swap_chain swap;
|
|
};
|
|
|
|
extern struct gs_swap_chain *gl_platform_getswap(struct gl_platform *platform)
|
|
{
|
|
return &platform->swap;
|
|
}
|
|
|
|
extern struct gl_windowinfo *gl_windowinfo_create(struct gs_init_data *info)
|
|
{
|
|
struct gl_windowinfo *wi = bzalloc(sizeof(struct gl_windowinfo));
|
|
wi->id = info->window.id;
|
|
wi->display = info->window.display;
|
|
|
|
return wi;
|
|
}
|
|
|
|
extern void gl_windowinfo_destroy(struct gl_windowinfo *wi)
|
|
{
|
|
bfree(wi);
|
|
}
|
|
|
|
extern void gl_getclientsize(struct gs_swap_chain *swap,
|
|
uint32_t *width, uint32_t *height)
|
|
{
|
|
XWindowAttributes info = { 0 };
|
|
|
|
XGetWindowAttributes(swap->wi->display, swap->wi->id, &info);
|
|
|
|
*height = info.height;
|
|
*width = info.width;
|
|
}
|
|
|
|
static void print_info_stuff(struct gs_init_data *info)
|
|
{
|
|
blog( LOG_INFO,
|
|
"X and Y: %i %i\n"
|
|
"Backbuffers: %i\n"
|
|
"Color Format: %i\n"
|
|
"ZStencil Format: %i\n"
|
|
"Adapter: %i\n",
|
|
info->cx, info->cy,
|
|
info->num_backbuffers,
|
|
info->format, info->zsformat,
|
|
info->adapter
|
|
);
|
|
}
|
|
|
|
int wait_for_notify(Display *dpy, XEvent *e, char *arg)
|
|
{
|
|
UNUSED_PARAMETER(dpy);
|
|
return (e->type == MapNotify) && (e->xmap.window == (Window)arg);
|
|
}
|
|
|
|
static bool got_x_error = false;
|
|
static int err_handler(Display *disp, XErrorEvent *e)
|
|
{
|
|
char estr[128];
|
|
XGetErrorText(disp, e->error_code, estr, 128);
|
|
|
|
blog(LOG_DEBUG, "Got X error: %s", estr);
|
|
|
|
got_x_error = true;
|
|
|
|
return 0;
|
|
}
|
|
|
|
static bool handle_x_error(Display *disp, const char *error_string)
|
|
{
|
|
XSync(disp, 0);
|
|
|
|
if (got_x_error) {
|
|
if (error_string)
|
|
blog(LOG_ERROR, "%s", error_string);
|
|
|
|
got_x_error = false;
|
|
return true;
|
|
}
|
|
|
|
return false;
|
|
}
|
|
|
|
struct gl_platform *gl_platform_create(gs_device_t device,
|
|
struct gs_init_data *info)
|
|
{
|
|
int num_configs = 0;
|
|
int error_base = 0, event_base = 0;
|
|
Display *display = info->window.display;
|
|
struct gl_platform *plat = bzalloc(sizeof(struct gl_platform));
|
|
GLXFBConfig* configs;
|
|
XWindowAttributes attrs;
|
|
int screen;
|
|
int major = 0, minor = 0;
|
|
|
|
print_info_stuff(info);
|
|
|
|
if (!display) {
|
|
blog(LOG_ERROR, "Unable to find display. DISPLAY variable "
|
|
"may not be set correctly.");
|
|
goto fail0;
|
|
}
|
|
|
|
if (!XGetWindowAttributes(display, info->window.id, &attrs)) {
|
|
blog(LOG_ERROR, "Failed getting window attributes");
|
|
goto fail0;
|
|
}
|
|
|
|
screen = XScreenNumberOfScreen(attrs.screen);
|
|
|
|
if (!gladLoadGLX(display, screen)) {
|
|
blog(LOG_ERROR, "Unable to load GLX entry functions.");
|
|
goto fail0;
|
|
}
|
|
|
|
if (!glXQueryExtension(display, &error_base, &event_base)) {
|
|
blog(LOG_ERROR, "GLX not supported.");
|
|
goto fail0;
|
|
}
|
|
|
|
/* We require glX version 1.3 */
|
|
|
|
glXQueryVersion(display, &major, &minor);
|
|
if (major < 1 || (major == 1 && minor < 3)) {
|
|
blog(LOG_ERROR, "GLX version found: %i.%i\nRequired: "
|
|
"1.3", major, minor);
|
|
goto fail0;
|
|
}
|
|
|
|
if (!GLAD_GLX_ARB_create_context) {
|
|
blog(LOG_ERROR, "ARB_GLX_create_context not supported!");
|
|
goto fail0;
|
|
}
|
|
|
|
configs = glXChooseFBConfig(display, screen,
|
|
fb_attribs, &num_configs);
|
|
|
|
if (!configs) {
|
|
blog(LOG_ERROR, "Attribute list or screen is invalid.");
|
|
goto fail0;
|
|
}
|
|
|
|
if (num_configs == 0) {
|
|
XFree(configs);
|
|
blog(LOG_ERROR, "No framebuffer configurations found.");
|
|
goto fail0;
|
|
}
|
|
|
|
plat->fbcfg = configs[0];
|
|
|
|
XFree(configs);
|
|
|
|
handle_x_error(display, NULL);
|
|
|
|
/* We just use the first configuration found... as it does everything
|
|
* we want at the very least. */
|
|
plat->context = glXCreateContextAttribsARB(display, plat->fbcfg, NULL,
|
|
true, ctx_attribs);
|
|
if (!plat->context) {
|
|
blog(LOG_ERROR, "Failed to create OpenGL context.");
|
|
goto fail0;
|
|
}
|
|
|
|
if (handle_x_error(display, "Failed to create OpenGL context."))
|
|
goto fail2;
|
|
|
|
device->plat = plat;
|
|
|
|
plat->swap.device = device;
|
|
plat->swap.info.window.id = info->window.id;
|
|
plat->swap.info.window.display = display;
|
|
plat->swap.info.format = GS_RGBA;
|
|
plat->swap.info.zsformat = GS_Z24_S8;
|
|
plat->swap.info.num_backbuffers = 1;
|
|
plat->swap.info.adapter = info->adapter;
|
|
plat->swap.info.cx = attrs.width;
|
|
plat->swap.info.cy = attrs.height;
|
|
plat->swap.wi = gl_windowinfo_create(info);
|
|
|
|
if (!gl_platform_init_swapchain(&plat->swap))
|
|
goto fail2;
|
|
|
|
if (!glXMakeCurrent(display, plat->swap.wi->glxid, plat->context)) {
|
|
blog(LOG_ERROR, "Failed to make context current.");
|
|
goto fail2;
|
|
}
|
|
|
|
if (!gladLoadGL()) {
|
|
blog(LOG_ERROR, "Failed to load OpenGL entry functions.");
|
|
goto fail2;
|
|
}
|
|
|
|
blog(LOG_INFO, "OpenGL version: %s\n", glGetString(GL_VERSION));
|
|
|
|
/* We assume later that cur_swap is already set. */
|
|
device->cur_swap = &plat->swap;
|
|
|
|
XSync(display, false);
|
|
|
|
blog(LOG_INFO, "Created new platform data");
|
|
|
|
return plat;
|
|
|
|
fail2:
|
|
glXMakeCurrent(display, None, NULL);
|
|
glXDestroyContext(display, plat->context);
|
|
|
|
gl_platform_cleanup_swapchain(&plat->swap);
|
|
|
|
fail0:
|
|
bfree(plat);
|
|
device->plat = 0;
|
|
|
|
return NULL;
|
|
}
|
|
|
|
void gl_platform_destroy(struct gl_platform *platform)
|
|
{
|
|
if (!platform)
|
|
return;
|
|
|
|
Display *dpy = platform->swap.wi->display;
|
|
|
|
glXMakeCurrent(dpy, None, NULL);
|
|
gl_platform_cleanup_swapchain(&platform->swap);
|
|
glXDestroyContext(dpy, platform->context);
|
|
gl_windowinfo_destroy(platform->swap.wi);
|
|
bfree(platform);
|
|
}
|
|
|
|
bool gl_platform_init_swapchain(struct gs_swap_chain *swap)
|
|
{
|
|
Display *display = swap->wi->display;
|
|
struct gl_windowinfo *info = swap->wi;
|
|
struct gl_platform *plat = swap->device->plat;
|
|
XVisualInfo *vi = 0;
|
|
Colormap cmap = 0;
|
|
XSetWindowAttributes swa;
|
|
XWindowAttributes attrs;
|
|
|
|
XErrorHandler phandler = XSetErrorHandler(err_handler);
|
|
|
|
gl_platform_cleanup_swapchain(swap);
|
|
|
|
if (!XGetWindowAttributes(display, info->id, &attrs)) {
|
|
blog(LOG_ERROR, "Failed getting window attributes");
|
|
goto fail;
|
|
}
|
|
|
|
vi = glXGetVisualFromFBConfig(display, plat->fbcfg);
|
|
|
|
if (handle_x_error(display, "Failed to get visual from fb config."))
|
|
goto fail;
|
|
|
|
cmap = XCreateColormap(display, info->id, vi->visual, AllocNone);
|
|
|
|
if (handle_x_error(display, "Failed creating colormap"))
|
|
goto fail;
|
|
|
|
swa.colormap = cmap;
|
|
swa.border_pixel = 0;
|
|
|
|
info->int_id = XCreateWindow(display, info->id, 0, 0,
|
|
attrs.width, attrs.height,
|
|
0, 24, InputOutput, vi->visual,
|
|
CWBorderPixel|CWColormap, &swa);
|
|
XMapWindow(display, info->int_id);
|
|
|
|
if (handle_x_error(display, "Failed creating intermediate X window"))
|
|
goto fail;
|
|
|
|
info->glxid = glXCreateWindow(display, plat->fbcfg, info->int_id, 0);
|
|
|
|
if (handle_x_error(display, "Failed creating intermediate GLX window"))
|
|
goto fail;
|
|
|
|
XFreeColormap(display, cmap);
|
|
XFree(vi);
|
|
|
|
return true;
|
|
|
|
fail:
|
|
|
|
gl_platform_cleanup_swapchain(swap);
|
|
|
|
if (cmap)
|
|
XFreeColormap(display, cmap);
|
|
|
|
if (vi)
|
|
XFree(vi);
|
|
|
|
XSetErrorHandler(phandler);
|
|
|
|
return false;
|
|
}
|
|
|
|
void gl_platform_cleanup_swapchain(struct gs_swap_chain *swap)
|
|
{
|
|
Display *display = swap->wi->display;
|
|
struct gl_windowinfo *info = swap->wi;
|
|
|
|
if (!info)
|
|
return;
|
|
|
|
if (info->glxid)
|
|
glXDestroyWindow(display, info->glxid);
|
|
|
|
if (info->int_id)
|
|
XDestroyWindow(display, info->int_id);
|
|
|
|
info->glxid = 0;
|
|
info->int_id = 0;
|
|
}
|
|
|
|
void device_enter_context(gs_device_t device)
|
|
{
|
|
GLXContext context = device->plat->context;
|
|
XID window = device->cur_swap->wi->glxid;
|
|
Display *display = device->cur_swap->wi->display;
|
|
|
|
if (!glXMakeCurrent(display, window, context)) {
|
|
blog(LOG_ERROR, "Failed to make context current.");
|
|
}
|
|
}
|
|
|
|
void device_leave_context(gs_device_t device)
|
|
{
|
|
Display *display = device->cur_swap->wi->display;
|
|
|
|
if (!glXMakeCurrent(display, None, NULL)) {
|
|
blog(LOG_ERROR, "Failed to reset current context.");
|
|
}
|
|
}
|
|
|
|
void gl_update(gs_device_t device)
|
|
{
|
|
Display *display = device->cur_swap->wi->display;
|
|
XID window = device->cur_swap->wi->int_id;
|
|
|
|
XResizeWindow(display, window,
|
|
device->cur_swap->info.cx, device->cur_swap->info.cy);
|
|
}
|
|
|
|
void device_load_swapchain(gs_device_t device, gs_swapchain_t swap)
|
|
{
|
|
if (!swap)
|
|
swap = &device->plat->swap;
|
|
|
|
if (device->cur_swap == swap)
|
|
return;
|
|
|
|
Display *dpy = swap->wi->display;
|
|
XID window = swap->wi->glxid;
|
|
GLXContext ctx = device->plat->context;
|
|
|
|
device->cur_swap = swap;
|
|
|
|
if (!glXMakeCurrent(dpy, window, ctx)) {
|
|
blog(LOG_ERROR, "Failed to make context current.");
|
|
}
|
|
}
|
|
|
|
void device_present(gs_device_t device)
|
|
{
|
|
Display *display = device->cur_swap->wi->display;
|
|
XID window = device->cur_swap->wi->glxid;
|
|
|
|
glXSwapBuffers(display, window);
|
|
}
|