diff options
| author | Jason Ekstrand <jason.ekstrand@intel.com> | 2015-06-19 15:40:09 -0700 |
|---|---|---|
| committer | Jason Ekstrand <jason.ekstrand@intel.com> | 2015-06-23 15:34:59 -0700 |
| commit | 1b0f6ffa15b25e8601d60fe1ea74e893f7d33cf5 (patch) | |
| tree | 14d8c8d4ce25c1cb204517540fdd0c2399b7f253 /src/mesa/drivers/dri/i965/brw_cs.cpp | |
| parent | c7893dc3c590b86787d8118e3920debaea3f16da (diff) | |
| download | external_mesa3d-1b0f6ffa15b25e8601d60fe1ea74e893f7d33cf5.zip external_mesa3d-1b0f6ffa15b25e8601d60fe1ea74e893f7d33cf5.tar.gz external_mesa3d-1b0f6ffa15b25e8601d60fe1ea74e893f7d33cf5.tar.bz2 | |
i965: Pull calls to get_shader_time_index out of the visitor
Reviewed-by: Kenneth Graunke <kenneth@whitecape.org>
Reviewed-by: Chris Forbes <chrisf@ijw.co.nz>
Diffstat (limited to 'src/mesa/drivers/dri/i965/brw_cs.cpp')
| -rw-r--r-- | src/mesa/drivers/dri/i965/brw_cs.cpp | 8 |
1 files changed, 6 insertions, 2 deletions
diff --git a/src/mesa/drivers/dri/i965/brw_cs.cpp b/src/mesa/drivers/dri/i965/brw_cs.cpp index 0833404..fa8b5c8 100644 --- a/src/mesa/drivers/dri/i965/brw_cs.cpp +++ b/src/mesa/drivers/dri/i965/brw_cs.cpp @@ -88,10 +88,14 @@ brw_cs_emit(struct brw_context *brw, cfg_t *cfg = NULL; const char *fail_msg = NULL; + int st_index = -1; + if (INTEL_DEBUG & DEBUG_SHADER_TIME) + st_index = brw_get_shader_time_index(brw, prog, &cp->Base, ST_CS); + /* Now the main event: Visit the shader IR and generate our CS IR for it. */ fs_visitor v8(brw, mem_ctx, MESA_SHADER_COMPUTE, key, &prog_data->base, prog, - &cp->Base, 8); + &cp->Base, 8, st_index); if (!v8.run_cs()) { fail_msg = v8.fail_msg; } else if (local_workgroup_size <= 8 * brw->max_cs_threads) { @@ -100,7 +104,7 @@ brw_cs_emit(struct brw_context *brw, } fs_visitor v16(brw, mem_ctx, MESA_SHADER_COMPUTE, key, &prog_data->base, prog, - &cp->Base, 16); + &cp->Base, 16, st_index); if (likely(!(INTEL_DEBUG & DEBUG_NO16)) && !fail_msg && !v8.simd16_unsupported && local_workgroup_size <= 16 * brw->max_cs_threads) { |