Home
last modified time | relevance | path

Searched refs:wg_size (Results 1 - 6 of 6) sorted by relevance

/third_party/mesa3d/src/broadcom/common/
H A Dv3d_util.c36 uint32_t wg_size) in v3d_csd_choose_workgroups_per_supergroup()
48 * max_batches_per_sg = (wg_size * max_wgs_per_sg) / elements_per_batch in v3d_csd_choose_workgroups_per_supergroup()
50 * max_batches_per_sg = wg_size in v3d_csd_choose_workgroups_per_supergroup()
52 uint32_t max_batches_per_sg = wg_size; in v3d_csd_choose_workgroups_per_supergroup()
63 uint32_t max_wgs_per_sg = max_batches_per_sg * 16 / wg_size; in v3d_csd_choose_workgroups_per_supergroup()
77 uint32_t unused_lanes = (16 - ((wgs_per_sg * wg_size) % 16)) & 0x0f; in v3d_csd_choose_workgroups_per_supergroup()
31 v3d_csd_choose_workgroups_per_supergroup(struct v3d_device_info *devinfo, bool has_subgroups, bool has_tsy_barrier, uint32_t threads, uint32_t num_wgs, uint32_t wg_size) v3d_csd_choose_workgroups_per_supergroup() argument
H A Dv3d_util.h36 uint32_t wg_size);
/third_party/mesa3d/src/gallium/drivers/v3d/
H A Dv3dx_draw.c1403 uint32_t wg_size = info->block[0] * info->block[1] * info->block[2]; in v3d_launch_grid() local
1413 num_wgs, wg_size); in v3d_launch_grid()
1415 uint32_t batches_per_sg = DIV_ROUND_UP(wgs_per_sg * wg_size, 16); in v3d_launch_grid()
1419 DIV_ROUND_UP(rem_wgs * wg_size, 16); in v3d_launch_grid()
1424 submit.cfg[3] |= (wg_size & 0xff) << V3D_CSD_CFG3_WG_SIZE_SHIFT; in v3d_launch_grid()
/third_party/mesa3d/src/broadcom/vulkan/
H A Dv3dv_cmd_buffer.c3603 submit->cfg[4] = DIV_ROUND_UP(info->wg_size, 16) * in v3dv_cmd_buffer_rewrite_indirect_csd_job()
3671 const uint32_t wg_size = cpd->local_size[0] * in cmd_buffer_create_csd_job() local
3681 num_wgs, wg_size); in cmd_buffer_create_csd_job()
3683 uint32_t batches_per_sg = DIV_ROUND_UP(wgs_per_sg * wg_size, 16); in cmd_buffer_create_csd_job()
3687 DIV_ROUND_UP(rem_wgs * wg_size, 16); in cmd_buffer_create_csd_job()
3691 submit->cfg[3] |= (wg_size & 0xff) << V3D_CSD_CFG3_WG_SIZE_SHIFT; in cmd_buffer_create_csd_job()
3693 *wg_size_out = wg_size; in cmd_buffer_create_csd_job()
3819 &job->cpu.csd_indirect.wg_size); in cmd_buffer_dispatch_indirect()
H A Dv3dv_private.h1036 uint32_t wg_size; member
/third_party/mesa3d/src/broadcom/compiler/
H A Dnir_to_vir.c4384 int wg_size = (c->s->info.workgroup_size[0] * in nir_to_vir() local
4388 ffs(util_next_power_of_two(MAX2(wg_size, 64))) - 1; in nir_to_vir()

Completed in 21 milliseconds