URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=d11c9f983632d35e7010b470fe0af2f6a2c087bf
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Dec 4 15:27:40 2023 -0400
asahi: clamp draw count for mdi
spec req. KHR-GL43.indirect_parameters_tests.MultiDrawArraysIndirectCount
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=fdec9dcf05811e79866cc3af2b513558500e82f8
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Dec 4 14:36:00 2023 -0400
asahi: wire up hardware gl_PrimitiveID
when FS reads but no GS in the pipeline, the hw supplies for us. fixes
KHR-GL43.shader_image_size.basic-*-fs-*
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=1e2de134ad9946dad9946f471b292f7baf7f81e5
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Dec 4 14:14:03 2023 -0400
asahi: respect render condition for compute
KHR-GL43.compute_shader.conditional-dispatching
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=1a39d1c73a86807daa9eed0f626fd8ce93ffdd02
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Dec 4 11:22:14 2023 -0400
asahi: allow more format reinterpretation
This seems to be the hw rule... would like to confirm with perf counters
though...
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=e69a0f830eaa5c17d97a7c1527b84af7c205a66e
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Dec 1 17:41:56 2023 -0400
asahi: fix size calculation for 2d msaa arrays
otherwise the hw can overprefetch. fixes
KHR-GL42.shader_image_load_store.basic-allTargets-load-ms
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=982e644d182bb98b13c1d91f24c9f1a9c1f2112a
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Dec 1 17:24:10 2023 -0400
agx: don't produce split of immediate
can't be consumed, affects
KHR-GL42.shader_image_load_store.basic-allTargets-load-ms
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=6e2c71dc3b0905ebe319abe86b4226c2eba3f41d
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Dec 1 17:13:58 2023 -0400
agx: Lower 64-bit I/O to 32-bit
Fixes KHR-GL42.vertex_attrib_64bit.*
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=d6474be46bb6e8aef15ed55f9e6153ba09097d6b
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Dec 1 15:32:25 2023 -0400
agx: fix fp64 lowering options
we have no fp64 whatsoever.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=8d451fe9f27ffc6d1e73cb79db1592a56803afea
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 30 21:14:26 2023 -0400
asahi: fix integer RT clamping
fixes the rest of KHR-GL33.packed_pixels.*
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=01d0fb1cdeef106e430f9c35afe2364cc98cff7f
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 30 19:00:40 2023 -0400
asahi: fix pbe swizzling
fixes cases in KHR-GL33.packed_pixels.rectangle.*. matches what the powervr
driver does.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=6d05bf8761a3324c2091dd41ab05270600af900e
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 30 18:26:17 2023 -0400
asahi: fix dupe rgb65 formats
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=b68caa13e415a1de260207008af3d66db226c06a
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 30 17:19:45 2023 -0400
asahi: add more BGR formats
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=c89f0becf7ce6ac7f49e52d91eb6cb416f579a80
Author: Alyssa Rosenzweig <[email protected]>
Date: Wed Nov 29 17:40:42 2023 -0400
asahi: Implement ARB_cull_distance
Passes KHR-GL33.cull_distance.* and the piglits.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=ba077d899e3ac58b88e259d49f9ae6214afb0837
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 30 16:04:36 2023 -0400
asahi: handle compact clip/cull in gs component gather
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=f02190b6886ce155cd0aa5faa230a06b28ae7a45
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 30 16:04:17 2023 -0400
asahi: prepare gs copy shaders for compact clip/cull
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=0dc004888c0f01b984376b3fbfc71b220d52f437
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 30 11:05:18 2023 -0400
asahi: handle some components/offsets in GS lowering
occurs for compact clip/cull xfb. not hard to deal with, do so instead of
getting caught up in assertions.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=17f348f73a9b5c6aaa3159f31565968c58220b98
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 28 20:39:30 2023 -0400
asahi: Implement ARB_viewport_array
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=af9241ce923cd6a087f76bb96a9cfd5dbc9c2ef7
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 28 19:44:33 2023 -0400
asahi: add XML for multiple viewports
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=3435ccb49a9b4557868d3b9448a9aaa9e7aca97f
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 28 19:36:28 2023 -0400
asahi: allow empty scissor box
we can't cull on the cpu when we have a scissor array, so don't try.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=bb59c787ecd9bc25e722b0af0813b5da3f410721
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 28 20:59:25 2023 -0400
agx: report if we have a nonzero viewport
so driver can optimize.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=bc7afbf23dc6b1228ff0ef0164369e8d904f16ff
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 28 20:05:30 2023 -0400
agx: allocate varying slot if writing viewport only
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=643acacd1b183a3e0c4b3d4565d6d9637a0db946
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 28 17:55:46 2023 -0400
agx: note that sample_mask runs occlusion queries
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=79e58e1d7709baad7602ff37c5e2825cd1315e5f
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 28 17:49:18 2023 -0400
agx: handle force early-z + discard
fixes ./arb_shader_image_load_store-early-z. experimentally, an opaque pass
type
works too but better match what the blob does.
also, I now have proof that sample_mask triggers occlusion query updates
because
if you run it multiple times, you get >1 hits per fragment in a counting
query
:p
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=3987c8a35f94fbcbafc1549959d28e379841338d
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 27 16:30:43 2023 -0400
agx: remove spurious z/s writes in force early-z shaders
fixes crash in arb_shader_image_load_store-early-z
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=c43c90a5faf37f48e245165c5c3df837c5d08db0
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 27 14:39:56 2023 -0400
asahi: rewrite pointsize handling
In the wise words of Mike Blumenkrantz, "I hate gl_PointSize and so can
you".
The mesa/st lowering won't mesh well with vertex shader epilogues, and it
falls
over in various circumstances. I am too tired to go against the grain, so
let's
just pretend to be a normal gallium driver and trust in the rasterizer CSO,
lowering point size internally. This properly handles transform feedback
without
any hacks, both GL and GLES behaviours, etc.
Fixes:
KHR-GL31.transform_feedback.capture_vertex_separate_test
gl-2.0-large-point-fs
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=aa1849a541504464f5aec385f1f6e194ca371aad
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Nov 26 18:05:44 2023 -0400
asahi: assert hw invariant
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=23f216d6e74331fa8053401b7bce96e0bba47598
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 27 11:53:14 2023 -0400
asahi: Lower edge flags
With the common geometry shader based lowering added for zink. Fixes edge
flag
related piglits.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=f4a648c607ecff672094a277cf79ea76b9fa0324
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 27 11:34:31 2023 -0400
asahi: Unroll GS/XFB primitive restart on the GPU
..and fix bugs versus the CPU unroll while we're at it. CPU based unrolling
is
invalid in Vulkan, but this slow-as-dogs GPU unroll is ok.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=15957219ad02657f18047a792cca146f37cb5394
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Nov 26 21:12:55 2023 -0400
agx: rework libagx linking a bit
for correctness with generic ptrs, avoids splat with the next patch.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=4a4c6d1bc6d0d2396d14ede923a172b4147dadd9
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Nov 26 21:13:53 2023 -0400
agx: Avoid scratch mem with tri strip w/ adjacency
with restart unroll kernel where nir fails to optimize this away without a
little help from us.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=7f9ef5b17697422bd37c5870a0a3bc6d133ec084
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Nov 26 17:03:37 2023 -0400
agx: fix VARYING_SLOT_COL0 getting flatshaded
it's a bit mask.
didn't fix the piglit i was debugging :-(
but did fix the shadow glitching out in neverball.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=643757843576ae5cf3f8eed6de49e4a4a4e8c724
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 22:41:04 2023 -0400
asahi: add xml for flatshading fans
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=403a20a9f27b9a147449c7c13361ff6acb0ae359
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 22:31:15 2023 -0400
asahi: rework cf binding xml
for flat shading of fans.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2fec6bf95150057f6b872fc46c1c35597ddddba0
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 19:42:57 2023 -0400
asahi: fix tri fan enum
from tracing macos. fixes piglits:
spec@!opengl [email protected] 100000 varray
gl_triangle_fan
spec@!opengl [email protected] 100000 vbo gl_triangle_fan
spec@!opengl 1.4@triangle-rasterization-overdraw
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=6ae72a2f2a3dfbe30cf19ea08a060038b6721a23
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Nov 26 13:13:10 2023 -0400
asahi: Support L/A/I formats for texture buffers
mesa/st doesn't know how to emulate them. Fixes
arb_texture_buffer_object-formats.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=5b33c74626a471258548660abb82348e664b4db4
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 12:08:19 2023 -0400
agxdecode: fix stack smash with border colour
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=a8857028bb797da617c9d27f80fdc3526e620172
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 12:04:03 2023 -0400
asahi: add static assert
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2be37d1c9659bb13285925b1ced7f1c8c68c95cc
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 14:18:02 2023 -0400
asahi: double depth bias
fixes gl-1.4-polygon-offset, other drivers do this too.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=3af825ed96f2714605cbbac03a104d48fe50b814
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Nov 23 11:05:42 2023 -0400
asahi: move heap alloc to first use
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=0fa7252d8a9d450a55f7e6f835c1c3afd75f1f2e
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 18 12:19:04 2023 -0400
asahi: Implement multidraw indirect
GS only for now (inserting a passthru GS if needed). This should be
optimized
later, but it's ~correct.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=5987e47a2967b1dcc13efcb926e1a86d641aec86
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Nov 17 13:49:47 2023 -0400
asahi: rework GS input assembly
in prep for tessellation (which will share the IA lowering), and for
multidraw
indirect (which greatly complicates IA lowering with geom/tess).
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=a816350d950e7dfc3d735d9dab5ce468cde2cb4d
Author: Alyssa Rosenzweig <[email protected]>
Date: Wed Nov 15 21:14:13 2023 -0400
asahi: force GS for indirect prim gen query
removes one more indirect cpu fallback (invalid in vulkan)
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=0805fef082b5384c1cfaf9e5cc816c1540e0f3db
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 10:34:46 2023 -0400
asahi: make UB easier to see
would've saved us
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=a12d2689d8c78d5ace7f49f4309ff779bbf27350
Author: Alyssa Rosenzweig <[email protected]>
Date: Wed Nov 15 22:18:27 2023 -0400
asahi: rm unnecessary uniform upload for GS
already done in launch gs.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2220044ca2a62fa738fb0ee9f4d13aa2dd92e553
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 18 12:17:09 2023 -0400
asahi: remove dead declarations
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=9c66ae9b36d158faaa57ac46c877709dbab17743
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 18 21:24:40 2023 -0400
asahi: use agx_push
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=4d48574bd7978483211282756045550a518ecadf
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 18 21:16:33 2023 -0400
asahi: collapse unreachable condition
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=09e46aa1683905d01de95dbd41ea8abcaeb92c55
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 18 21:28:16 2023 -0400
asahi: add agx_push macro
Thanks, Ella!
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=31b1bdb475aa0b36c2124c545a6529404b758e3d
Author: Alyssa Rosenzweig <[email protected]>
Date: Sat Nov 25 10:12:35 2023 -0400
asahi: fix destroy_query leaving dangling references
this was fixed for occlusion queries already, but other queries have
equivalent
issues.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2d8a714f9c3afaa331c1fb4a82b61b3cc057b294
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Nov 24 23:34:00 2023 -0400
asahi: choose staging bind better
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=5257283941a1cd0254aa5d480a8213d7d2f1e1e6
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Nov 24 22:48:53 2023 -0400
asahi: use correct target packing PBE
harmless, but more correct.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=a3ae9e1a598ed9b05e460cc14e8fa56a23867779
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Nov 24 10:02:47 2023 -0400
asahi: fix layout transitions with arrays
don't minify the layer count for non-3D!
Affects: dEQP-GLES31.functional.copy_image.*array
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=25d185a501c561b0103cfb787d5cdc668c038ee4
Author: Asahi Lina <[email protected]>
Date: Fri Nov 24 16:19:08 2023 +0900
ail: Fix tile size & strides for compressed textures
Compressed textures have two additional quirks that affect the tiling
code (but not the mip offsets): they get extra stride padding in some
cases for the large miptree, and the tile size is based on the POT size
and not the real size for the small miptree.
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=be3890a898559db401c928c98b485af2a068388b
Author: Asahi Lina <[email protected]>
Date: Fri Nov 24 16:14:38 2023 +0900
ail: Add explicit specification of mip level strides
For compressed textures, mip levels > 0 can have additional stride
padding. This (in some cases) affects the tile stride calculation, so it
cannot be implicitly represented with the existing members.
Add an explicit array containing the stride, in elements, of each
miptree level. The tiling code uses this instead of the minified and
element-aligned width when computing tile addressing.
This commit should be a functional no-op.
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2221eb6cecb52c5aec8bd119a41378e1713b0941
Author: Asahi Lina <[email protected]>
Date: Thu Nov 23 02:09:10 2023 +0900
ail: Fix miptree offset generation for compressed textures
For compressed textures, the POT miptree starting size is calculated
backwards (POT then minify instead of minify then POT).
In addition, the existing POT miptree start level code does not work for
compressed textures. Due to the extra block alignment requirement each
step of the way, we can no longer get away with nice log-based O(1)
math. Switch to a loop. This should be equivalent for uncompressed
textures, but yields different results with compression (element size >
1x1).
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=5382f57e81ddd0b430d41bd50558b7513c5dac5d
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 21 19:27:12 2023 -0400
asahi: advertise ARB_shader_texture_image_samples
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=bc6b2d087be172b0f3fc6c506536352091b719c9
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 21 19:26:53 2023 -0400
agx: wire up texture_samples/image_samplers
CL makes this too easy, lmao
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=6979a1aa07defc4fec5ff2422368129c66441e19
Author: Karol Herbst <[email protected]>
Date: Tue Aug 29 20:54:14 2023 +0200
nir/opt_preamble: make load_workgroup_size handling optional
not all drivers support it being in the preamble, e.g. asahi.
Signed-off-by: Karol Herbst <[email protected]>
Reviewed-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=3ddb07c36b7c602eeff43bb908f4442f58f4db5b
Author: i509VCB <[email protected]>
Date: Wed Nov 22 00:30:15 2023 -0600
asahi,docs: add PBE to hardware glossary
Signed-off-by: i509VCB <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=47337e791861327e02063b77622b0d6bfe18a7ed
Author: Alyssa Rosenzweig <[email protected]>
Date: Wed Nov 15 15:23:38 2023 -0400
asahi: Implement draw parameters
This is the easy part, passes the piglits.
---
N.b.: this also includes a bug fix for ARB_base_instance that would be
nontrivial to extract out, so I'm backporting the whole feature for
release. How
terrible, more features :-P
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=31f1ef0a79d317d7c342c0797e1e0d45c282329a
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 13 18:36:05 2023 -0400
asahi: Early out for GS + rast discard
Reduces overhead for XFB.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2129fe30bcccd73975f1d489154d06df3d7da30d
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 16:08:19 2023 -0400
asahi: use GS for first-provoking fans
workaround hw bug / missing feature, in a vk compliant way.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=e10e21120b10ef04540e69e291c85fff4c420528
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 16:02:41 2023 -0400
asahi: Rotate tri fans based on provoking vtx
I don't have a spec citation for the rotation but it's implied by the GL
and VK
specs taken together with piglit.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=5bae4bfc8c9462d5d7544f3295b3aa06962def2d
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 15:20:51 2023 -0400
asahi: defeature quads
fixes xfb piglits. i am not paid enough to care.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=decd134c0c4054bedbc408b6465c85bf98d24280
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 15:09:38 2023 -0400
asahi: fix xfb of pointsize when not drawing points
stupid case.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=9d1a0f11e22b461fc9acc6b2bf0620d73cc51097
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Jul 21 08:22:40 2023 -0400
agx: Fix flatshading of matrices
Fixes dEQP-VK.glsl.conversions.scalar_to_matrix.float_to_mat4_vertex
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=9fc23df0d589f919705e69a850f8e8cbc023c709
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 13:48:51 2023 -0400
asahi: flush before resource transition
otherwise data_valid is not valid! fixes arb_shader_image_load_store-bitcast
and who knows what else.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=e637ccff3633b312561037806dcaf188d7c1cbbe
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 13:45:46 2023 -0400
asahi: blit with the old format when transitioning
dest is uncompressed, it can take it. but src is compressed so we don't
want to
view. bugfix by inspection
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=9031f04642a402083702018871595435f015e451
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 13:44:07 2023 -0400
asahi: minify when blitting for transition
asahi version of
https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26077/diffs
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=a0485292af54294522c8544562bf50822e5f7ab7
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 12:59:53 2023 -0400
asahi: bump glsl version
should work and fixes a buggy test falling over due to missing gpu_shader5
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2ad5bcc41e6c7aea9e24314c3267278f3d0f8e98
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 13:21:08 2023 -0400
asahi: fix output to non-rast streams
fixes arb_gpu_shader5-emitstreamvertex_nodraw
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=79e37f75817e3aa639f3de0047ddcc566cc1b48b
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 13:10:39 2023 -0400
asahi: implement xfb stream queries
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=0099315edf479fd5187c340df8847211ccbeee59
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 12:22:58 2023 -0400
asahi: fix meta usc builder allocation
otherwise can usc overflow (caught by the usc builder validation :) )
fixes clearbuffer-mixed-format
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=f82264fec0e88d3591f28aebea51f8a2e89e3029
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 12:11:01 2023 -0400
asahi: return GL_OOM for excessive image sizes
fixes piglit max-texture-size
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=fd91d4648745ca3dc1ee8d001ff2a9d80acf6590
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 12:09:40 2023 -0400
ail: handle >4GiB textures
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=7a7a3b884795301013f7ae1e98b15e22c0641b5e
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 11:56:28 2023 -0400
asahi: defer texture packing to draw-time
needed for correctness with layout transitions.
fixes arb_shader_image_load_store-host-mem-barrier
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=b74d2dcd57f54c58f2a5170afb9c7aeb74f903d1
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 11:10:08 2023 -0400
asahi: use 2D descriptors for cubes
fixes arb_shader_image_load_store-invalid case imageLoad/address bounds
test/imageCube/rgba32f
this is also better codegen since it avoids the wacko division by 6.
although it
creates a div by 6 in imageSize, that's better because that one is much more
likely to hoist to the preamble. probably should've done this from the
start.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=86c4a7276766facef284abeae4fc220caee64da3
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 10:48:09 2023 -0400
asahi: rm compact image atomic descriptors
these cause robustness problems -- since the target type might not match the
shader for invalid apps -- and are a dubious microoptimization. can revisit
later. for now, fixes imageAtomic*/target mismatch test.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=b13e3adb04e55789bbabcbb46dfc7f6eb6d764bd
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 10:35:03 2023 -0400
asahi: fix imageSize of null image
Fixes faulting in imageAtomicAdd/unbound image test.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=0cd032e4bb1c8a21e7848a571d8f1ab360955b7d
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 10:26:45 2023 -0400
asahi: Be robust with arrays of images
fixes imageLoad/index bounds test subcase.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=b0f4b0a9eff740f9799786eacd3c0fc143c9251a
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 09:12:41 2023 -0400
asahi: handle null PBE
fixes some subcases of arb_shader_image_load_store-invalid
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=c73d7d042cbf538726a1d320d34ce9b776db88e2
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 08:33:23 2023 -0400
asahi: fix dirty tracking fail with point sprites
fixes arb_point_sprite-checkerboard
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=683dac24b29accef2f1f8b2d4625d0eeab6434e8
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 08:24:45 2023 -0400
asahi: be robust about null xfb
fixes arb_enhanced_layouts-transform-feedback-layout-qualifiers tests.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=3ac44d8c5e55db1f6ecb194893bbb605daea3530
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 08:22:01 2023 -0400
asahi: remove bogus assertion
replace with optional debug flag for retaining debugability but getting
conformant behaviour by default. fixes piles of piglit crashes.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=e3c528068f346fa79a320e80c30be7964699514f
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 08:14:56 2023 -0400
asahi: bump limits
fixes gl-3.3-minmax.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=84a8324c552763d66e1659f312823a47cd867244
Author: Alyssa Rosenzweig <[email protected]>
Date: Mon Nov 20 08:09:52 2023 -0400
asahi: handle self blits
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=de6336381b7ee96bef9ecefb93192e83b7e1ecc1
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Nov 19 19:55:19 2023 -0400
asahi: clamp clear colours
fixes arb_texture_view-rendering-formats_gles3
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=acd095f03dd130e1ddfc7d691c062d77e432b936
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Nov 19 19:39:51 2023 -0400
asahi: init clear colour between batches
should be a noop, but safer
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2cceacdb8eb30fb7f0708e957b90fcfd58ad94db
Author: Janne Grunau <[email protected]>
Date: Sun Nov 19 22:54:17 2023 +0100
asahi: Fix typo in arch check in agx_get_gpu_timestamp
Signed-off-by: Janne Grunau <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=4ff78407f717f311011a6c4fb939757b36fa7835
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Nov 17 17:44:29 2023 -0400
asahi: Sync heap size
Hot fix... gpu alloc needs bigger reworks but that's probably not going to
happen until tess is done & we can see the whole picture.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=afb60d7707f835e3a8ba2e3bf16518af01509b01
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Nov 17 17:20:17 2023 -0400
asahi: fix index bias with GS/XFB
noticed when bringing up mdi.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=45ef977481e2b825e953d64464a42bf71cb90820
Author: Asahi Lina <[email protected]>
Date: Fri Nov 17 19:27:37 2023 +0900
asahi: Add extra barrier for texture atomics on G13X
Found experimentally. Fixes
KHR-GLES31.core.texture_buffer.texture_buffer_atomic_functions on G13D.
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=376c2697dc1984a58b072d946c2727bb5c93c4e6
Author: Asahi Lina <[email protected]>
Date: Fri Nov 17 19:27:04 2023 +0900
asahi: Add more memory barrier opcodes
These are used by the helper program, and at least one experimentally
fixes texture atomics on G13X.
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=c507f4a330d1fbbc753ab5f3f30060b82ea278f5
Author: Alyssa Rosenzweig <[email protected]>
Date: Fri Jul 14 19:21:28 2023 -0400
asahi: Identify bicubic filtering mode
Officially undocumented but supported by MSL.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=58d6374b4c9a11cb589909395d64098458a9a22c
Author: Alyssa Rosenzweig <[email protected]>
Date: Thu Jul 13 22:08:07 2023 -0400
asahi: Identify Primitive ID frag input
With a name from powervr :)
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=0cb6a993a8c346bc74f138e423b5b807b8f7bb22
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 7 13:42:01 2023 -0400
asahi: Add XML for hw tessellation
AFAICT, there's no way to use this with...
* transform feedback
* geometry shaders
* isolines
* points mode
...so it's not terribly useful to us. But worth knowing it exists.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=2c328f4f8abcff8bf3b723339cd10e39e08154f4
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 7 13:43:01 2023 -0400
asahi: Add half float type to genxml
Used with the tessellator.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=3da3b18d0c4bac6b1ffe2bb621ce055a1e9afcb8
Author: Alyssa Rosenzweig <[email protected]>
Date: Tue Nov 7 13:47:49 2023 -0400
asahi: Quiet clang warning
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=033bb91468d21a1b5de3d3209cfe21c55e0ffc2f
Author: Alyssa Rosenzweig <[email protected]>
Date: Sun Jul 9 18:09:16 2023 -0400
asahi/decode: Decode multiple macOS commands
We get a CDM+VDM pair for OpenGL tess, decode them all for better r/e.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=1b1a0e0ce73f7ce5988abeb14a26d879595b08e7
Author: Asahi Lina <[email protected]>
Date: Fri Nov 10 15:14:00 2023 +0900
asahi: Move USC cache flush to agx_batch_init_state
This shouldn't make a difference, but it's cleaner to do it here, since
then we don't have to check whether we have any draws.
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=5a9136a0ef12e2c066f9b22371eb80ab75e221db
Author: Asahi Lina <[email protected]>
Date: Fri Nov 10 14:33:52 2023 +0900
asahi: Add extra CDM barrier bit for G13X
I don't know if we need the other bits yet. I'm assuming the logic here
is the same as we used to use for VDM...
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=c20210c6436693b3e0b54e066f8d1a36d07681cc
Author: Asahi Lina <[email protected]>
Date: Fri Nov 10 14:10:59 2023 +0900
asahi: Fix CDM Launch/Barrier naming
"Launch" is actually just a barrier, and it seems likely to use the same
bit assignments as in VDM...
Signed-off-by: Asahi Lina <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
URL:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=412922ed73d8f7663993ee24bdff8059bbe4bffe
Author: Alyssa Rosenzweig <[email protected]>
Date: Wed Nov 8 17:01:38 2023 -0400
agx: Hotfix for stack_adjust in GS
Spurious, turn this off for now, it's inert rn anyway.
Signed-off-by: Alyssa Rosenzweig <[email protected]>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/26614>
