Searched refs:workgroup_size (Results 1 - 25 of 63) sorted by relevance

123

/xsrc/external/mit/MesaLib/dist/src/intel/compiler/
H A Dbrw_nir_lower_cs_intrinsics.c89 size_x = nir_imm_int(b, nir->info.workgroup_size[0]);
90 size_y = nir_imm_int(b, nir->info.workgroup_size[1]);
124 nir->info.workgroup_size[1] % 4 == 0) {
223 size = nir_imm_int(b, nir->info.workgroup_size[0] *
224 nir->info.workgroup_size[1] *
225 nir->info.workgroup_size[2]);
278 assert(nir->info.workgroup_size[0] % 2 == 0);
279 assert(nir->info.workgroup_size[1] % 2 == 0);
281 ASSERTED unsigned workgroup_size = local in function:brw_nir_lower_cs_intrinsics
282 nir->info.workgroup_size[
[all...]
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/radeonsi/
H A Dsi_shaderlib_nir.c62 b.shader->info.workgroup_size[0] = 8;
63 b.shader->info.workgroup_size[1] = 8;
64 b.shader->info.workgroup_size[2] = 1;
110 b.shader->info.workgroup_size[0] = 8;
111 b.shader->info.workgroup_size[1] = 8;
112 b.shader->info.workgroup_size[2] = 1;
/xsrc/external/mit/MesaLib/dist/src/compiler/nir/
H A Dnir_lower_variable_initializers.c158 const unsigned local_count = shader->info.workgroup_size[0] *
159 shader->info.workgroup_size[1] *
160 shader->info.workgroup_size[2];
H A Dnir_lower_system_values.c323 unsigned size_x = b->shader->info.workgroup_size[0];
408 nir_imm_int(b, b->shader->info.workgroup_size[0]);
410 nir_imm_int(b, b->shader->info.workgroup_size[1]);
439 workgroup_size_const[0].u32 = b->shader->info.workgroup_size[0];
440 workgroup_size_const[1].u32 = b->shader->info.workgroup_size[1];
441 workgroup_size_const[2].u32 = b->shader->info.workgroup_size[2];
H A Dnir_opt_uniform_atomics.c172 dims_needed |= (shader->info.workgroup_size[i] > 1) << i;
311 shader->info.workgroup_size[0] == 1 && shader->info.workgroup_size[1] == 1 &&
312 shader->info.workgroup_size[2] == 1)
H A Dnir_range_analysis.c1306 res = (shader->info.workgroup_size[0] *
1307 shader->info.workgroup_size[1] *
1308 shader->info.workgroup_size[2]) - 1u;
1315 res = shader->info.workgroup_size[scalar.comp] - 1u;
1328 res = (shader->info.workgroup_size[scalar.comp] *
1357 uint32_t workgroup_size = config->max_workgroup_invocations; local in function:nir_unsigned_upper_bound
1360 workgroup_size = shader->info.workgroup_size[0] *
1361 shader->info.workgroup_size[1] *
1362 shader->info.workgroup_size[
[all...]
/xsrc/external/mit/MesaLib/dist/src/amd/common/
H A Dac_shader_util.c560 unsigned workgroup_size = MAX2(es_verts, gs_inst_prims); local in function:ac_compute_esgs_workgroup_size
561 return CLAMP(workgroup_size, 1, 256);
580 unsigned workgroup_size = MAX4(max_vtx_in, max_vtx_out, max_prim_in, max_prim_out); local in function:ac_compute_ngg_workgroup_size
582 return CLAMP(workgroup_size, 1, 256);
/xsrc/external/mit/MesaLib/dist/src/mesa/state_tracker/
H A Dst_cb_compute.c62 info.block[i] = group_size ? group_size[i] : prog->info.workgroup_size[i];
/xsrc/external/mit/MesaLib/dist/src/intel/blorp/
H A Dblorp_priv.h445 nir->info.workgroup_size[0] = 16 / local_y;
446 nir->info.workgroup_size[1] = local_y;
447 nir->info.workgroup_size[2] = 1;
/xsrc/external/mit/MesaLib/dist/src/amd/vulkan/
H A Dradv_meta_buffer.c11 b.shader->info.workgroup_size[0] = 64;
12 b.shader->info.workgroup_size[1] = 1;
13 b.shader->info.workgroup_size[2] = 1;
35 b.shader->info.workgroup_size[0] = 64;
36 b.shader->info.workgroup_size[1] = 1;
37 b.shader->info.workgroup_size[2] = 1;
H A Dradv_meta_copy_vrs_htile.c48 b.shader->info.workgroup_size[0] = 8;
49 b.shader->info.workgroup_size[1] = 8;
50 b.shader->info.workgroup_size[2] = 1;
H A Dradv_meta_dcc_retile.c37 b.shader->info.workgroup_size[0] = 8;
38 b.shader->info.workgroup_size[1] = 8;
39 b.shader->info.workgroup_size[2] = 1;
H A Dradv_meta_fmask_expand.c38 b.shader->info.workgroup_size[0] = 8;
39 b.shader->info.workgroup_size[1] = 8;
40 b.shader->info.workgroup_size[2] = 1;
H A Dradv_meta_bufimage.c43 b.shader->info.workgroup_size[0] = 8;
44 b.shader->info.workgroup_size[1] = 8;
45 b.shader->info.workgroup_size[2] = 1;
225 b.shader->info.workgroup_size[0] = 8;
226 b.shader->info.workgroup_size[1] = 8;
227 b.shader->info.workgroup_size[2] = 1;
405 b.shader->info.workgroup_size[0] = 8;
406 b.shader->info.workgroup_size[1] = 8;
407 b.shader->info.workgroup_size[2] = 1;
559 b.shader->info.workgroup_size[
[all...]
H A Dradv_query.c134 b.shader->info.workgroup_size[0] = 64;
135 b.shader->info.workgroup_size[1] = 1;
136 b.shader->info.workgroup_size[2] = 1;
273 b.shader->info.workgroup_size[0] = 64;
274 b.shader->info.workgroup_size[1] = 1;
275 b.shader->info.workgroup_size[2] = 1;
413 b.shader->info.workgroup_size[0] = 64;
414 b.shader->info.workgroup_size[1] = 1;
415 b.shader->info.workgroup_size[2] = 1;
538 b.shader->info.workgroup_size[
[all...]
H A Dradv_meta_decompress.c45 b.shader->info.workgroup_size[0] = 8;
46 b.shader->info.workgroup_size[1] = 8;
47 b.shader->info.workgroup_size[2] = 1;
59 nir_imm_ivec4(&b, b.shader->info.workgroup_size[0], b.shader->info.workgroup_size[1],
60 b.shader->info.workgroup_size[2], 0);
H A Dradv_meta_resolve_cs.c70 b.shader->info.workgroup_size[0] = 8;
71 b.shader->info.workgroup_size[1] = 8;
72 b.shader->info.workgroup_size[2] = 1;
142 b.shader->info.workgroup_size[0] = 8;
143 b.shader->info.workgroup_size[1] = 8;
144 b.shader->info.workgroup_size[2] = 1;
H A Dradv_acceleration_structure.c919 b.shader->info.workgroup_size[0] = 64;
920 b.shader->info.workgroup_size[1] = 1;
921 b.shader->info.workgroup_size[2] = 1;
944 nir_imm_int(&b, b.shader->info.workgroup_size[0])),
1265 b.shader->info.workgroup_size[0] = 64;
1266 b.shader->info.workgroup_size[1] = 1;
1267 b.shader->info.workgroup_size[2] = 1;
1297 nir_imm_int(&b, b.shader->info.workgroup_size[0])),
1376 b.shader->info.workgroup_size[0] = 64;
1377 b.shader->info.workgroup_size[
[all...]
/xsrc/external/mit/MesaLib/dist/src/microsoft/clc/
H A Dclc_nir.c76 nir_const_value_for_int(b->shader->info.workgroup_size[0], 32),
77 nir_const_value_for_int(b->shader->info.workgroup_size[1], 32),
78 nir_const_value_for_int(b->shader->info.workgroup_size[2], 32)
H A Dclc_compiler.c1109 memcpy(metadata->local_size, nir->info.workgroup_size,
1116 for (unsigned i = 0; i < ARRAY_SIZE(nir->info.workgroup_size); i++) {
1118 conf->local_size[i] == nir->info.workgroup_size[i])
1121 if (nir->info.workgroup_size[i] &&
1122 nir->info.workgroup_size[i] != conf->local_size[i]) {
1127 nir->info.workgroup_size[i] = conf->local_size[i];
1129 memcpy(metadata->local_size, nir->info.workgroup_size,
1133 for (unsigned i = 0; i < ARRAY_SIZE(nir->info.workgroup_size); i++) {
1134 if (nir->info.workgroup_size[i] == 0)
1135 nir->info.workgroup_size[
[all...]
/xsrc/external/mit/MesaLib/dist/src/compiler/glsl/
H A Dlower_cs_derived.cpp147 data.u[i] = shader->Program->info.workgroup_size[i];
/xsrc/external/mit/MesaLib/dist/src/compiler/
H A Dshader_info.h215 uint16_t workgroup_size[3]; member in struct:shader_info
/xsrc/external/mit/MesaLib/dist/src/amd/compiler/
H A Daco_live_var_analysis.cpp270 unsigned workgroup_size = local in function:aco::__anon04c364850110::calc_waves_per_workgroup
271 program->workgroup_size == UINT_MAX ? program->wave_size : program->workgroup_size;
273 return align(workgroup_size, program->wave_size) / program->wave_size;
H A Daco_statistics.cpp361 is_vector(instr->opcode) && program->workgroup_size > 32;
542 if (program->workgroup_size != UINT_MAX)
544 program->workgroup_size / (double)align(program->workgroup_size, program->wave_size);
/xsrc/external/mit/MesaLib/dist/src/gallium/frontends/clover/nir/
H A Dinvocation.cpp438 nir->info.workgroup_size[0] = sym.reqd_work_group_size[0];
439 nir->info.workgroup_size[1] = sym.reqd_work_group_size[1];
440 nir->info.workgroup_size[2] = sym.reqd_work_group_size[2];

Completed in 28 milliseconds

123