Add a new runner, written in C.

Whereas run.py runs piglit's shader_runner binary to compile each shader
individually and parses the output of INTEL_DEBUG=fs,vs,gs to find the
number of instructions and loops, this runner compiles all of the
shaders from a single process and uses output from GL_KHR_debug to get
the information we want.

It uses EGL and GBM (and render nodes) to create a GL display and uses
libepoxy for GL function pointer management.

It creates one thread per-CPU using OpenMP, each of which compiles
shaders in parallel. It creates two OpenGL contexts, one core context
and one compatibility context and switches between them as needed.

run.py is able to compile all of the GLSL shaders in shader-db
(including the closed portion) in about 300 seconds on my quad-core
Haswell. This program can do the same in 90 seconds.

Profiling shows that it's largely limited by malloc performance, and
preloading jemalloc (LD_PRELOAD=/usr/lib64/libjemalloc.so.1) reduces the
execution time to about 80 seconds.

2 files changed, 584 insertions, 0 deletions

diff --git a/Makefile b/Makefile
new file mode 100644
index 0000000..1ae0776
--- /dev/null
+++ b/Makefile
@@ -0,0 +1,29 @@
+# Copyright © 2014 Intel Corporation
+#
+# Permission is hereby granted, free of charge, to any person obtaining a
+# copy of this software and associated documentation files (the "Software"),
+# to deal in the Software without restriction, including without limitation
+# the rights to use, copy, modify, merge, publish, distribute, sublicense,
+# and/or sell copies of the Software, and to permit persons to whom the
+# Software is furnished to do so, subject to the following conditions:
+#
+# The above copyright notice and this permission notice (including the next
+# paragraph) shall be included in all copies or substantial portions of the
+# Software.
+#
+# THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
+# IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
+# FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.  IN NO EVENT SHALL
+# THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
+# LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING
+# FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS
+# IN THE SOFTWARE.
+
+CFLAGS ?= -g -O2 -march=native -pipe
+CFLAGS += -std=gnu99 -fopenmp
+LDFLAGS = -lepoxy -lgbm
+
+run:
+
+clean:
+	rm -f run
diff --git a/run.c b/run.c
new file mode 100644
index 0000000..f6c99f8
--- /dev/null
+++ b/run.c
@@ -0,0 +1,555 @@
+/* vim: set expandtab tabstop=4 softtabstop=4 shiftwidth=4: */
+/*
+ * Copyright © 2014 Intel Corporation
+ *
+ * Permission is hereby granted, free of charge, to any person obtaining a
+ * copy of this software and associated documentation files (the "Software"),
+ * to deal in the Software without restriction, including without limitation
+ * the rights to use, copy, modify, merge, publish, distribute, sublicense,
+ * and/or sell copies of the Software, and to permit persons to whom the
+ * Software is furnished to do so, subject to the following conditions:
+ *
+ * The above copyright notice and this permission notice (including the next
+ * paragraph) shall be included in all copies or substantial portions of the
+ * Software.
+ *
+ * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
+ * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
+ * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.  IN NO EVENT SHALL
+ * THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
+ * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING
+ * FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER
+ * DEALINGS IN THE SOFTWARE.
+ */
+
+#include <time.h>
+#include <stdio.h>
+#include <fcntl.h>
+#include <assert.h>
+/* for memmem(). The man page doesn't say __USE_GNU... */
+#define __USE_GNU
+#include <string.h>
+#include <stdlib.h>
+#include <unistd.h>
+#include <stdbool.h>
+#include <sys/mman.h>
+#include <sys/stat.h>
+#include <sys/types.h>
+#include <ftw.h>
+
+#include <epoxy/gl.h>
+#include <epoxy/egl.h>
+#include <gbm.h>
+#include <omp.h>
+
+#define unlikely(x) __builtin_expect(!!(x), 0)
+
+#define ARRAY_SIZE(x) (sizeof(x) / sizeof((x)[0]))
+
+struct context_info {
+    char *extension_string;
+    int extension_string_len;
+    int max_glsl_version;
+};
+
+enum shader_type {
+    TYPE_CORE,
+    TYPE_COMPAT,
+    TYPE_VP,
+    TYPE_FP,
+};
+
+struct shader {
+    const char *text;
+    int length;
+    int type;
+};
+
+static struct shader *
+get_shaders(const struct context_info *core, const struct context_info *compat,
+            const char *text, size_t text_size,
+            enum shader_type *type, unsigned *num_shaders,
+            const char *shader_name)
+{
+    static const char *req = "[require]";
+    static const char *glsl_req = "\nGLSL >= ";
+    static const char *fp_req = "\nGL_ARB_fragment_program";
+    static const char *vp_req = "\nGL_ARB_vertex_program";
+    static const char *gs = "geometry shader]\n";
+    static const char *fs = "fragment ";
+    static const char *vs = "vertex ";
+    static const char *shder = "shader]\n";
+    static const char *program = "program]\n";
+    static const char *test = "test]\n";
+    const char *end_text = text + text_size;
+
+    /* Find the [require] block and parse it first. */
+    text = memmem(text, end_text - text, req, strlen(req)) + strlen(req);
+
+    if (memcmp(text, glsl_req, strlen(glsl_req)) == 0) {
+        text += strlen(glsl_req);
+        long major = strtol(text, (char **)&text, 10);
+        long minor = strtol(text + 1, (char **)&text, 10);
+        long version = major * 100 + minor;
+
+        if (version <= 130) {
+            if (unlikely(version > compat->max_glsl_version)) {
+                fprintf(stderr, "SKIP: %s requires GLSL %ld\n",
+                        shader_name, version);
+                return NULL;
+            }
+            *type = TYPE_COMPAT;
+        } else {
+            if (unlikely(version > core->max_glsl_version)) {
+                fprintf(stderr, "SKIP: %s requires GLSL %ld\n",
+                        shader_name, version);
+                return NULL;
+            }
+            *type = TYPE_CORE;
+        }
+    } else if (memcmp(text, fp_req, strlen(fp_req)) == 0) {
+        *type = TYPE_FP;
+    } else if (memcmp(text, vp_req, strlen(vp_req)) == 0) {
+        *type = TYPE_VP;
+    } else {
+        fprintf(stderr, "ERROR: Unexpected token in %s\n", shader_name);
+        return NULL;
+    }
+
+    const struct context_info *info = *type == TYPE_CORE ? core : compat;
+
+    const char *extension_text = text;
+    while ((extension_text = memmem(extension_text, end_text - extension_text,
+                                    "\nGL_", strlen("\nGL_"))) != NULL) {
+        extension_text += 1;
+        const char *newline = memchr(extension_text, '\n',
+                                     end_text - extension_text);
+        if (memmem(info->extension_string, info->extension_string_len,
+                   extension_text, newline - extension_text) == NULL) {
+            fprintf(stderr, "SKIP: %s requires unavailable extension %.*s\n",
+                    shader_name, (int)(newline - extension_text), extension_text);
+            return NULL;
+        }
+    }
+
+    /* Find the shaders. */
+    unsigned shader_size = 3;
+    struct shader *shader = malloc(shader_size * sizeof(struct shader));
+    unsigned i = 0;
+    while ((text = memmem(text, end_text - text, "\n[", strlen("\n["))) != NULL) {
+        const char *save_text = text;
+        text += strlen("\n[");
+
+        if (shader_size == i)
+            shader = realloc(shader, ++shader_size * sizeof(struct shader));
+
+        if (memcmp(text, fs, strlen(fs)) == 0) {
+            text += strlen(fs);
+            if (memcmp(text, shder, strlen(shder)) == 0) {
+                shader[i].type = GL_FRAGMENT_SHADER;
+                text += strlen(shder);
+            } else if (memcmp(text, program, strlen(program)) == 0) {
+                shader[i].type = GL_FRAGMENT_PROGRAM_ARB;
+                text += strlen(program);
+            }
+            shader[i].text = text;
+        } else if (memcmp(text, vs, strlen(vs)) == 0) {
+            text += strlen(vs);
+            if (memcmp(text, shder, strlen(shder)) == 0) {
+                shader[i].type = GL_VERTEX_SHADER;
+                text += strlen(shder);
+            } else if (memcmp(text, program, strlen(program)) == 0) {
+                shader[i].type = GL_VERTEX_PROGRAM_ARB;
+                text += strlen(program);
+            }
+            shader[i].text = text;
+        } else if (memcmp(text, gs, strlen(gs)) == 0) {
+            text += strlen(gs);
+            shader[i].type = GL_GEOMETRY_SHADER;
+            shader[i].text = text;
+        } else if (memcmp(text, test, strlen(test)) == 0) {
+            shader[i - 1].length = save_text + 1 - shader[i - 1].text;
+            goto out;
+        } else {
+            fprintf(stderr, "ERROR: Unexpected token in %s\n", shader_name);
+            free(shader);
+            return NULL;
+        }
+
+        if (i != 0)
+            shader[i - 1].length = save_text + 1 - shader[i - 1].text;
+        i++;
+    }
+
+    shader[i - 1].length = end_text - shader[i - 1].text;
+
+ out:
+    *num_shaders = i;
+    return shader;
+}
+
+static void
+callback(GLenum source, GLenum type, GLuint id, GLenum severity, GLsizei length,
+         const GLchar *message, const void *userParam)
+{
+    assert(source == GL_DEBUG_SOURCE_SHADER_COMPILER);
+    assert(type == GL_DEBUG_TYPE_OTHER);
+    assert(severity == GL_DEBUG_SEVERITY_NOTIFICATION);
+
+    const char *const *shader_name = userParam;
+    printf("%s - %s", *shader_name, message);
+}
+
+static unsigned shader_test_size = 1 << 15; /* next-pow-2(num shaders in db) */
+static unsigned shader_test_length;
+static struct shader_test {
+    char *filename;
+    off_t filesize;
+} *shader_test;
+
+static int
+gather_shader_test(const char *fpath, const struct stat *sb, int typeflag)
+{
+    static const char *ext = ".shader_test";
+
+    if (strlen(fpath) >= strlen(ext) &&
+        memcmp(fpath + strlen(fpath) - strlen(ext), ext, strlen(ext)) == 0) {
+        if (unlikely(!S_ISREG(sb->st_mode))) {
+            fprintf(stderr, "ERROR: %s is not a regular file\n", fpath);
+            return -1;
+        }
+
+        if (unlikely(shader_test_size < shader_test_length)) {
+            shader_test_size *= 2;
+            shader_test = realloc(shader_test, shader_test_size * sizeof(char *));
+        }
+        shader_test[shader_test_length].filename = malloc(strlen(fpath) + 1);
+        memcpy(shader_test[shader_test_length].filename, fpath, strlen(fpath) + 1);
+        shader_test[shader_test_length].filesize = sb->st_size;
+        shader_test_length++;
+    }
+
+    return 0;
+}
+
+int
+main(int argc, char **argv)
+{
+    if (unlikely(argc < 2)) {
+        fprintf(stderr, "Usage: %s <directories and *.shader_test files>\n",
+                argv[0]);
+        return -1;
+    }
+
+    setenv("allow_glsl_extension_directive_midshader", "true", 1);
+    setenv("shader_precompile", "true", 1);
+
+    int ret = 0;
+
+    int fd = open("/dev/dri/renderD128", O_RDWR);
+    if (unlikely(fd < 0)) {
+        fprintf(stderr, "ERROR: Couldn't open /dev/dri/renderD128\n");
+        return -1;
+    }
+
+    struct gbm_device *gbm = gbm_create_device(fd);
+    if (unlikely(gbm == NULL)) {
+        fprintf(stderr, "ERROR: Couldn't create gbm device\n");
+        ret = -1;
+        goto close_fd;
+    }
+
+    EGLDisplay egl_dpy = eglGetDisplay(gbm);
+    if (unlikely(egl_dpy == EGL_NO_DISPLAY)) {
+        fprintf(stderr, "ERROR: eglGetDisplay() failed\n");
+        ret = -1;
+        goto destroy_gbm_device;
+    }
+
+    if (unlikely(!eglInitialize(egl_dpy, NULL, NULL))) {
+        fprintf(stderr, "ERROR: eglInitialize() failed\n");
+        ret = -1;
+        goto destroy_gbm_device;
+    }
+
+    static const char *egl_extension[] = {
+            "EGL_KHR_create_context",
+            "EGL_KHR_surfaceless_context"
+    };
+    char *extension_string = eglQueryString(egl_dpy, EGL_EXTENSIONS);
+    for (int i = 0; i < ARRAY_SIZE(egl_extension); i++) {
+        if (strstr(extension_string, egl_extension[i]) == NULL) {
+            fprintf(stderr, "ERROR: Missing necessary %s extension\n",
+                    egl_extension[i]);
+            ret = -1;
+            goto egl_terminate;
+        }
+    }
+
+    static const EGLint config_attribs[] = {
+        EGL_RENDERABLE_TYPE, EGL_OPENGL_BIT,
+        EGL_NONE
+    };
+    EGLConfig cfg;
+    EGLint count;
+
+    if (!eglChooseConfig(egl_dpy, config_attribs, &cfg, 1, &count) ||
+        count == 0) {
+        fprintf(stderr, "ERROR: eglChooseConfig() failed\n");
+        ret = -1;
+        goto egl_terminate;
+    }
+    eglBindAPI(EGL_OPENGL_API);
+
+    static struct context_info core = { 0 }, compat = { 0 };
+
+    static const EGLint attribs[] = {
+        EGL_CONTEXT_OPENGL_PROFILE_MASK_KHR,
+        EGL_CONTEXT_OPENGL_CORE_PROFILE_BIT_KHR,
+        EGL_CONTEXT_MAJOR_VERSION_KHR, 3,
+        EGL_CONTEXT_MINOR_VERSION_KHR, 2,
+        EGL_NONE
+    };
+    EGLContext core_ctx = eglCreateContext(egl_dpy, cfg, EGL_NO_CONTEXT,
+                                           attribs);
+    if (core_ctx != EGL_NO_CONTEXT &&
+        eglMakeCurrent(egl_dpy, EGL_NO_SURFACE, EGL_NO_SURFACE, core_ctx)) {
+        int num_extensions;
+        glGetIntegerv(GL_NUM_EXTENSIONS, &num_extensions);
+
+        size_t extension_string_size = num_extensions * 26;
+        core.extension_string = malloc(extension_string_size);
+        extension_string = core.extension_string;
+        char *end_extension_string = core.extension_string +
+                                     extension_string_size;
+
+        for (int i = 0; i < num_extensions; i++) {
+            const char *ext = glGetStringi(GL_EXTENSIONS, i);
+            size_t len = strlen(ext);
+
+            if (unlikely(extension_string + len + 1 >= end_extension_string)) {
+                extension_string_size *= 2;
+                core.extension_string = realloc(core.extension_string,
+                                                extension_string_size);
+                extension_string = core.extension_string;
+                end_extension_string = core.extension_string +
+                                       extension_string_size;
+            }
+
+            memcpy(extension_string, ext, len);
+            extension_string[len] = ' ';
+            extension_string += len + 1;
+        }
+        extension_string[-1] = '\0';
+        core.extension_string_len = extension_string - 1 -
+                                    core.extension_string;
+
+        char *ver = glGetString(GL_SHADING_LANGUAGE_VERSION);
+        long major = strtol(ver, &ver, 10);
+        long minor = strtol(ver + 1, NULL, 10);
+        core.max_glsl_version = major * 100 + minor;
+
+        if (memmem(core.extension_string, core.extension_string_len,
+                   "GL_KHR_debug", strlen("GL_KHR_debug")) == NULL) {
+            fprintf(stderr, "ERROR: Missing GL_KHR_debug\n");
+            ret = -1;
+            goto egl_terminate;
+        }
+    }
+
+    EGLContext compat_ctx = eglCreateContext(egl_dpy, cfg, EGL_NO_CONTEXT,
+                                             &attribs[6]);
+    if (compat_ctx == EGL_NO_CONTEXT) {
+        fprintf(stderr, "ERROR: eglCreateContext() failed\n");
+        ret = -1;
+        goto egl_terminate;
+    }
+
+    if (!eglMakeCurrent(egl_dpy, EGL_NO_SURFACE, EGL_NO_SURFACE, compat_ctx)) {
+        fprintf(stderr, "ERROR: eglMakeCurrent() failed\n");
+        ret = -1;
+        goto egl_terminate;
+    } else {
+        compat.extension_string = (char *)glGetString(GL_EXTENSIONS);
+        compat.extension_string_len = strlen(compat.extension_string);
+
+        char *ver = glGetString(GL_SHADING_LANGUAGE_VERSION);
+        long major = strtol(ver, &ver, 10);
+        long minor = strtol(ver + 1, NULL, 10);
+        compat.max_glsl_version = major * 100 + minor;
+
+        if (memmem(compat.extension_string, compat.extension_string_len,
+                   "GL_KHR_debug", strlen("GL_KHR_debug")) == NULL) {
+            fprintf(stderr, "ERROR: Missing GL_KHR_debug\n");
+            ret = -1;
+            goto egl_terminate;
+        }
+    }
+
+    shader_test = malloc(shader_test_size * sizeof(struct shader_test));
+    for (int i = 1; i < argc; i++) {
+        ftw(argv[i], gather_shader_test, 100);
+    }
+
+    #pragma omp parallel if(shader_test_length > omp_get_max_threads())
+    {
+        const char *current_shader_name;
+        unsigned shaders_compiled = 0;
+        unsigned ctx_switches = 0;
+        struct timespec start, end;
+        clock_gettime(CLOCK_THREAD_CPUTIME_ID, &start);
+
+        eglBindAPI(EGL_OPENGL_API);
+
+        EGLContext core_ctx = eglCreateContext(egl_dpy, cfg, EGL_NO_CONTEXT,
+                                               attribs);
+        if (core_ctx != EGL_NO_CONTEXT &&
+            eglMakeCurrent(egl_dpy, EGL_NO_SURFACE, EGL_NO_SURFACE, core_ctx)) {
+            glEnable(GL_DEBUG_OUTPUT);
+            glEnable(GL_DEBUG_OUTPUT_SYNCHRONOUS);
+            glDebugMessageControl(GL_DONT_CARE, GL_DONT_CARE, GL_DONT_CARE,
+                                  0, NULL, GL_FALSE);
+            glDebugMessageControl(GL_DEBUG_SOURCE_SHADER_COMPILER,
+                                  GL_DEBUG_TYPE_OTHER,
+                                  GL_DEBUG_SEVERITY_NOTIFICATION, 0, NULL,
+                                  GL_TRUE);
+            glDebugMessageCallback(callback, &current_shader_name);
+        }
+
+        EGLContext compat_ctx = eglCreateContext(egl_dpy, cfg, EGL_NO_CONTEXT,
+                                                 &attribs[6]);
+        if (compat_ctx == EGL_NO_CONTEXT) {
+            fprintf(stderr, "ERROR: eglCreateContext() failed\n");
+            exit(-1);
+        }
+
+        bool ctx_is_core = false;
+        if (!eglMakeCurrent(egl_dpy, EGL_NO_SURFACE, EGL_NO_SURFACE,
+                            compat_ctx)) {
+            fprintf(stderr, "ERROR: eglMakeCurrent() failed\n");
+        }
+
+        glEnable(GL_DEBUG_OUTPUT);
+        glEnable(GL_DEBUG_OUTPUT_SYNCHRONOUS);
+        glDebugMessageControl(GL_DONT_CARE, GL_DONT_CARE, GL_DONT_CARE,
+                              0, NULL, GL_FALSE);
+        glDebugMessageControl(GL_DEBUG_SOURCE_SHADER_COMPILER,
+                              GL_DEBUG_TYPE_OTHER,
+                              GL_DEBUG_SEVERITY_NOTIFICATION, 0, NULL, GL_TRUE);
+        glDebugMessageCallback(callback, &current_shader_name);
+
+        #pragma omp for schedule(dynamic)
+        for (int i = 0; i < shader_test_length; i++) {
+            current_shader_name = shader_test[i].filename;
+
+            int fd = open(current_shader_name, O_RDONLY);
+            if (unlikely(fd == -1)) {
+                perror("open");
+                continue;
+            }
+
+            char *text = mmap(NULL, shader_test[i].filesize, PROT_READ,
+                              MAP_PRIVATE, fd, 0);
+            if (unlikely(text == MAP_FAILED)) {
+                perror("mmap");
+                continue;
+            }
+
+            if (unlikely(close(fd) == -1)) {
+                perror("close");
+                continue;
+            }
+
+            enum shader_type type;
+            unsigned num_shaders;
+            struct shader *shader = get_shaders(&core, &compat,
+                                                text, shader_test[i].filesize,
+                                                &type, &num_shaders,
+                                                current_shader_name);
+            if (unlikely(shader == NULL)) {
+                continue;
+            }
+
+            if (ctx_is_core != (type == TYPE_CORE)) {
+                ctx_switches++;
+                if (!eglMakeCurrent(egl_dpy, EGL_NO_SURFACE, EGL_NO_SURFACE,
+                                    type == TYPE_CORE ? core_ctx : compat_ctx)) {
+                    fprintf(stderr, "ERROR: eglMakeCurrent() failed\n");
+                    continue;
+                }
+            }
+            ctx_is_core = type == TYPE_CORE;
+
+            if (type == TYPE_CORE || type == TYPE_COMPAT) {
+                GLuint prog = glCreateProgram();
+
+                for (unsigned i = 0; i < num_shaders; i++) {
+                    GLuint s = glCreateShader(shader[i].type);
+                    glShaderSource(s, 1, &shader[i].text, &shader[i].length);
+                    glCompileShader(s);
+
+                    GLint param;
+                    glGetShaderiv(s, GL_COMPILE_STATUS, &param);
+                    if (unlikely(!param)) {
+                        GLchar log[4096];
+                        GLsizei length;
+                        glGetShaderInfoLog(s, 4096, &length, log);
+
+                        fprintf(stderr, "ERROR: %s failed to compile:\n%s\n",
+                                current_shader_name, log);
+                    }
+                    glAttachShader(prog, s);
+                    glDeleteShader(s);
+                }
+
+                glLinkProgram(prog);
+                glDeleteProgram(prog);
+            } else {
+                for (unsigned i = 0; i < num_shaders; i++) {
+                    GLuint prog;
+                    glGenProgramsARB(1, &prog);
+                    glBindProgramARB(GL_FRAGMENT_PROGRAM_ARB, prog);
+                    glProgramStringARB(shader[i].type, GL_PROGRAM_FORMAT_ASCII_ARB,
+                                       shader[i].length, shader[i].text);
+                    glDeleteProgramsARB(1, &prog);
+                    if (glGetError() == GL_INVALID_OPERATION) {
+                        fprintf(stderr, "ERROR: %s failed to compile\n",
+                                current_shader_name);
+                    }
+                }
+            }
+            shaders_compiled += num_shaders;
+
+            free(shader);
+            free(shader_test[i].filename);
+
+            if (unlikely(munmap(text, shader_test[i].filesize) == -1)) {
+                perror("munmap");
+                continue;
+            }
+        }
+
+        eglDestroyContext(egl_dpy, compat_ctx);
+        eglDestroyContext(egl_dpy, core_ctx);
+        eglReleaseThread();
+
+        clock_gettime(CLOCK_THREAD_CPUTIME_ID, &end);
+        printf("Thread %d took %.2lf seconds and compiled %u shaders "
+               "(not including SIMD16) with %u GL context switches\n",
+               omp_get_thread_num(),
+               (end.tv_sec - start.tv_sec) + 10e-9 * (end.tv_nsec - start.tv_nsec),
+               shaders_compiled, ctx_switches);
+    }
+
+    free(shader_test);
+    free(core.extension_string);
+
+ egl_terminate:
+    eglTerminate(egl_dpy);
+ destroy_gbm_device:
+    gbm_device_destroy(gbm);
+ close_fd:
+    close(fd);
+
+    return ret;
+}