fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2026-01-25 16:40:30 +01:00
Code Issues Projects Releases Packages Wiki Activity Actions 1

panfrost: Fix transform feedback on v9

Browse source 
We were using a stale FAU buffer which meant we wrote to garbage addresses. I'm
guessing this was fallout from the big sysval rework but not 100% sure.

Signed-off-by: Alyssa Rosenzweig <alyssa@rosenzweig.io>
Cc: mesa-stable
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/24199>
This commit is contained in:
Alyssa Rosenzweig 2023-07-17 16:54:58 -04:00 • committed by Marge Bot
parent 75990e5564
commit c282f80c98
1 changed files with 4 additions and 4 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

8
src/gallium/drivers/panfrost/pan_cmdstream.c
View file

@ -3436,6 +3436,10 @@ panfrost_launch_xfb(struct panfrost_batch *batch,
batch->rsd[PIPE_SHADER_VERTEX] =
panfrost_emit_compute_shader_meta(batch, PIPE_SHADER_VERTEX);
batch->uniform_buffers[PIPE_SHADER_VERTEX] =
panfrost_emit_const_buf(batch, PIPE_SHADER_VERTEX, NULL,
&batch->push_uniforms[PIPE_SHADER_VERTEX], NULL);
#if PAN_ARCH >= 9
pan_section_pack(t.cpu, COMPUTE_JOB, PAYLOAD, cfg) {
cfg.workgroup_size_x = 1;
@ -3466,10 +3470,6 @@ panfrost_launch_xfb(struct panfrost_batch *batch,
info->instance_count, 1, 1, 1,
PAN_ARCH <= 5, false);
batch->uniform_buffers[PIPE_SHADER_VERTEX] =
panfrost_emit_const_buf(batch, PIPE_SHADER_VERTEX, NULL,
&batch->push_uniforms[PIPE_SHADER_VERTEX], NULL);
panfrost_draw_emit_vertex(batch, info, &invocation, 0, 0, attribs,
attrib_bufs, t.cpu);
#endif