Eric Anholt
1e188f2dae
intel: Fix signed/unsigned comparison warnings.
2012-05-14 16:51:00 -07:00
Eric Anholt
1c1040dcf0
intel: Fix compile warning from 7b6424143d
2012-05-14 16:51:00 -07:00
Eric Anholt
cdca6e3c9f
intel: Fix compiler warning from 3cd7bee48f
2012-05-14 16:51:00 -07:00
Kenneth Graunke
a4e9b5a768
i965/fs: Add a local common subexpression elimination pass.
...
Total instructions: 18210 -> 17836
49/163 programs affected (30.1%)
12888 -> 12514 instructions in affected programs (2.9% reduction)
This reduces Lightsmark's "Scale down filter" shader from 395
instructions to 283, a whopping 28%. It also reduces register pressure
significantly: the SIMD8 program now uses 29 registers instead of 101,
giving us more than enough room for a SIMD16 program.
v2: Add && !inst->conditional_mod to the "skip some instructions" check.
Signed-off-by: Kenneth Graunke <kenneth@whitecape.org>
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Reviewed-by: Eric Anholt <eric@anholt.net>
2012-05-14 15:13:55 -07:00
Kenneth Graunke
d1029f9988
i965/fs: Use a const reference in fs_reg::equals instead of a pointer.
...
This lets you omit some ampersands and is more idiomatic C++. Using
const also marks the function as not altering either register (which
was obvious, but nice to enforce).
Signed-off-by: Kenneth Graunke <kenneth@whitecape.org>
Reviewed-by: Ian Romanick <ian.d.romanick@intel.com>
Reviewed-by: Eric Anholt <eric@anholt.net>
2012-05-14 15:12:46 -07:00
Oliver McFadden
bf78806133
mesa: print the Git SHA1 in GL_VERSION for ES1 and ES2.
...
Signed-off-by: Oliver McFadden <oliver.mcfadden@linux.intel.com>
Reviewed-by: Brian Paul <brianp@vmware.com>
2012-05-14 19:13:44 +03:00
Oliver McFadden
60e8a49440
mesa: GLES specifies restrictions on uniform matrix transpose.
...
GL_INVALID_VALUE is generated if transpose is not GL_FALSE.
http://www.khronos.org/opengles/sdk/docs/man/xhtml/glUniform.xml
Signed-off-by: Oliver McFadden <oliver.mcfadden@linux.intel.com>
Reviewed-by: Brian Paul <brianp@vmware.com>
2012-05-14 19:13:43 +03:00
Michel Dänzer
8969de7e98
radeonsi: Keep around copies of original sampler states.
...
Fixes crashes when restoring sampler states after blits.
2012-05-14 17:56:03 +02:00
Michel Dänzer
1deb2be2b7
radeonsi: Flesh out shader interpolation related code.
...
Handle perspective interpolation and ceontroid vs. center.
2012-05-14 17:56:03 +02:00
Michel Dänzer
de52a56a0e
radeonsi: Add proper SI family names.
2012-05-14 17:56:02 +02:00
Michel Dänzer
23e4fe2a53
radeonsi: Separate states for samplers and sampler views.
...
And reset nregs on updates. Prevents eventual assertion failure.
2012-05-14 17:56:02 +02:00
Michel Dänzer
36abadd0db
radeonsi: Fixups for drawing with an index buffer.
...
Mostly using the DRAW_INDEX_2 type 3 packet instead of DRAW_INDEX, which is
no longer supported on SI.
2012-05-14 17:56:02 +02:00
Vinson Lee
599140119e
vl: Initialize pipe_vertex_buffer.user_buffer fields.
...
Fix uninitialized scalar variable defects reported by Coverity.
Signed-off-by: Vinson Lee <vlee@freedesktop.org>
Reviewed-by: José Fonseca <jfonseca@vmware.com>
2012-05-14 08:44:16 -07:00
James Benton
24678700ed
llvmpipe: Calculate fixed point coordinates for triangle setup earlier.
...
This allows us to calculate the triangle's area using fixed point,
previously it was cacluated in floating point space. It was possible
that a triangle which had negative area in floating point space had
a positive area in fixed point space.
Fixes fdo 40920.
Reviewed-by: Jose Fonseca <jfonseca@vmware.com>
Reviewed-by: Brian Paul <brianp@vmware.com>
2012-05-14 16:07:49 +01:00
Tom Stellard
ec201667bf
radeon/llvm: Coding style fixes for R600CodeEmitter.cpp
2012-05-14 10:40:58 -04:00
Tom Stellard
224e187f98
radeon/llvm: Lower bitcast instructions to copies
2012-05-14 10:40:58 -04:00
Marek Olšák
ed9955dc29
radeonsi: remove slab allocator for pipe_resource (used mainly for user buffers)
2012-05-13 14:32:57 +02:00
Marek Olšák
05ea705c7c
r600g: remove slab allocator for pipe_resource (used mainly for user buffers)
2012-05-13 14:32:57 +02:00
Marek Olšák
b2d6386086
r600g: handle R16G16B16_FLOAT and R32G32B32_FLOAT in translate_colorswap (EG)
2012-05-12 23:13:45 +02:00
Marek Olšák
b496136af8
gallium: remove user_buffer_create from the interface
...
Nothing uses it now.
2012-05-12 23:13:45 +02:00
Marek Olšák
1a840cc592
gallium/graw: stop using user_buffer_create
...
This is compile-tested.
2012-05-12 23:13:45 +02:00
Marek Olšák
685a28fd8a
gallium/util: remove unused parameter nr_vertex_buffers in util_draw_max_index
2012-05-12 23:13:45 +02:00
Francisco Jerez
b70736fa82
clover: Fix build on i386.
2012-05-12 19:43:06 +02:00
Francisco Jerez
fcab4d4a34
clover: Check the total work-group size provided to clEnqueueNDRangeKernel.
2012-05-12 19:43:01 +02:00
Christoph Bumiller
5c9bccc97e
clover, gallium: add PIPE_COMPUTE_CAP_MAX_THREADS_PER_BLOCK
...
This is not necessarily the product of MAX_BLOCK_SIZE[i].
Reviewed-by: Tom Stellard <thomas.stellard@amd.com>
Reviewed-by: Francisco Jerez <currojerez@riseup.net>
2012-05-12 19:33:48 +02:00
Francisco Jerez
ec848d2730
r600g: Handle compute caps.
2012-05-12 19:17:18 +02:00
Francisco Jerez
4065639310
r300g: Handle compute caps.
2012-05-12 19:17:13 +02:00
José Fonseca
f96540847e
auxiliary/util: Ensure pipe_constant_buffer::user_buffer is initialized.
2012-05-12 17:23:52 +01:00
José Fonseca
7b49d4f05d
scons: Fix missing gbm symbols in st/egl.
2012-05-12 17:10:32 +01:00
José Fonseca
96e73cc4ae
targets/egl-static: Fix some missing symbols.
2012-05-12 17:10:32 +01:00
José Fonseca
fd687e06f0
trace: Fix pipe_context::clear dumping.
2012-05-12 17:10:31 +01:00
José Fonseca
b275bed549
trace: Fix pipe_shader_state dumping.
2012-05-12 17:10:31 +01:00
José Fonseca
e9efcd99d1
scons: Link r600_drm.so against libdrm-radeon
2012-05-12 17:10:31 +01:00
José Fonseca
9a23a69f45
trace: Match NULL context members.
2012-05-12 17:10:31 +01:00
Marek Olšák
7c799f8f6b
gallium/docs: remove documentation of redefine_user_buffer
2012-05-12 13:09:19 +02:00
Michel Dänzer
74b9ef83cf
radeonsi: Fixed point vertex formats aren't supported.
2012-05-12 12:27:10 +02:00
Michel Dänzer
24bc382010
radeonsi: Fixups for recent build infrastructure changes.
...
In particular for the pipe loader changes.
2012-05-12 12:12:21 +02:00
Dave Airlie
31a25dac98
r600g: setup COLOR1 for possible dual-src in the framebuffer bind
...
As pointed out by Marek, if we have only one cb, we may as well add this
single register write here rather than adding it in the draw loop.
Reviewed-by: Marek Olšák <maraeo@gmail.com>
Signed-off-by: Dave Airlie <airlied@redhat.com>
2012-05-12 08:25:21 +01:00
Roy Spliet
e253ead78e
nv30: Silence pipe_cap warnings
...
Signed-off-by: Roy Spliet <r.spliet@student.tudelft.nl>
Signed-off-by: Ben Skeggs <bskeggs@redhat.com>
2012-05-12 12:42:48 +10:00
Roy Spliet
897d235132
nv30/shader: SSG, LIT only requires one source register
...
Fixes crashing due to assertion error
Signed-off-by: Roy Spliet <r.spliet@student.tudelft.nl>
Signed-off-by: Ben Skeggs <bskeggs@redhat.com>
2012-05-12 12:42:47 +10:00
Ben Skeggs
6660041483
nouveau/vieux: finish != flush, how about we do that..
...
Signed-off-by: Ben Skeggs <bskeggs@redhat.com>
2012-05-12 12:42:47 +10:00
Marek Olšák
9d6b46b1cd
r300g/swtcl: move vertex buffer updates into set_vertex_buffers
2012-05-12 00:50:53 +02:00
Marek Olšák
735d0d93a7
r300g/swtcl: move index buffer updates from swtcl_draw_vbo into set_index_buffer
2012-05-12 00:50:53 +02:00
Marek Olšák
21b012d3b0
r300g/swtcl: malloc vertex and index buffers (don't use radeon DRM to get them)
...
Vertex and index buffers are never used by hardware, only by Draw.
SWTCL chipsets usually have very little memory, so this might help
with stability and reliability.
2012-05-12 00:50:53 +02:00
Marek Olšák
8a963d122d
r300g/swtcl: don't do stuff which is only for HWTCL
2012-05-12 00:50:52 +02:00
Marek Olšák
f808984f43
r300g: remove slab allocator for pipe_resource (used mainly for user buffers)
2012-05-12 00:50:52 +02:00
Marek Olšák
4fd60ad6da
r300g: remove user_buffer_create
2012-05-12 00:50:52 +02:00
Marek Olšák
bdba35befa
r300g: fix breakage after gallium-userbuf merge
2012-05-12 00:50:52 +02:00
Brian Paul
550de24c17
llvmpipe: add cast to silence warning
2012-05-11 16:16:11 -06:00
Andreas Betz
9d6e908f14
vega: fix 565 color unpacking bug
...
NOTE: This is a candidate for the 8.0 branch.
Signed-off-by: Brian Paul <brianp@vmware.com>
2012-05-11 16:13:14 -06:00