ChanServ changed the topic of #dri-devel to: <ajax> nothing involved with X should ever be unable to find a bar
<cmarcelo> alyssa: probably I wasn't sure whether all gallium drivers would be able to support it. the SPIR-V for GL comes with GL 4.6, so there might be assumptions that those shaders make about what's there for GL...?
<cmarcelo> maybe I was too conservative? (-:
<cmarcelo> the GL_ARB_gl_spirv requires 3.3, so we should be fine in that camp.
<karolherbst> maybe we can nuke that variable pointer cap as well? not sure if that requires anything from drivers either
<cmarcelo> maybe start enabling it for other drivers until all are happy and drop the cap
<karolherbst> I think the problem is rather that there aren't that many tests for it, are there?
<karolherbst> probably nobody would notice the bugs anyway
<cmarcelo> there's some on piglit, but I remember some shenanigans to run them.. maybe was fixed now.
<karolherbst> I think the CTS has like 8 tests? Once I enabled that on nouveau it just worked
<cmarcelo> karolherbst: yeah, I remember it was not really much there.
rotationmatrix has quit [Remote host closed the connection]
<cmarcelo> karolherbst: still would be nice at least do a sanity check before enabling/nuking. maybe some driver is unhappy with some NIR coming out of our spirv parser.
<cmarcelo> sanity check of the drivers that don't enable it yet
<karolherbst> yeah.. that's what I would be worried about
rotationmatrix has joined #dri-devel
sh-zam has joined #dri-devel
sh_zam has quit [Read error: Connection reset by peer]
<jenatali> I'd assumed that since there was a cap I'd need to do something special to handle it
pcercuei has quit [Quit: dodo]
<karolherbst> is there a good way of testing dozen locally? I think my MR breaks it real hard: https://gitlab.freedesktop.org/mesa/mesa/-/jobs/30698605/raw
<alyssa> jenatali: Also my assumption
<jenatali> karolherbst: that looks pretty broken... It only runs on Windows and WSL right now. I can help on Monday
<karolherbst> it's this MR if you didn't guess that already: https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/19381
<karolherbst> I can see many reasons it fails, but given that nothing else regressed :/
<karolherbst> jenatali: I might not be around on monday as there is a public holiday and I might just game games all day lol
<jenatali> Yeah I'll take a look first chance I get
<karolherbst> cool, thanks
<alyssa> why are we all on irc today anyway it's saturday
jessica_24 has quit [Quit: Ping timeout (120 seconds)]
jessica_24 has joined #dri-devel
abhinav__ has quit [Quit: Ping timeout (120 seconds)]
abhinav__ has joined #dri-devel
<karolherbst> what's a saturday?
<karolherbst> also, for me it's sunday
<alyssa> go to sleep karol
<alyssa> ;p
<karolherbst> rude
<alyssa> i'm sorry
<alyssa> i didn't mean to be rude
<karolherbst> I am sure you are not, and you wanted to be rude :P
<alyssa> the :P suffix makes me think that's also a joke
<alyssa> how many layers of irony are we on right now
<karolherbst> it's totaly not, I am dead serious as always
<karolherbst> too many... way too many
<karolherbst> what's even real at this point
andrey-konovalov has quit []
<alyssa> brain
andrey-konovalov has joined #dri-devel
<alyssa> why must gallium_hud take up an entire render pass >.>
<alyssa> I have a driver hack to make it not do that, but I am quite certain it's not conformant
<HdkR> Powerful HUD
<alyssa> It does not seem trivial to teach gallium_hud not to do that, either
<alyssa> the depth/stencil buffer thing can be worked around in the driver, the sRGB thing can't..
<jenatali> karolherbst: It's subpass inputs... glsl_type::get_texture_instance for a subpass dimension returns an image var instead of a texture var
<jenatali> Since our Vulkan driver uses lower_readonly_images_to_tex
camus has joined #dri-devel
<jenatali> Eh it's still not making total sense though
<jenatali> Ah it's because it moved from image -> uniform var mode, but the type is still an image :(
<alyssa> HdkR: bad gallium integration i guess
<HdkR> alyssa: Is it just a perf concern?
<alyssa> yeah
co1umbarius has joined #dri-devel
<HdkR> alyssa: Now I'm curious if there are users using it instead of something like mangohud :D
columbarius has quit [Ping timeout: 480 seconds]
<jenatali> karolherbst: Commented with a fix on your MR
<alyssa> HdkR: yes
danvet has joined #dri-devel
<HdkR> alyssa: Interesting, I would have assumed it's mostly developer facing
<alyssa> user/developer is a permeable boundary
hakzsam has quit [Read error: Connection reset by peer]
hakzsam has joined #dri-devel
haasn has quit [Quit: ZNC 1.7.5+deb4 - https://znc.in]
haasn has joined #dri-devel
danvet has quit [Ping timeout: 480 seconds]
JohnnyonFlame has quit [Read error: Connection reset by peer]
srslypascal has quit [Quit: Leaving]
<HdkR> ./win 3
<alyssa> bash: ./win: Permission denied
<HdkR> Dang
tlwoerner_ has quit []
tlwoerner has joined #dri-devel
srslypascal has joined #dri-devel
heat has quit [Ping timeout: 480 seconds]
psykose has quit [Remote host closed the connection]
psykose has joined #dri-devel
aravind has joined #dri-devel
kts has joined #dri-devel
eukara has quit []
garrison has joined #dri-devel
i-garrison has quit [Read error: Connection reset by peer]
garrison has quit []
i-garrison has joined #dri-devel
mhenning has quit [Quit: mhenning]
kts has quit [Quit: Leaving]
YuGiOhJCJ has quit [Remote host closed the connection]
YuGiOhJCJ has joined #dri-devel
danvet has joined #dri-devel
kts has joined #dri-devel
srslypascal is now known as Guest4495
srslypascal has joined #dri-devel
alanc has quit [Remote host closed the connection]
alanc has joined #dri-devel
srslypascal has quit [Remote host closed the connection]
srslypascal has joined #dri-devel
Guest4495 has quit [Ping timeout: 480 seconds]
srslypascal has quit [Ping timeout: 480 seconds]
kts has quit [Quit: Leaving]
aravind has quit [Ping timeout: 480 seconds]
lemonzest has joined #dri-devel
Duke`` has joined #dri-devel
camus1 has joined #dri-devel
camus has quit [Read error: Connection reset by peer]
kts has joined #dri-devel
mattst88 has joined #dri-devel
mattst88_ has quit [Ping timeout: 480 seconds]
mszyprow has joined #dri-devel
mupuf has quit [Remote host closed the connection]
Leopold has joined #dri-devel
mupuf has joined #dri-devel
rasterman has joined #dri-devel
fab has joined #dri-devel
fab has quit [Ping timeout: 480 seconds]
mszyprow has quit [Ping timeout: 480 seconds]
<karolherbst> jenatali: thanks!
kts has quit [Quit: Leaving]
pcercuei has joined #dri-devel
aleasto has quit [Quit: ZNC 1.8.2 - https://znc.in]
aleasto has joined #dri-devel
kts has joined #dri-devel
kts has quit [Quit: Leaving]
JohnnyonFlame has joined #dri-devel
srslypascal has joined #dri-devel
morphis has quit []
morphis has joined #dri-devel
Leopold has quit [Remote host closed the connection]
Scorpi_ has joined #dri-devel
<ElementW> Hmm, I'm having some display issues but I'm not sure where to start investigating and/or reporting a bug... Basically my display has the great idea of completely disconnecting itself when I turn it off (yes, that means its EDID is gone too), and I can consistently make amdgpu emit a kernel warning if that happens while the screen is off using DPMS. Kwin can recover if I make it release and regain DRM master thru VT switching, but Sway is in
<ElementW> complete shambles when that happens
YuGiOhJCJ has quit [Quit: YuGiOhJCJ]
<ElementW> The warning is `drm_WARN_ON(atomic_read(&vblank->refcount) == 0)` at drivers/gpu/drm/drm_vblank.c:1210 so I'm not sure if it's an actual kernel driver issue or if my Wayland compositors just try and use the display even when the kernel signalled it's gone
<karolherbst> jenatali: seems like your fix made it even worse: https://gitlab.freedesktop.org/mesa/mesa/-/jobs/30703294/raw :(
<illwieckz> oh that looks like doing list.extend(string) instead of list.append(string)
<jenatali> Sigh
<karolherbst> jenatali: though we might want to add texture variangs for the subpass stuff.. dunno :(
<karolherbst> there is quite a bit of code depending on that as it seems
<karolherbst> jenatali: I am wondering if one could make dozen to run on wine... but debugging things in wine is also kind annoying
<jenatali> Probably
<jenatali> I'll take a look when I can
rasterman has quit [Quit: Gettin' stinky!]
<jenatali> karolherbst: FWIW it's not worse, it's just not fully fixed...
<jenatali> There's probably something else that's leaving tex ops pointing to image types
<karolherbst> ahh.. maybe
<karolherbst> thought there are more crashes now, but maybe I misremembered
<Scorpi_> karolherbst: Hi! I built mesa from git master to play around with rusticl. I set RUSTICL_ENABLE=radeojsi. clinfo shows that rusticl is used, but no devices are found and there are 2 messages "radeonsi: driver missing"
<karolherbst> Scorpi_: you'll need this MR: https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/19232
<Scorpi_> karolherbst: thanks, I'll try
<Scorpi_> hum, need to rewind to a matching main commit first
RSpliet has quit [Quit: Bye bye man, bye bye]
RSpliet has joined #dri-devel
<Scorpi_> karolherbst: okay, clinfo looks fine
* Scorpi_ fires up darktable
<Scorpi_> hum, hangs at startup
<karolherbst> ohh..
<karolherbst> you need to patch llvm..
<karolherbst> maybe I should try to get it applied to llvm-15
<jenatali> karolherbst: Got another fix for you
<karolherbst> yeah.. I think your upper patch looks fine. we shouldn't convert samplers to textures here I think :)
<Scorpi_> karolherbst: okay, I think rebuilding llvm is something that can be done when it's dark outside...
<karolherbst> or use llvm-git if possible
<karolherbst> uhm.. packages I mean
<karolherbst> but... I guess you don't want to kill your system
<Scorpi_> karolherbst: I intend to just rebuild the Debian package with the patch applied
<karolherbst> you'll have to fix the patch a little, also not sure if that even works before llvm-15
<Scorpi_> Debian Sid has llvm-15
<karolherbst> okay, still need to adjust the patch a little (it touches tests which aren't there with llvm-15)
<Scorpi_> okay
user34234 has joined #dri-devel
bluepqnuin is now known as bluepenquin
user34234 has quit [Quit: Konversation terminated!]
rasterman has joined #dri-devel
user34234 has joined #dri-devel
<user34234> how do I use amdgpu.virtual_display with recent kernels? Xorg will just crash on startup. Is there some secret? I can't find anything mentioned in manuals
<user34234> i'm running it on bare haredware, no SR-IOV, IOMMU or anything like that. No display hardware attached either
heat has joined #dri-devel
kts has joined #dri-devel
<karolherbst> jenatali: okay, seems like that fixed it :)
<karolherbst> now let's see if anything else still works
<jenatali> Yep
<jenatali> Dozen is a little picky but I'd say both of these fixes produce better looking code
<karolherbst> yeah, and it's overall more consistent anyway
<jenatali> Yeah
<jenatali> And this is why I'm so glad we have our drivers in CI
Haaninjo has joined #dri-devel
glennk has quit [Remote host closed the connection]
glennk has joined #dri-devel
sarnex has quit [Quit: Quit]
<karolherbst> okay, seems like the other drivers are fine as well
sarnex has joined #dri-devel
jernej has quit [Quit: Free ZNC ~ Powered by LunarBNC: https://LunarBNC.net]
jernej has joined #dri-devel
jernej has quit [Read error: Connection reset by peer]
jernej has joined #dri-devel
jernej has quit []
jernej has joined #dri-devel
jernej_ has joined #dri-devel
jernej has quit []
jernej has joined #dri-devel
jernej_ has quit []
<jenatali> I doubt anybody else is using that pass
<karolherbst> right, but I also modify other parts
kts has quit [Quit: Leaving]
kts has joined #dri-devel
exit70 has quit [Quit: ZNC 1.8.2 - https://znc.in]
exit70 has joined #dri-devel
digetx has quit [Ping timeout: 480 seconds]
<karolherbst> jenatali: I saw some people talking about a potential MSVC compiler bug, best place to file those? (the compiler turns a conditional store into an unconditional one, still correct in terms of single threaded correctness tho
<karolherbst> )
srslypascal is now known as Guest4527
srslypascal has joined #dri-devel
alyssa has left #dri-devel [#dri-devel]
<karolherbst> thx!
xypron has quit [Quit: xypron]
xypron has joined #dri-devel
<FLHerne> maybe not because that blows up even in a single thread (which seems egregiously broken as compilers go)
Guest4527 has quit [Ping timeout: 480 seconds]
<karolherbst> no, it was about extern
<FLHerne> ah
<karolherbst> apparently c++11 forbids those kind of optimizations
digetx has joined #dri-devel
idr has quit [Quit: Leaving]
rasterman has quit [Remote host closed the connection]
rasterman has joined #dri-devel
TMM has quit [Quit: https://quassel-irc.org - Chat comfortably. Anywhere.]
TMM has joined #dri-devel
camus1 has quit [Remote host closed the connection]
camus has joined #dri-devel
mhenning has joined #dri-devel
kts has quit [Quit: Leaving]
lemonzest has quit [Quit: WeeChat 3.6]
user34234 has quit [Quit: Konversation terminated!]
Haaninjo has quit [Quit: Ex-Chat]
apinheiro has joined #dri-devel
luc4 has joined #dri-devel
<airlied> jenatali: when you say DRI being bloat, do you mean the internal/dri_interface.h?
JohnnyonFlame has quit [Ping timeout: 480 seconds]
<jenatali> airlied: Sorry yeah, the frontend -> driver interface, not the kernel API
<airlied> jenatali: do you envisage libEGL just loading libGL which has all the drivers?
<jenatali> Yep
<airlied> or rather libOpenGL
<airlied> and always requiring glvnd?
<jenatali> Well, my expectation is you'd have a gallium libEGL which loads the gallium megadriver
<jenatali> And yeah if you want a different libEGL then you either need glvnd or to replace it with a different one
<airlied> just trying to think about how it would look from the older drivers newer libGL pov
<airlied> I suppose in that case you'd have to rely on glvnd
<jenatali> Right, that's already the plan for Amber though, isn't it?
<airlied> but there's also fixing the X server I suppose to not need that interface
<airlied> jenatali: yeah probably
<airlied> not sure where ajax's make X server use EGL always plan ende up
<jenatali> FWIW my personal stake here is quite low, it just strikes me as something that can be trimmed once glvnd is a given
<jenatali> Though I know... basically nothing about X internals
<airlied> yeah I think the X server loader is the other problem
<jenatali> Fair enough
camus has quit [Remote host closed the connection]
Duke`` has quit [Ping timeout: 480 seconds]
danvet has quit [Ping timeout: 480 seconds]
nchery has quit [Ping timeout: 480 seconds]
rasterman has quit [Quit: Gettin' stinky!]
lynxeye has joined #dri-devel
<karolherbst> anybody here have native support for nir_intrinsic_load_workgroup_size?
heat has quit [Remote host closed the connection]
heat has joined #dri-devel
<karolherbst> mhh.. nvidia has it apparetnly..
<karolherbst> but I really don't want to add another CAP :(
<HdkR> karolherbst: Indeed, which is why I'm always confused when you are using a constant instead :D
<karolherbst> yeah.. most hardware doesn't seem to support it... but it's way less painful to deal with that in the frontend for me
<karolherbst> than drivers lowering it
<karolherbst> and slowly I'm inclined to just merge https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/18581 if I am not getting any reviews on the radeonsi code.... this is really blocking me
luc4 has quit []
lynxeye has quit [Quit: Leaving.]
gouchi has joined #dri-devel
gouchi has quit [Remote host closed the connection]
apinheiro has quit [Quit: Leaving]