Mesa (17.1): 35 new commits
Andres Gomez
tanty at kemper.freedesktop.org
Wed Jul 12 19:02:23 UTC 2017
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=8164345b77a8e1538a070796c659a07539b5ab7f
Author: James Legg <jlegg at feralinteractive.com>
Date: Mon Jun 26 10:46:23 2017 +0100
spirv: Fix reaching unreachable for compare exchange on images
We were hitting the
unreachable("Invalid image opcode")
near the end of vtn_handle_image when parsing the
SpvOpAtomicCompareExchange opcode.
v2: Add stable CC.
v3: Ignore SpvOpAtomicCompareExchangeWeak. It requires the Kernel
capability which is not exposed in Vulkan, and spirv_to_nir is not used
for OpenCL which does support it.
Reviewed-by: Jason Ekstrand <jason at jlekstrand.net>
CC: <mesa-stable at lists.freedesktop.org>
(cherry picked from commit b117f59710e62f4afa5781c554f8113e2b0df9cc)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=8d0fa95bf222153cb5c8919c93a5011e0ca59ddc
Author: Brian Paul <brianp at vmware.com>
Date: Mon Jul 10 08:36:15 2017 -0600
svga: fix PIPE_CAP_MAX_TEXTURE_BUFFER_SIZE value
This query is supposed to return the max texture buffer size/width in
texels, not size in bytes. Divide by 16 (the largest format size) to
return texels.
Fixes Piglit arb_texture_buffer_object-max-size test.
Cc: mesa-stable at lists.freedesktop.org
Reviewed-by :Charmaine Lee <charmainel at vmware.com>
(cherry picked from commit 3b28eaabf603657c388caa72bc92b1b660d00b2a)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=82aff6ad188db4703e55593e136e45824f7e9ad9
Author: Olivier Lauffenburger <o.lauffenburger at topsolid.com>
Date: Thu Jul 6 09:08:00 2017 -0600
st/wgl: improve selection of pixel format
Current selection of pixel format does not enforce the request of
stencil or depth buffer if the color depth is not the same as
requested.
For instance, GLUT requests a 32-bit color buffer with an 8-bit
stencil buffer, but because color buffers are only 24-bit, no
priority is given to creating a stencil buffer.
This patch gives more priority to the creation of requested buffers
and less priority to the difference in bit depth.
Bugzilla: https://bugs.freedesktop.org/show_bug.cgi?id=101703
Signed-off-by: Olivier Lauffenburger <o.lauffenburger at topsolid.com>
Tested-by: Brian Paul <brianp at vmware.com>
Reviewed-by: Brian Paul <brianp at vmware.com>
(cherry picked from commit 80c6598cdba36edb43d618f97175103e560d61a1)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=729b999e351283b398e17d042dc1ef91ed4155cb
Author: Charmaine Lee <charmainel at vmware.com>
Date: Tue Jun 6 11:52:50 2017 -0700
svga: fixed surface size to include array size
This patch fixes the total surface size in surface cache
to include array size as well.
Tested with MTT glretrace.
Reviewed-by: Brian Paul <brianp at vmware.com>
(cherry picked from commit adead35320c0afe95f3f170a6047905179f8c6c3)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=759d84177e87cc82afadeca7953c47848668fda0
Author: Neha Bhende <bhenden at vmware.com>
Date: Thu Oct 27 12:35:03 2016 -0700
svga: loop over box.depth for ReadBack_image on each slice
piglit test ext_texture_array-gen-mipmap is fixed with this patch.
Tested with mtt piglit, glretrace, viewperf and conform. No regression.
Reviewed-by: Brian Paul <brianp at vmware.com>
(cherry picked from commit 31fe1d10b291bcd1b9ee376d53db05028719831d)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=c36c8ec52808eb55bf1517a7beaaacc955c1e612
Author: Juan A. Suarez Romero <jasuarez at igalia.com>
Date: Thu Jun 22 12:47:57 2017 +0200
glsl: do not call link_xfb_stride_layout_qualifiers() for fragment shaders
xfb only applies to the latest stage before the fragment shader, so
there is no need to invoke it in the fragment shader.
Fixes:
KHR-GL45.enhanced_layouts.xfb_stride_of_empty_list
KHR-GL45.enhanced_layouts.xfb_stride_of_empty_list_and_api
v2: do reset only if shaders provide an explicit stride
v3: do not call link_xfb_stride_layout_qualifiers() for fragment shaders
(Timothy)
Reviewed-by: Timothy Arceri <tarceri at itsqueeze.com>
Signed-off-by: Juan A. Suarez Romero <jasuarez at igalia.com>
(cherry picked from commit 860919a3b237386cba5b2951ae520bf6734fd17e)
[Andres Gomez: resolve trivial conflicts]
Signed-off-by: Andres Gomez <agomez at igalia.com>
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=7bcb63457ba9a696ff023a3871baf61c3d1bbd05
Author: Anuj Phogat <anuj.phogat at gmail.com>
Date: Fri May 19 12:09:22 2017 -0700
intel/isl: Add the maximum surface size limit
V2: Use 2^31 bytes (2GB) surface size limit on pre-gen9 and
2^38 bytes for gen9+.
Signed-off-by: Anuj Phogat <anuj.phogat at gmail.com>
Reviewed-by: Nanley Chery <nanley.g.chery at intel.com>
(cherry picked from commit c07271fef095164c8bcfb54fdc95567c3774a866)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=7fc94625cca0d9f5997252b0598bc4e0e6b9597a
Author: Anuj Phogat <anuj.phogat at gmail.com>
Date: Fri May 19 13:47:12 2017 -0700
intel/isl: Use uint64_t to store total surface size
Signed-off-by: Anuj Phogat <anuj.phogat at gmail.com>
Reviewed-by: Nanley Chery <nanley.g.chery at intel.com>
(cherry picked from commit 70229782370c7ed9a63e05689f4d8bfc80128dd9)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=9e0ef936918f3a6b940f0a1509c1b7dd09bdc3d9
Author: Marek Olšák <marek.olsak at amd.com>
Date: Tue Jun 27 19:24:20 2017 +0200
gallium/radeon: fix a possible crash for buffer exports
Reviewed-by: Nicolai Hähnle <nicolai.haehnle at amd.com>
(cherry picked from commit e6dbe975eff8e23992c9d9a72ce302896b5fecfc)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=914a26d549aa5f5e28fc6a45292c225e663aa644
Author: Aleksander Morgado <aleksander at aleksander.es>
Date: Thu Jul 6 11:35:37 2017 +0200
etnaviv: don't dereference etna_resource pointer if allocation fails
The check for the pointer being non-NULL was being done too late.
Signed-off-by: Aleksander Morgado <aleksander at aleksander.es>
Reviewed-by: Christian Gmeiner <christian.gmeiner at gmail.com>
(cherry picked from commit a6893a50c8ae5b68e4175366dac718ee9f6fa9d1)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=c6e841667f27f7c97f80f9b447d22b1610372353
Author: Brian Paul <brianp at vmware.com>
Date: Thu Jun 15 11:31:53 2017 -0600
svga: clamp device line width to at least 1 to fix HWv8 line stippling
The line stipple fallback code for virtual HW version 8 didn't work.
With HW version 8, we were getting zero when querying the max line
widths (AA and non-AA). This means we were setting the draw module's
wide line threshold to zero. This caused the wide line stage to always
get enabled. That caused the line stipple module to fall because the
wide line stage was clobbering the rasterization state with a state
object setting the line stipple pattern to 0xffff.
Now the wide_lines variable in draw's validate_pipeline() will not
be incorrectly set.
Also improve debug output.
BTW, also this fixes several other piglit tests: polygon-mode,
primitive- restart-draw-mode, and line-flat-clip-color since they
all use the draw module fallback.
See VMware bug 1895811.
Reviewed-by: Charmaine Lee <charmainel at vmware.com>
(cherry picked from commit c2b92dada076afc303e31e3d029256d234254c27)
Squashed with:
svga: adjust line subpixel position for HWv8
This fixes two regressions on HWv8:
Piglit gl-1.0-ortho-pos
Piglit/glean fbo
This was caused by commit c2b92dada076a "svga: clamp device line width
to at least 1 to fix HWv8 line stippling"
This also fixes two conform tests: Vertex Order and Polygon Face
No Piglit/conform changes with HWv9 or later.
VMware bug 1905053
Reviewed-by: Charmaine Lee <charmainel at vmware.com>
(cherry picked from commit 5b8d33acefa9adbf1f0c9ff10f1933a0b3a5c66b)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=49b5da785f52a092bebef32dde6536c9d898a7d5
Author: Alex Smith <asmith at feralinteractive.com>
Date: Fri Jun 30 11:15:42 2017 +0100
ac/nir: Fix ordering of parameters for image atomic cmpswap intrinsics
The NIR parameters are ordered "compare, data", matching GLSL, but both
the image and buffer LLVM intrinsics take them the other way around.
This is already handled correctly for SSBO atomics.
Signed-off-by: Alex Smith <asmith at feralinteractive.com>
Reviewed-by: Bas Nieuwenhuizen <bas at basnieuwenhuizen.nl>
Fixes: f4e499ec791 "radv: add initial non-conformant radv vulkan driver"
(cherry picked from commit c2a5cb64272da3cd8d97b0a58da6c6992b0417d3)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=401c37f500f351272dede9e7464d836183dafac4
Author: Aleksander Morgado <aleksander at aleksander.es>
Date: Thu Jul 6 23:18:57 2017 +0200
etnaviv: fix refcnt initialization in etna_screen
Despite being a member of the etna_screen struct, 'refcnt' is used by
the winsys-specific logic to track the reference count of the object
managed in a hash table. When the count reaches zero, the pipe screen
is removed from the table and destroyed.
Fix the logic by initializing the refcnt to 1 when screen created.
This initialization is done in etna_screen_create(), to follow the
same logic as in freedreno and virgl.
Fixes: c9e8b49b885 ("etnaviv: gallium driver for Vivante GPUs")
Cc: mesa-stable at lists.freedesktop.org
Signed-off-by: Aleksander Morgado <aleksander at aleksander.es>
Reviewed-by: Christian Gmeiner <christian.gmeiner at gmail.com>
Reviewed-by: Lucas Stach <l.stach at pengutronix.de>
(cherry picked from commit 5d8514de14bd27170293bb373e06f5ff43c708ad)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=d856e97d928c97c159964f1edd07f95909f572f0
Author: Tim Rowley <timothy.o.rowley at intel.com>
Date: Thu Jul 6 13:16:18 2017 -0500
swr/rast: Correctly allocate SWR_STATS memory as cacheline aligned
Cacheline alignment of SWR_STATS to prevent sharing of cachelines
between threads (performance).
Gets rid of gcc-7.1 warning about using c++17's over-aligned new
feature.
Cc: mesa-stable at lists.freedesktop.org
Reviewed-by: Bruce Cherniak <bruce.cherniak at intel.com>
(cherry picked from commit bab03c06fc79ec5624982777684d0c5f123c127c)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=7bd9eccbfeb178389e7a55bcfa1f4877f6289e5f
Author: Tim Rowley <timothy.o.rowley at intel.com>
Date: Wed Jul 5 13:26:02 2017 -0500
swr/rast: _mm*_undefined_* implementations for gcc<4.9
Define these in terms of setzero for ancient gcc versions which don't
have the undefined intrinsics.
Cc: mesa-stable at lists.freedesktop.org
Reviewed-by: Bruce Cherniak <bruce.cherniak at intel.com>
(cherry picked from commit f0a22956be4802e01f2b4f3244f011212626f12d)
Squashed with:
swr: modifications to allow gcc-4.8 compilation
Code unconditionally used avx2 intrinsics in the avx compilation.
The simd intrinsics library we used has diverged significantly between
branch and master; the non-“undefined intrinsics” portion is specific
to the branch.
This complements:
f0a22956be “swr/rast: _mm*_undefined_* implementations for gcc<4.9”
And makes this branch equivalent with the additional master patch:
d50ef7332c “swr/rast: don't use _mm256_fmsub_ps in AVX code”
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=e1842e8acbc4a60e27c191f2c020e85d632d17a7
Author: Vinson Lee <vlee at freedesktop.org>
Date: Wed Jul 5 14:16:11 2017 -0700
scons: Check for xlocale.h before defining HAVE_XLOCALE_H.
Don't assume the header is present on some platforms - use the more
robust CheckHeader() instead.
glibc 2.26 removed xlocale.h.
https://sourceware.org/glibc/wiki/Release/2.26#Removal_of_.27xlocale.h.27
Fix this build error with glibc 2.26.
Compiling src/util/strtod.c ...
src/util/strtod.c:32:10: fatal error: xlocale.h: No such file or directory
#include <xlocale.h>
^~~~~~~~~~~
Bugzilla: https://bugs.freedesktop.org/show_bug.cgi?id=101657
Signed-off-by: Vinson Lee <vlee at freedesktop.org>
Cc: mesa-stable at lists.freedesktop.org
Reviewed-by: Emil Velikov <emil.velikov at collabora.com>
Reviewed-by: Eric Engestrom <eric.engestrom at imgtec.com>
Tested-by: Eric Engestrom <eric.engestrom at imgtec.com>
(cherry picked from commit c5d0dc7fa5566941a49ede8c83a0cfe0a33a3d7f)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=e9f0179221d175aa59974eaa4a386074ad37ca8a
Author: Plamena Manolova <plamena.manolova at intel.com>
Date: Wed Jun 14 19:33:12 2017 +0300
mesa/main: Move NULL pointer check.
In blit_framebuffer we're already doing a NULL
pointer check for readFb and drawFb so it makes
sense to do it before we actually use the pointers.
CID: 1412569
Signed-off-by: Plamena Manolova <plamena.manolova at intel.com>
Reviewed-by: Rafael Antognolli <rafael.antognolli at intel.com>
(cherry picked from commit b3b61211157ab934f1898d3519e7288c1fd89d80)
[Andres Gomez: resolve trivial conflicts]
Signed-off-by: Andres Gomez <agomez at igalia.com>
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=1d4d3f88c6c8a14b33b5f371db2e373935625648
Author: Chandu Babu N <chandu at amd.com>
Date: Thu Jun 22 10:48:41 2017 +0530
st/va: Fix leak in VAAPI subpictures
sampler view allocated in vaAssociateSubpicture is not cleared
in vaiDeassociateSubpicture.
Reviewed-by: Christian König <christian.koenig at amd.com>
(cherry picked from commit b1a359b7d8a0559412d253101e930a6a45d9af7a)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=1a972ddd941f83f493e53e67eef3d08ec0c7e787
Author: Iago Toral Quiroga <itoral at igalia.com>
Date: Fri Jun 16 12:05:20 2017 +0200
glsl: gl_Max{Vertex,Fragment}UniformComponents exist in all desktop GL versions
The current implementation assumed that these were replaced in GLSL >= 4.10
by gl_Max{Vertex,Fragment}UniformVectors, however this is not true: both
built-ins should be produced from GLSL 4.10 onwards.
This was raised by new CTS tests that are in development.
Reviewed-by: Nicolai Hähnle <nicolai.haehnle at amd.com>
(cherry picked from commit b70d6a2de1c90409c7a2e0d6484f350558f5c2ac)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=056681e5a1781d9a511c286984e099530f04fc6b
Author: Tomasz Figa <tfiga at chromium.org>
Date: Wed Jul 5 23:54:18 2017 +0900
intel: common: Fix link failure with standalone Android build
Some reshuffle in the Makefiles under src/intel resulted in Android
libraries being no longer linked with code using
src/intel/common/gen_debug.h that contains references to functions
exported by those libraries (namely ALOGW macro, which is currently
resolved into a call to __android_log_print() from cutils).
Fix the build by taking into account ANDROID_CFLAGS and ANDROID_LIBS for
affected module on Android NDK builds.
Fixes: d5b355ce5fd ("i965: Move intel_debug.h to intel/common/gen_debug.h")
Signed-off-by: Tomasz Figa <tfiga at chromium.org>
Reviewed-by: Emil Velikov <emil.velikov at collabora.com>
(cherry picked from commit 50a8a7377ae071d5b4b927e9055a7ec8391acc59)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=2711a13a4fca238d0647558905f98e7f1170b67d
Author: Ilia Mirkin <imirkin at alum.mit.edu>
Date: Mon Jul 3 17:08:12 2017 -0400
glsl: check if any of the named builtins are available first
_mesa_glsl_has_builtin_function is used to determine whether any variant
of a builtin are available, for the purpose of enforcing the GLSL ES
3.00+ rule that overloads or overrides of builtins are disallowed.
However the builtin_builder contains information on all builtins,
irrespective of parse state, or versions, or extension enablement. As a
result we would say that a builtin existed even if it was not actually
available.
To resolve this, first check if at least one signature is available for
a builtin before returning true.
Bugzilla: https://bugs.freedesktop.org/show_bug.cgi?id=101666
Signed-off-by: Ilia Mirkin <imirkin at alum.mit.edu>
Cc: mesa-stable at lists.freedesktop.org
Reviewed-by: Timothy Arceri <tarceri at itsqueeze.com>
Acked-by: Lionel Landwerlin <lionel.g.landwerlin at intel.com>
Reviewed-by: Kenneth Graunke <kenneth at whitecape.org>
(cherry picked from commit 880f21f55d579fe2183255d031c23343da30f69e)
[Andres Gomez: resolve trivial conflicts]
Signed-off-by: Andres Gomez <agomez at igalia.com>
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=9b4970b0354ae8fc9fdd64d18a46551ab0727d0c
Author: Jason Ekstrand <jason at jlekstrand.net>
Date: Thu Jun 29 10:33:24 2017 -0700
nir/spirv: Use the type from the deref for atomics
Previously, we were using the type of the variable which is incorrect.
Cc: "17.1" <mesa-stable at lists.freedesktop.org>
Reviewed-by: Connor Abbott <cwabbott0 at gmail.com>
(cherry picked from commit a10d887ad1eba7baca74b8fbd9c9ec171dbcf3a7)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=fb5fc8d7eecef09373bdfc851f0395e7aaf2172b
Author: Connor Abbott <cwabbott0 at gmail.com>
Date: Wed Jun 7 14:16:31 2017 -0700
ac/nir: implement 64-bit packing and unpacking
We implement the split opcodes, and tell NIR to lower the original ones.
The lowering to LLVM is a little more complicated, but NIR can optimize
the split ones a little better, and some NIR lowering passes that we
might want to use (particularly for doubles) emit the split ones.
This should fix pack/unpackDouble2x32, which seems like a bug since when
we enabled the Float64 capability. It will also fix pack/unpackInt2x32
when we enable the Int64 capability.
Fixes: 798ae37c ("radv: Enable Float64 support.")
Signed-off-by: Connor Abbott <cwabbott0 at gmail.com>
Reviewed-by: Bas Nieuwenhuizen <bas at basnieuwenhuizen.nl>
(cherry picked from commit 7168425dd77f37fa048de5a4639619763556c331)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=387e0e12a905ae3093071825240ba7f6ff7ff3b5
Author: Connor Abbott <cwabbott0 at gmail.com>
Date: Wed Jun 7 14:12:05 2017 -0700
spirv: fix OpBitcast when the src and dst bitsize are different (v3)
Before, we were just implementing it with a move, which is incorrect
when the source and destination have different bitsizes. To implement
it properly, we need to use the 64-bit pack/unpack opcodes. Since
glslang uses OpBitcast to implement packInt2x32 and unpackInt2x32, this
should fix them on anv (and radv once we enable the int64 capability).
v2: make supporting non-32/64 bit easier (Jason)
v3: add another assert (Jason)
Fixes: b3135c3c ("anv: Advertise shaderInt64 on Broadwell and above")
Signed-off-by: Connor Abbott <cwabbott0 at gmail.com>
Reviewed-by: Jason Ekstrand <jason at jlekstrand.net>
(cherry picked from commit 196e6b60b1e392c5e55c07a9f9b4e85dad52fb66)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=8db6b8326758c0d3209ee90a7e3cf08ca88d223f
Author: Philipp Zabel <p.zabel at pengutronix.de>
Date: Fri Jun 30 10:39:53 2017 +0200
st/mesa: release EGLImage on EGLImageTarget* error
The smapi->get_egl_image() call in st_egl_image_get_surface() stores a
reference to the EGLImage's texture in stimg.texture. That reference is
released via pipe_resource_reference(&stimg.texture, NULL) before stimg
goes out of scope at the end of the function, but not in the error path
if !is_format_supported().
Fixes: 83e9de25f325 ("st/mesa: EGLImageTarget* error handling")
Cc: mesa-stable at lists.freedesktop.org
Signed-off-by: Philipp Zabel <p.zabel at pengutronix.de>
Reviewed-by: Marek Olšák <marek.olsak at amd.com>
(cherry picked from commit 7d7bcd65d6019dfb63f31138a426fe2a043016db)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=c50ed4cadec1f37a6cef474160feb021674112bc
Author: Nicolai Hähnle <nicolai.haehnle at amd.com>
Date: Tue Jun 27 09:50:32 2017 +0200
winsys/radeon: only call pb_slabs_reclaim when slabs are actually used
Bugzilla: https://bugs.freedesktop.org/show_bug.cgi?id=100242
Fixes: fb827c055cb1 ("winsys/radeon: enable buffer allocation from slabs")
Cc: mesa-stable at lists.freedesktop.org
Reviewed-by: Samuel Pitoiset <samuel.pitoiset at gmail.com>
Reviewed-by: Marek Olšák <marek.olsak at amd.com>
(cherry picked from commit b0b4b5e8f7a25dd11c1662d339d68c9733e9b2dc)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=b5b4ef577b997f968ef43ba9c64d23fe47b156a5
Author: Andres Gomez <agomez at igalia.com>
Date: Mon Jul 3 23:24:37 2017 +0300
cherry-ignore: i965: Fix anisotropic filtering for mag filter
extra: References 6a7c5257cac but because later f8d69beed49 introduced
a regression and the latter didn't land.
Signed-off-by: Andres Gomez <agomez at igalia.com>
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=5c91fcfad89f04b02eb538c4c6f23df369d6b742
Author: Bruce Cherniak <bruce.cherniak at intel.com>
Date: Fri Jun 30 22:24:46 2017 -0500
swr: Limit memory held by defer deleted resources.
This patch limits the number of items on the fence work queue (the
deferred deletion list) by submitting a sync fence when the queue size
exceeds a threshold. This initiates deferred deletion of all resources
on the list and decreases the total amount of memory held waiting for
"deferred deletion".
This resolves bug 101467 filed against swr for the piglit
streaming-texture-leak test. For those running on smaller memory
(16GB?) systems, this will prevent oom-killer.
Thus far, we have not seen any real world applications that exhibit
behavior like the streaming-texture-leak test; as any form of pipeline
flush will trigger the defer queue and properly free any retained
allocations. But, this addresses those as well.
Cc: "17.1" <mesa-stable at lists.freedesktop.org>
Reviewed-by: Ilia Mirkin <imirkin at alum.mit.edu>
(cherry picked from commit 32c1a54bd01465e77a8e26b9cc8d2487b31509c5)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=ea3f94b5556a32da7196c04c34636a01266fc3c5
Author: Lucas Stach <l.stach at pengutronix.de>
Date: Mon Jun 26 18:24:31 2017 +0200
etnaviv: fix shader miscompilation with more than 16 labels
The labels array may change its virtual address on a reallocation, so
it is invalid to cache pointers into the array. Rather than using the
pointer directly, remember the array index.
Fixes miscompilation of shaders in glmark2 ideas, leading to GPU hangs.
Fixes: c9e8b49b (etnaviv: gallium driver for Vivante GPUs)
Cc: mesa-stable at lists.freedesktop.org
Signed-off-by: Lucas Stach <l.stach at pengutronix.de>
Reviewed-by: Christian Gmeiner <christian.gmeiner at gmail.com>
(cherry picked from commit ec43605189907fa327a4a7f457aa3c822cfdea5d)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=cc2a62991a104bdbaf06913501d777cd4037fed8
Author: Alex Smith <asmith at feralinteractive.com>
Date: Mon Jun 26 17:17:32 2017 +0100
ac/nir: Use correct LLVM intrinsics for atomic ops on imageBuffers
The buffer intrinsics should be used instead of the image ones.
Signed-off-by: Alex Smith <asmith at feralinteractive.com>
Cc: <mesa-stable at lists.freedesktop.org>
Reviewed-by: Bas Nieuwenhuizen <bas at basnieuwenhuizen.nl>
(cherry picked from commit 909184ac9cf59f23803915773f5659f05c161394)
[Andres Gomez: resolve trivial conflicts]
Signed-off-by: Andres Gomez <agomez at igalia.com>
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=5b8b891a45b206ca1d6e6eced3c80b50fb20b820
Author: James Legg <jlegg at feralinteractive.com>
Date: Fri Jun 23 11:18:56 2017 +0100
ac/nir: Make intrinsic_name buffer long enough
When using cmpswap on an image, it was being trunctated to
lvm.amdgcn.image.atomic.cmpswa, with the coords type missing entirely.
v2: Add stable CC
CC: <mesa-stable at lists.freedesktop.org>
Reviewed-by: Grazvydas Ignotas <notasas at gmail.com>
Reviewed-by: Nicolai Hähnle <nicolai.haehnle at amd.com>
Reviewed-by: Bas Nieuwenhuizen <bas at basnieuwenhuizen.nl>
(cherry picked from commit 6fc41bb4d59313985f67b1276d1fd1225be09426)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=70d5ca0363fe50534e7f1d30564b9f0bc0ce0486
Author: Kenneth Graunke <kenneth at whitecape.org>
Date: Wed Apr 26 14:27:15 2017 -0700
i965: Always set AALINEDISTANCE_TRUE on Sandybridge.
We set this unconditionally on every other platform. Zero (Manhattan)
isn't even listed as an option in the Sandybridge docs - only "true".
Reviewed-by: Plamena Manolova <plamena.manolova at intel.com>
Reviewed-by: Francisco Jerez <currojerez at riseup.net>
(cherry picked from commit 4878ab9bd4281c4554254bbb0c62faae453bb863)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=cfba0e166ab7b7180392abd31c97ad8df5db6e1b
Author: Kenneth Graunke <kenneth at whitecape.org>
Date: Wed Apr 26 14:28:49 2017 -0700
i965: Use true AA line distance on G45/Ironlake.
The original Broadwater and Crestline platforms computed antialiased
line distances using "manhattan" distance, aka a + b = c. Eaglelake
and Cantiga added "true" distance, which apparently does something
like max(a, b) + min(a, b) / 4. Not exactly "true", but at least
more accurate.
The G45 documentation indicates that the old manhattan distance setting
is "only for debug purposes" and should never be used. The Ironlake
documentation no longer mentions AALINEDISTANCE_MANHATTAN, though it
does still contain the narrative about the feature.
At any rate, we should use the more accurate mode.
Reviewed-by: Plamena Manolova <plamena.manolova at intel.com>
Reviewed-by: Francisco Jerez <currojerez at riseup.net>
(cherry picked from commit b625bcc601a16fab1962f9ed569700d3d08738b9)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=1492237b74c54363f85e459053633c6960ca3dc5
Author: Aaron Watry <awatry at gmail.com>
Date: Fri Jun 9 12:57:42 2017 -0500
radeon/winsys: Limit max allocation size to 70% of VRAM
The CL CTS queries the max allocation size, and then attempts to
allocate buffers of that size. If not enough contiguous RAM/VRAM is
available, this causes errors in the radeon kernel module due to
inability to allocate the required memory.
It's a bit of a hack, but experimentally on my system, I can use ~3/4
of the card's VRAM for a single global/constant buffer allocation given
current GUI/compositor use.
For a 1GB Pitcairn (HD7850) this gets me from the reported clinfo values of:
Global memory size 2143076352 (1.996GiB)
Max memory allocation 1500153446 (1.397GiB)
Max constant buffer size 1500153446 (1.397GiB)
To:
Global memory size 2143076352 (1.996GiB)
Max memory allocation 751619276 (716MiB)
Max constant buffer size 751619276 (716MiB)
Fixes: OpenCL CTS test/conformance/api/min_max_mem_alloc_size,
OpenCL CTS test/conformance/api/min_max_constant_buffer_size
Signed-off-by: Aaron Watry <awatry at gmail.com>
Reviewed-by: Marek Olšák <marek.olsak at amd.com>
(cherry picked from commit e4d06e4c531157f1f3e4683487ee9c81fa0cff9b)
URL: http://cgit.freedesktop.org/mesa/mesa/commit/?id=b17bd63229f01fa3cd63d2568f29813c207c119a
Author: Brian Paul <brianp at vmware.com>
Date: Thu Jun 15 11:29:38 2017 -0600
draw: check for line_width != 1.0f in validate_pipeline()
We shouldn't use the wide line stage if the line width is 1.
This check isn't strictly needed because all drivers are (now)
specifying a line wide threshold of at least 1.0 pixels, but
let's play it safe.
Reviewed-by: Charmaine Lee <charmainel at vmware.com>
(cherry picked from commit c8f344ed2d471f0e012205aecfae4aa765d9fffb)
More information about the mesa-commit
mailing list