Searched refs:group_size (Results 1 - 25 of 31) sorted by relevance

12

/xsrc/external/mit/MesaLib/dist/src/mesa/main/
H A Dcompute.c104 const GLuint *group_size)
148 if (group_size[i] == 0 ||
149 group_size[i] > ctx->Const.MaxComputeVariableGroupSize[i]) {
164 uint64_t total_invocations = group_size[0] * group_size[1];
169 total_invocations *= group_size[2];
176 group_size[0], group_size[1], group_size[2],
195 ((group_size[
102 validate_DispatchComputeGroupSizeARB(struct gl_context * ctx,const GLuint * num_groups,const GLuint * group_size) argument
360 const GLuint group_size[3] = { group_size_x, group_size_y, group_size_z }; local in function:dispatch_compute_group_size
[all...]
/xsrc/external/mit/MesaLib.old/dist/src/mesa/state_tracker/
H A Dst_cb_compute.c40 const GLuint *group_size,
61 info.block[i] = group_size ? group_size[i] : prog->info.cs.local_size[i];
90 const GLuint *group_size)
92 st_dispatch_compute_common(ctx, num_groups, group_size, NULL, 0);
38 st_dispatch_compute_common(struct gl_context * ctx,const GLuint * num_groups,const GLuint * group_size,struct pipe_resource * indirect,GLintptr indirect_offset) argument
88 st_dispatch_compute_group_size(struct gl_context * ctx,const GLuint * num_groups,const GLuint * group_size) argument
/xsrc/external/mit/MesaLib/dist/src/mesa/state_tracker/
H A Dst_cb_compute.c40 const GLuint *group_size,
62 info.block[i] = group_size ? group_size[i] : prog->info.workgroup_size[i];
91 const GLuint *group_size)
93 st_dispatch_compute_common(ctx, num_groups, group_size, NULL, 0);
38 st_dispatch_compute_common(struct gl_context * ctx,const GLuint * num_groups,const GLuint * group_size,struct pipe_resource * indirect,GLintptr indirect_offset) argument
89 st_dispatch_compute_group_size(struct gl_context * ctx,const GLuint * num_groups,const GLuint * group_size) argument
/xsrc/external/mit/MesaLib/dist/src/mesa/drivers/dri/i965/
H A Dbrw_compute.c104 brw->compute.group_size = NULL;
124 brw->compute.group_size = NULL;
133 const GLuint *group_size)
139 brw->compute.group_size = group_size;
131 brw_dispatch_compute_group_size(struct gl_context * ctx,const GLuint * num_groups,const GLuint * group_size) argument
H A Dgfx6_constant_state.c69 return brw->compute.group_size[i];
313 brw->compute.group_size);
H A Dbrw_context.h936 const GLuint *group_size; member in struct:brw_context::__anon3cd19dee0708
/xsrc/external/mit/MesaLib.old/dist/src/mesa/main/
H A Dcompute.c104 const GLuint *group_size)
150 if (group_size[i] == 0 ||
151 group_size[i] > ctx->Const.MaxComputeVariableGroupSize[i]) {
157 total_invocations *= group_size[i];
319 const GLuint group_size[3] = { group_size_x, group_size_y, group_size_z }; local in function:dispatch_compute_group_size
330 !validate_DispatchComputeGroupSizeARB(ctx, num_groups, group_size))
336 ctx->Driver.DispatchComputeGroupSize(ctx, num_groups, group_size);
102 validate_DispatchComputeGroupSizeARB(struct gl_context * ctx,const GLuint * num_groups,const GLuint * group_size) argument
H A Ddd.h1082 const GLuint *group_size);
/xsrc/external/mit/glu/dist/src/libutil/
H A Dmipmap.c111 GLint ysize, GLint group_size);
116 GLint ysize, GLint group_size);
121 GLint ysize, GLint group_size,
127 GLint ysize, GLint group_size,
133 GLint ysize, GLint group_size,
139 GLint ysize, GLint group_size,
145 GLint ysize, GLint group_size,
370 GLint element_size, GLint ysize, GLint group_size)
382 element_size,ysize,group_size);
388 padBytes = ysize - (width*group_size);
368 halveImage_ubyte(GLint components,GLuint width,GLuint height,const GLubyte * datain,GLubyte * dataout,GLint element_size,GLint ysize,GLint group_size) argument
410 halve1Dimage_ubyte(GLint components,GLuint width,GLuint height,const GLubyte * dataIn,GLubyte * dataOut,GLint element_size,GLint ysize,GLint group_size) argument
469 halveImage_byte(GLint components,GLuint width,GLuint height,const GLbyte * datain,GLbyte * dataout,GLint element_size,GLint ysize,GLint group_size) argument
511 halve1Dimage_byte(GLint components,GLuint width,GLuint height,const GLbyte * dataIn,GLbyte * dataOut,GLint element_size,GLint ysize,GLint group_size) argument
569 halveImage_ushort(GLint components,GLuint width,GLuint height,const GLushort * datain,GLushort * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
627 halve1Dimage_ushort(GLint components,GLuint width,GLuint height,const GLushort * dataIn,GLushort * dataOut,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
708 halveImage_short(GLint components,GLuint width,GLuint height,const GLshort * datain,GLshort * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
773 halve1Dimage_short(GLint components,GLuint width,GLuint height,const GLshort * dataIn,GLshort * dataOut,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
854 halveImage_uint(GLint components,GLuint width,GLuint height,const GLuint * datain,GLuint * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
919 halve1Dimage_uint(GLint components,GLuint width,GLuint height,const GLuint * dataIn,GLuint * dataOut,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
999 halveImage_int(GLint components,GLuint width,GLuint height,const GLint * datain,GLint * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
1065 halve1Dimage_int(GLint components,GLuint width,GLuint height,const GLint * dataIn,GLint * dataOut,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
1146 halveImage_float(GLint components,GLuint width,GLuint height,const GLfloat * datain,GLfloat * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
1211 halve1Dimage_float(GLint components,GLuint width,GLuint height,const GLfloat * dataIn,GLfloat * dataOut,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
1385 scale_internal_ubyte(GLint components,GLint widthin,GLint heightin,const GLubyte * datain,GLint widthout,GLint heightout,GLubyte * dataout,GLint element_size,GLint ysize,GLint group_size) argument
1602 scale_internal_byte(GLint components,GLint widthin,GLint heightin,const GLbyte * datain,GLint widthout,GLint heightout,GLbyte * dataout,GLint element_size,GLint ysize,GLint group_size) argument
1819 scale_internal_ushort(GLint components,GLint widthin,GLint heightin,const GLushort * datain,GLint widthout,GLint heightout,GLushort * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
2099 scale_internal_short(GLint components,GLint widthin,GLint heightin,const GLshort * datain,GLint widthout,GLint heightout,GLshort * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
2393 scale_internal_uint(GLint components,GLint widthin,GLint heightin,const GLuint * datain,GLint widthout,GLint heightout,GLuint * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
2680 scale_internal_int(GLint components,GLint widthin,GLint heightin,const GLint * datain,GLint widthout,GLint heightout,GLint * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
2976 scale_internal_float(GLint components,GLint widthin,GLint heightin,const GLfloat * datain,GLint widthout,GLint heightout,GLfloat * dataout,GLint element_size,GLint ysize,GLint group_size,GLint myswap_bytes) argument
3819 GLint myswap_bytes, groups_per_line, element_size, group_size; local in function:gluBuild2DMipmapLevelsCore
4888 GLint group_size; local in function:fill_image
5151 GLint group_size; local in function:empty_image
[all...]
/xsrc/external/mit/MesaLib/dist/src/broadcom/cle/
H A Dv3d_decoder.h72 uint32_t group_size; member in struct:v3d_group
H A Dv3d_decoder.c236 &group->group_size,
819 iter->group->group_size);
/xsrc/external/mit/MesaLib.old/dist/src/compiler/nir/
H A Dnir_lower_system_values.c105 nir_ssa_def *group_size = build_local_group_size(b, bit_size); local in function:build_global_group_size
107 return nir_imul(b, group_size, num_work_groups);
118 nir_ssa_def *group_size = build_local_group_size(b, bit_size); local in function:build_global_invocation_id
122 return nir_iadd(b, nir_imul(b, group_id, group_size), local_id);
/xsrc/external/mit/MesaLib.old/dist/src/broadcom/cle/
H A Dv3d_decoder.h72 uint32_t group_size; member in struct:v3d_group
H A Dv3d_decoder.c225 &group->group_size,
794 iter->group->group_size);
/xsrc/external/mit/MesaLib/dist/src/compiler/nir/
H A Dnir_lower_system_values.c57 nir_ssa_def *group_size = nir_load_workgroup_size(b); local in function:build_global_group_size
59 return nir_imul(b, nir_u2u(b, group_size, bit_size),
448 nir_ssa_def *group_size = nir_load_workgroup_size(b); local in function:lower_compute_system_value_instr
453 nir_u2u(b, group_size, bit_size)),
/xsrc/external/mit/MesaLib.old/dist/src/intel/common/
H A Dgen_decoder.h115 uint32_t group_size; member in struct:gen_group
H A Dgen_decoder.c209 &group->group_size,
868 return iter->group->group_offset + (group_iter * iter->group->group_size);
/xsrc/external/mit/MesaLib.old/dist/src/gallium/drivers/r600/
H A Devergreen_compute.c586 int group_size = 1; local in function:evergreen_emit_dispatch
593 /* Calculate group_size/grid_size */
595 group_size *= info->block[i];
611 radeon_set_config_reg(cs, R_008970_VGT_NUM_INDICES, group_size);
619 group_size);
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/r600/
H A Devergreen_compute.c607 int group_size = 1; local in function:evergreen_emit_dispatch
615 /* Calculate group_size/grid_size */
617 group_size *= info->block[i];
633 radeon_set_config_reg(cs, R_008970_VGT_NUM_INDICES, group_size);
641 group_size);
/xsrc/external/mit/MesaLib/dist/src/intel/compiler/
H A Dbrw_fs.h371 fs_reg group_size[3]; member in class:fs_visitor
H A Dbrw_fs.cpp1233 for (unsigned i = 0; i < ARRAY_SIZE(this->group_size); i++)
1234 this->group_size[i] = v->group_size[i];
10348 unsigned group_size)
10362 if ((mask & simd8) && group_size <= 8 * max_threads) {
10371 if ((mask & simd16) && group_size <= 16 * max_threads)
10375 assert(group_size <= 32 * max_threads);
10390 info.group_size = sizes[0] * sizes[1] * sizes[2];
10392 brw_cs_simd_size_for_group_size(devinfo, prog_data, info.group_size);
10393 info.threads = DIV_ROUND_UP(info.group_size, inf
10346 brw_cs_simd_size_for_group_size(const struct intel_device_info * devinfo,const struct brw_cs_prog_data * cs_prog_data,unsigned group_size) argument
[all...]
H A Dbrw_compiler.h1783 uint32_t group_size; member in struct:brw_cs_dispatch_info
H A Dbrw_fs_nir.cpp121 group_size[i] = fs_reg(UNIFORM, uniforms++, BRW_REGISTER_TYPE_UD);
3968 group_size[i]);
5527 const unsigned group_size = dispatch_width / groups; local in function:fs_visitor::nir_emit_intrinsic
5529 const unsigned cluster = (i * group_size) / cluster_size;
5531 bld.group(group_size, i).MOV(horiz_offset(dest, i * group_size),
/xsrc/external/mit/MesaLib.old/dist/src/intel/vulkan/
H A DgenX_pipeline.c2054 uint32_t group_size = cs_prog_data->local_size[0] * local in function:compute_pipeline_create
2056 uint32_t remainder = group_size & (cs_prog_data->simd_size - 1);
/xsrc/external/mit/MesaLib.old/dist/src/intel/compiler/
H A Dbrw_fs_nir.cpp4935 const unsigned group_size = dispatch_width / groups; local in function:fs_visitor::nir_emit_intrinsic
4937 const unsigned cluster = (i * group_size) / cluster_size;
4939 bld.group(group_size, i).MOV(horiz_offset(dest, i * group_size),

Completed in 55 milliseconds

12