gl-shader.c 14 KB

123456789101112131415161718192021222324252627282930313233343536373839404142434445464748495051525354555657585960616263646566676869707172737475767778798081828384858687888990919293949596979899100101102103104105106107108109110111112113114115116117118119120121122123124125126127128129130131132133134135136137138139140141142143144145146147148149150151152153154155156157158159160161162163164165166167168169170171172173174175176177178179180181182183184185186187188189190191192193194195196197198199200201202203204205206207208209210211212213214215216217218219220221222223224225226227228229230231232233234235236237238239240241242243244245246247248249250251252253254255256257258259260261262263264265266267268269270271272273274275276277278279280281282283284285286287288289290291292293294295296297298299300301302303304305306307308309310311312313314315316317318319320321322323324325326327328329330331332333334335336337338339340341342343344345346347348349350351352353354355356357358359360361362363364365366367368369370371372373374375376377378379380381382383384385386387388389390391392393394395396397398399400401402403404405406407408409410411412413414415416417418419420421422423424425426427428429430431432433434435436437438439440441442443444445446447448449450451452453454455456457458459460461462463464465466467468469470471472473474475476477478479480481482483484485486487488489490491492493494495496497498499500501502503504505506507508509510511512513514515516517518519520521522523524525526527528529530531532533534535536537538539540
  1. /******************************************************************************
  2. Copyright (C) 2013 by Hugh Bailey <[email protected]>
  3. This program is free software: you can redistribute it and/or modify
  4. it under the terms of the GNU General Public License as published by
  5. the Free Software Foundation, either version 2 of the License, or
  6. (at your option) any later version.
  7. This program is distributed in the hope that it will be useful,
  8. but WITHOUT ANY WARRANTY; without even the implied warranty of
  9. MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the
  10. GNU General Public License for more details.
  11. You should have received a copy of the GNU General Public License
  12. along with this program. If not, see <http://www.gnu.org/licenses/>.
  13. ******************************************************************************/
  14. #include <assert.h>
  15. #include <graphics/vec2.h>
  16. #include <graphics/vec3.h>
  17. #include <graphics/vec4.h>
  18. #include <graphics/matrix3.h>
  19. #include <graphics/matrix4.h>
  20. #include "gl-subsystem.h"
  21. #include "gl-shaderparser.h"
  22. static inline void shader_param_init(struct shader_param *param)
  23. {
  24. memset(param, 0, sizeof(struct shader_param));
  25. }
  26. static inline void shader_param_free(struct shader_param *param)
  27. {
  28. bfree(param->name);
  29. da_free(param->cur_value);
  30. da_free(param->def_value);
  31. }
  32. static void gl_get_program_info(GLuint program, const char *file,
  33. char **error_string)
  34. {
  35. char *errors;
  36. GLint info_len = 0;
  37. GLsizei chars_written = 0;
  38. glGetProgramiv(program, GL_INFO_LOG_LENGTH, &info_len);
  39. if (!gl_success("glGetProgramiv") || !info_len)
  40. return;
  41. errors = bzalloc(info_len+1);
  42. glGetProgramInfoLog(program, info_len, &chars_written, errors);
  43. gl_success("glGetProgramInfoLog");
  44. blog(LOG_DEBUG, "Compiler warnings/errors for %s:\n%s", file, errors);
  45. if (error_string)
  46. *error_string = errors;
  47. else
  48. bfree(errors);
  49. }
  50. static bool gl_add_param(struct gs_shader *shader, struct shader_var *var,
  51. GLint *texture_id)
  52. {
  53. struct shader_param param = {0};
  54. param.array_count = var->array_count;
  55. param.name = bstrdup(var->name);
  56. param.shader = shader;
  57. param.type = get_shader_param_type(var->type);
  58. if (param.type == SHADER_PARAM_TEXTURE) {
  59. param.sampler_id = var->gl_sampler_id;
  60. param.texture_id = (*texture_id)++;
  61. } else {
  62. param.changed = true;
  63. }
  64. da_move(param.def_value, var->default_val);
  65. da_copy(param.cur_value, param.def_value);
  66. param.param = glGetUniformLocation(shader->program, param.name);
  67. if (!gl_success("glGetUniformLocation"))
  68. goto fail;
  69. if (param.type == SHADER_PARAM_TEXTURE) {
  70. glProgramUniform1i(shader->program, param.param,
  71. param.texture_id);
  72. if (!gl_success("glProgramUniform1i"))
  73. goto fail;
  74. }
  75. da_push_back(shader->params, &param);
  76. return true;
  77. fail:
  78. shader_param_free(&param);
  79. return false;
  80. }
  81. static inline bool gl_add_params(struct gs_shader *shader,
  82. struct gl_shader_parser *glsp)
  83. {
  84. size_t i;
  85. GLint tex_id = 0;
  86. for (i = 0; i < glsp->parser.params.num; i++)
  87. if (!gl_add_param(shader, glsp->parser.params.array+i, &tex_id))
  88. return false;
  89. shader->viewproj = shader_getparambyname(shader, "ViewProj");
  90. shader->world = shader_getparambyname(shader, "World");
  91. return true;
  92. }
  93. static inline void gl_add_sampler(struct gs_shader *shader,
  94. struct shader_sampler *sampler)
  95. {
  96. samplerstate_t new_sampler;
  97. struct gs_sampler_info info;
  98. shader_sampler_convert(sampler, &info);
  99. new_sampler = device_create_samplerstate(shader->device, &info);
  100. da_push_back(shader->samplers, &new_sampler);
  101. }
  102. static inline void gl_add_samplers(struct gs_shader *shader,
  103. struct gl_shader_parser *glsp)
  104. {
  105. size_t i;
  106. for (i = 0; i < glsp->parser.samplers.num; i++) {
  107. struct shader_sampler *sampler = glsp->parser.samplers.array+i;
  108. gl_add_sampler(shader, sampler);
  109. }
  110. }
  111. static void get_attrib_type(const char *mapping, enum attrib_type *type,
  112. size_t *index)
  113. {
  114. if (strcmp(mapping, "POSITION") == 0) {
  115. *type = ATTRIB_POSITION;
  116. } else if (strcmp(mapping, "NORMAL") == 0) {
  117. *type = ATTRIB_NORMAL;
  118. } else if (strcmp(mapping, "TANGENT") == 0) {
  119. *type = ATTRIB_TANGENT;
  120. } else if (strcmp(mapping, "COLOR") == 0) {
  121. *type = ATTRIB_COLOR;
  122. } else if (astrcmp_n(mapping, "TEXCOORD", 8) == 0) {
  123. *type = ATTRIB_TEXCOORD;
  124. *index = (*(mapping+8)) - '0';
  125. return;
  126. } else if (strcmp(mapping, "TARGET") == 0) {
  127. *type = ATTRIB_TARGET;
  128. }
  129. *index = 0;
  130. }
  131. static inline bool gl_process_attrib(struct gs_shader *shader,
  132. struct gl_parser_attrib *pa)
  133. {
  134. struct shader_attrib attrib = {0};
  135. /* don't parse output attributes */
  136. if (!pa->input)
  137. return true;
  138. get_attrib_type(pa->mapping, &attrib.type, &attrib.index);
  139. attrib.attrib = glGetAttribLocation(shader->program, pa->name.array);
  140. if (!gl_success("glGetAttribLocation"))
  141. return false;
  142. if (attrib.attrib == -1) {
  143. blog(LOG_ERROR, "glGetAttribLocation: Could not find "
  144. "attribute '%s'", pa->name.array);
  145. return false;
  146. }
  147. da_push_back(shader->attribs, &attrib);
  148. return true;
  149. }
  150. static inline bool gl_process_attribs(struct gs_shader *shader,
  151. struct gl_shader_parser *glsp)
  152. {
  153. size_t i;
  154. for (i = 0; i < glsp->attribs.num; i++) {
  155. struct gl_parser_attrib *pa = glsp->attribs.array+i;
  156. if (!gl_process_attrib(shader, pa))
  157. return false;
  158. }
  159. return true;
  160. }
  161. static bool gl_shader_init(struct gs_shader *shader,
  162. struct gl_shader_parser *glsp,
  163. const char *file, char **error_string)
  164. {
  165. GLenum type = convert_shader_type(shader->type);
  166. int compiled = 0;
  167. bool success = true;
  168. shader->program = glCreateShaderProgramv(type, 1,
  169. (const GLchar**)&glsp->gl_string.array);
  170. if (!gl_success("glCreateShaderProgramv") || !shader->program)
  171. return false;
  172. #if 1
  173. blog(LOG_DEBUG, "+++++++++++++++++++++++++++++++++++");
  174. blog(LOG_DEBUG, " GL shader string for: %s", file);
  175. blog(LOG_DEBUG, "-----------------------------------");
  176. blog(LOG_DEBUG, "%s", glsp->gl_string.array);
  177. blog(LOG_DEBUG, "+++++++++++++++++++++++++++++++++++");
  178. #endif
  179. glGetProgramiv(shader->program, GL_LINK_STATUS, &compiled);
  180. if (!gl_success("glGetProgramiv"))
  181. return false;
  182. if (!compiled)
  183. success = false;
  184. gl_get_program_info(shader->program, file, error_string);
  185. if (success)
  186. success = gl_add_params(shader, glsp);
  187. /* Only vertex shaders actually require input attributes */
  188. if (success && shader->type == SHADER_VERTEX)
  189. success = gl_process_attribs(shader, glsp);
  190. if (success)
  191. gl_add_samplers(shader, glsp);
  192. return success;
  193. }
  194. static struct gs_shader *shader_create(device_t device, enum shader_type type,
  195. const char *shader_str, const char *file, char **error_string)
  196. {
  197. struct gs_shader *shader = bzalloc(sizeof(struct gs_shader));
  198. struct gl_shader_parser glsp;
  199. bool success = true;
  200. shader->device = device;
  201. shader->type = type;
  202. gl_shader_parser_init(&glsp, type);
  203. if (!gl_shader_parse(&glsp, shader_str, file))
  204. success = false;
  205. else
  206. success = gl_shader_init(shader, &glsp, file, error_string);
  207. if (!success) {
  208. shader_destroy(shader);
  209. shader = NULL;
  210. }
  211. gl_shader_parser_free(&glsp);
  212. return shader;
  213. }
  214. shader_t device_create_vertexshader(device_t device,
  215. const char *shader, const char *file,
  216. char **error_string)
  217. {
  218. struct gs_shader *ptr;
  219. ptr = shader_create(device, SHADER_VERTEX, shader, file, error_string);
  220. if (!ptr)
  221. blog(LOG_ERROR, "device_create_vertexshader (GL) failed");
  222. return ptr;
  223. }
  224. shader_t device_create_pixelshader(device_t device,
  225. const char *shader, const char *file,
  226. char **error_string)
  227. {
  228. struct gs_shader *ptr;
  229. ptr = shader_create(device, SHADER_PIXEL, shader, file, error_string);
  230. if (!ptr)
  231. blog(LOG_ERROR, "device_create_pixelshader (GL) failed");
  232. return ptr;
  233. }
  234. void shader_destroy(shader_t shader)
  235. {
  236. size_t i;
  237. if (!shader)
  238. return;
  239. for (i = 0; i < shader->samplers.num; i++)
  240. samplerstate_destroy(shader->samplers.array[i]);
  241. for (i = 0; i < shader->params.num; i++)
  242. shader_param_free(shader->params.array+i);
  243. if (shader->program) {
  244. glDeleteProgram(shader->program);
  245. gl_success("glDeleteProgram");
  246. }
  247. da_free(shader->samplers);
  248. da_free(shader->params);
  249. da_free(shader->attribs);
  250. bfree(shader);
  251. }
  252. int shader_numparams(shader_t shader)
  253. {
  254. return (int)shader->params.num;
  255. }
  256. sparam_t shader_getparambyidx(shader_t shader, uint32_t param)
  257. {
  258. assert(param < shader->params.num);
  259. return shader->params.array+param;
  260. }
  261. sparam_t shader_getparambyname(shader_t shader, const char *name)
  262. {
  263. size_t i;
  264. for (i = 0; i < shader->params.num; i++) {
  265. struct shader_param *param = shader->params.array+i;
  266. if (strcmp(param->name, name) == 0)
  267. return param;
  268. }
  269. return NULL;
  270. }
  271. static inline bool matching_shader(shader_t shader, sparam_t sparam)
  272. {
  273. if (shader != sparam->shader) {
  274. blog(LOG_ERROR, "Shader and shader parameter do not match");
  275. return false;
  276. }
  277. return true;
  278. }
  279. void shader_getparaminfo(shader_t shader, sparam_t param,
  280. struct shader_param_info *info)
  281. {
  282. if (!matching_shader(shader, param))
  283. return;
  284. info->type = param->type;
  285. info->name = param->name;
  286. }
  287. sparam_t shader_getviewprojmatrix(shader_t shader)
  288. {
  289. return shader->viewproj;
  290. }
  291. sparam_t shader_getworldmatrix(shader_t shader)
  292. {
  293. return shader->world;
  294. }
  295. void shader_setbool(shader_t shader, sparam_t param, bool val)
  296. {
  297. if (matching_shader(shader, param)) {
  298. glProgramUniform1i(shader->program, param->param, (GLint)val);
  299. gl_success("glProgramUniform1i");
  300. }
  301. }
  302. void shader_setfloat(shader_t shader, sparam_t param, float val)
  303. {
  304. if (matching_shader(shader, param)) {
  305. glProgramUniform1f(shader->program, param->param, val);
  306. gl_success("glProgramUniform1f");
  307. }
  308. }
  309. void shader_setint(shader_t shader, sparam_t param, int val)
  310. {
  311. if (matching_shader(shader, param)) {
  312. glProgramUniform1i(shader->program, param->param, val);
  313. gl_success("glProgramUniform1i");
  314. }
  315. }
  316. void shader_setmatrix3(shader_t shader, sparam_t param,
  317. const struct matrix3 *val)
  318. {
  319. struct matrix4 mat;
  320. matrix4_from_matrix3(&mat, val);
  321. if (matching_shader(shader, param)) {
  322. glProgramUniformMatrix4fv(shader->program, param->param, 1,
  323. false, mat.x.ptr);
  324. gl_success("glProgramUniformMatrix4fv");
  325. }
  326. }
  327. void shader_setmatrix4(shader_t shader, sparam_t param,
  328. const struct matrix4 *val)
  329. {
  330. if (matching_shader(shader, param)) {
  331. glProgramUniformMatrix4fv(shader->program, param->param, 1,
  332. false, val->x.ptr);
  333. gl_success("glProgramUniformMatrix4fv");
  334. }
  335. }
  336. void shader_setvec2(shader_t shader, sparam_t param,
  337. const struct vec2 *val)
  338. {
  339. if (matching_shader(shader, param)) {
  340. glProgramUniform2fv(shader->program, param->param, 1, val->ptr);
  341. gl_success("glProgramUniform2fv");
  342. }
  343. }
  344. void shader_setvec3(shader_t shader, sparam_t param,
  345. const struct vec3 *val)
  346. {
  347. if (matching_shader(shader, param)) {
  348. glProgramUniform3fv(shader->program, param->param, 1, val->ptr);
  349. gl_success("glProgramUniform3fv");
  350. }
  351. }
  352. void shader_setvec4(shader_t shader, sparam_t param,
  353. const struct vec4 *val)
  354. {
  355. if (matching_shader(shader, param)) {
  356. glProgramUniform4fv(shader->program, param->param, 1, val->ptr);
  357. gl_success("glProgramUniform4fv");
  358. }
  359. }
  360. void shader_settexture(shader_t shader, sparam_t param, texture_t val)
  361. {
  362. if (matching_shader(shader, param))
  363. param->texture = val;
  364. }
  365. static void shader_setval_data(shader_t shader, sparam_t param,
  366. const void *val, int count)
  367. {
  368. if (!matching_shader(shader, param))
  369. return;
  370. if (param->type == SHADER_PARAM_BOOL ||
  371. param->type == SHADER_PARAM_INT) {
  372. glProgramUniform1iv(shader->program, param->param, count, val);
  373. gl_success("glProgramUniform1iv");
  374. } else if (param->type == SHADER_PARAM_FLOAT) {
  375. glProgramUniform1fv(shader->program, param->param, count, val);
  376. gl_success("glProgramUniform1fv");
  377. } else if (param->type == SHADER_PARAM_VEC2) {
  378. glProgramUniform2fv(shader->program, param->param, count, val);
  379. gl_success("glProgramUniform2fv");
  380. } else if (param->type == SHADER_PARAM_VEC3) {
  381. glProgramUniform3fv(shader->program, param->param, count, val);
  382. gl_success("glProgramUniform3fv");
  383. } else if (param->type == SHADER_PARAM_VEC4) {
  384. glProgramUniform4fv(shader->program, param->param, count, val);
  385. gl_success("glProgramUniform4fv");
  386. } else if (param->type == SHADER_PARAM_MATRIX4X4) {
  387. glProgramUniformMatrix4fv(shader->program, param->param,
  388. count, false, val);
  389. gl_success("glProgramUniformMatrix4fv");
  390. }
  391. }
  392. void shader_update_textures(struct gs_shader *shader)
  393. {
  394. size_t i;
  395. for (i = 0; i < shader->params.num; i++) {
  396. struct shader_param *param = shader->params.array+i;
  397. if (param->type == SHADER_PARAM_TEXTURE)
  398. device_load_texture(shader->device, param->texture,
  399. param->texture_id);
  400. }
  401. }
  402. void shader_setval(shader_t shader, sparam_t param, const void *val,
  403. size_t size)
  404. {
  405. int count = param->array_count;
  406. size_t expected_size = 0;
  407. if (!count)
  408. count = 1;
  409. if (!matching_shader(shader, param))
  410. return;
  411. switch ((uint32_t)param->type) {
  412. case SHADER_PARAM_FLOAT: expected_size = sizeof(float); break;
  413. case SHADER_PARAM_BOOL:
  414. case SHADER_PARAM_INT: expected_size = sizeof(int); break;
  415. case SHADER_PARAM_VEC2: expected_size = sizeof(float)*2; break;
  416. case SHADER_PARAM_VEC3: expected_size = sizeof(float)*3; break;
  417. case SHADER_PARAM_VEC4: expected_size = sizeof(float)*4; break;
  418. case SHADER_PARAM_MATRIX4X4: expected_size = sizeof(float)*4*4; break;
  419. case SHADER_PARAM_TEXTURE: expected_size = sizeof(void*); break;
  420. default: expected_size = 0;
  421. }
  422. expected_size *= count;
  423. if (!expected_size)
  424. return;
  425. if (expected_size != size) {
  426. blog(LOG_ERROR, "shader_setval (GL): Size of shader param does "
  427. "not match the size of the input");
  428. return;
  429. }
  430. if (param->type == SHADER_PARAM_TEXTURE)
  431. shader_settexture(shader, param, *(texture_t*)val);
  432. else
  433. shader_setval_data(shader, param, val, count);
  434. }
  435. void shader_setdefault(shader_t shader, sparam_t param)
  436. {
  437. shader_setval(shader, param, param->def_value.array,
  438. param->def_value.num);
  439. }