Commit message (Collapse) | Author | Age | Files | Lines | |
---|---|---|---|---|---|
* | radeon/llvm: Remove AMDIL floating-point ADD instruction defs | Tom Stellard | 2012-05-17 | 5 | -8/+9 |
| | |||||
* | radeon/llvm: Remove AMDIL CMOVLOG* instruction defs | Tom Stellard | 2012-05-17 | 4 | -26/+6 |
| | |||||
* | radeon/llvm: Move lowering of ABS_i32 to ISel | Tom Stellard | 2012-05-17 | 4 | -17/+16 |
| | |||||
* | radeon/llvm: Remove sub patterns from AMDILInstrPatterns.td | Tom Stellard | 2012-05-17 | 2 | -21/+1 |
| | |||||
* | radeon/llvm: Add custom SDNodes for MAX | Tom Stellard | 2012-05-17 | 10 | -10/+108 |
| | | | | | We now lower the various intrinsics for max to SDNodes and then use tablegen patterns to lower the SDNodes to instructions. | ||||
* | nouveau: place static buffers in VRAM if preferred by the driver | Christoph Bumiller | 2012-05-17 | 6 | -12/+62 |
| | |||||
* | nv50/ir: fix reversed order of lane ops in quadops | Christoph Bumiller | 2012-05-17 | 2 | -4/+6 |
| | |||||
* | nv50,nvc0: handle user vertex buffers | Christoph Bumiller | 2012-05-17 | 14 | -308/+423 |
| | | | | And restructure VBO validation a little in the process. | ||||
* | nv50,nvc0: handle user index buffers | Christoph Bumiller | 2012-05-17 | 8 | -47/+49 |
| | |||||
* | nv50,nvc0: handle user constbufs without wrapping them in a resource | Christoph Bumiller | 2012-05-17 | 14 | -165/+201 |
| | |||||
* | gallium/radeon: Fix r300g tiling breakage. | Michel Dänzer | 2012-05-16 | 6 | -3/+18 |
| | | | | | | Commit 11f056a3f0b87e86267efa8b5ac9d36a343c9dc1 broke the r300g build. Fix it up, and reinstate some code which isn't needed by r600g and radeonsi but is by r300g. | ||||
* | gallium/auxiliary/pipe-loader: Fix usage of anonymous union. | Francisco Jerez | 2012-05-16 | 3 | -8/+8 |
| | | | | | | | | | Anonymous unions aren't part of the C99 standard. Fixes build on GCC versions older than 4.6. https://bugs.freedesktop.org/show_bug.cgi?id=50001 Reported-by: Michael Lange <[email protected]> | ||||
* | radeonsi: Initial tiling support. | Michel Dänzer | 2012-05-16 | 7 | -131/+359 |
| | | | | Largely based on the corresponding Evergreen support in r600g. | ||||
* | r600g: Set tiling information for BOs being shared. | Michel Dänzer | 2012-05-16 | 3 | -9/+47 |
| | | | | Fixes https://bugs.freedesktop.org/show_bug.cgi?id=48747 | ||||
* | st/xorg: Better handling of EXA copies. | Michel Dänzer | 2012-05-16 | 4 | -225/+41 |
| | | | | | Always use the resource_copy_region hook. If a source and destination rectangle overlap, copy to/from a temporary pixmap. | ||||
* | radeonsi: Bump MAX_DRAW_CS_DWORDS. | Michel Dänzer | 2012-05-16 | 3 | -3/+3 |
| | | | | I missed this when updating si_context_draw(). | ||||
* | draw,llvmpipe: Avoid named struct types on LLVM 3.0 and later. | José Fonseca | 2012-05-16 | 2 | -30/+6 |
| | | | | | | | | | | | | Starting with LLVM 3.0, named structures are meant not for debugging, but for recursive data types, previously also known as opaque types. The recursive nature of these types leads to several memory management difficulties. Given that we don't actually need recursive types, avoid them altogether. This is an attempt to address fdo bugs 41791 and 44466. The issue is somewhat random so there's no easy way to check how effective this is. | ||||
* | llvmpipe: Color slot interpolation can be flat or perspective, not linear. | Olivier Galibert | 2012-05-16 | 3 | -3/+3 |
| | | | | | | | Fixes a bunch of glsl 1.10 interpolation piglit tests. Signed-off-by: Olivier Galibert <[email protected]> Signed-off-by: José Fonseca <[email protected]> | ||||
* | gallivm: Add MCRegisterInfo.h to silence benign warnings about missing ↵ | José Fonseca | 2012-05-15 | 1 | -0/+3 |
| | | | | | | implementation. Trivial. | ||||
* | llvmpipe: Add a test for lp_build_sgn. | José Fonseca | 2012-05-15 | 1 | -0/+13 |
| | | | | Only floating point though, but better than nothing. | ||||
* | gallivm: Fix lp_build_sgn for normalized/fixed-point integers. | José Fonseca | 2012-05-15 | 1 | -1/+2 |
| | | | | | These types got broken with the recent commit that fixed lp_build_sgn for negative integers. | ||||
* | gallivm: Fix lp_build_const_xxx for negative integers. | José Fonseca | 2012-05-15 | 1 | -5/+6 |
| | | | | | | Do proper rounding. Thanks to Olivier Galibert for investigating this. | ||||
* | svga: fix FBO / viewport bugs | Brian Paul | 2012-05-15 | 1 | -7/+24 |
| | | | | | | | | | | | When drawing to a FBO, the viewport wasn't always set correctly. It was fine in the usual case of the viewport dims matching the surface dims but broken otherwise. In particular, this was happening because the viewport scale is negative for FBO rendering. The piglit fbo-viewport test exercises this. Reviewed-by: José Fonseca <[email protected]> | ||||
* | radeon/llvm: add support for texture offsets, fix TEX_LD | Vadim Girlin | 2012-05-15 | 4 | -10/+51 |
| | | | | | Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: add SET_GRADIENTS*, fix SAMPLE_G | Vadim Girlin | 2012-05-15 | 6 | -9/+108 |
| | | | | | Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: increase const regs count | Vadim Girlin | 2012-05-15 | 1 | -1/+1 |
| | | | | | Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: use IntrNoMem property for intrinsics where possible | Vadim Girlin | 2012-05-15 | 7 | -105/+171 |
| | | | | | Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: use correct intrinsic for CEIL | Vadim Girlin | 2012-05-15 | 2 | -3/+3 |
| | | | | | | | Should be round_posinf instead of round_neginf. Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: improve ABS_i32 lowering | Vadim Girlin | 2012-05-15 | 1 | -13/+5 |
| | | | | | | | | | We can save one instruction by lowering it to: SUB_INT tmp, 0, src MAX_INT dst, src, tmp Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: fix BUILD_VECTOR lowering for replicated value | Vadim Girlin | 2012-05-15 | 1 | -0/+2 |
| | | | | | | | We expect that all elements will be assigned even if they are equal Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: add names for AMDGPU* passes | Vadim Girlin | 2012-05-15 | 2 | -0/+5 |
| | | | | | Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | radeon/llvm: add generated files to .gitignore | Vadim Girlin | 2012-05-15 | 1 | -0/+18 |
| | | | | | Signed-off-by: Vadim Girlin <[email protected]> Reviewed-by: Tom Stellard <[email protected]> | ||||
* | Add .gitignore files for recently-added gallium projects | Paul Berry | 2012-05-15 | 3 | -0/+3 |
| | | | | | | | This patch adds .gitignore files to ignore the makefiles generated by the gallium pipe loader and the clover OpenCL state tracker. Reviewed-by: Francisco Jerez <[email protected]> | ||||
* | radeonsi: Keep around copies of original sampler states. | Michel Dänzer | 2012-05-14 | 1 | -0/+2 |
| | | | | Fixes crashes when restoring sampler states after blits. | ||||
* | radeonsi: Flesh out shader interpolation related code. | Michel Dänzer | 2012-05-14 | 3 | -4/+38 |
| | | | | Handle perspective interpolation and ceontroid vs. center. | ||||
* | radeonsi: Add proper SI family names. | Michel Dänzer | 2012-05-14 | 1 | -1/+3 |
| | |||||
* | radeonsi: Separate states for samplers and sampler views. | Michel Dänzer | 2012-05-14 | 2 | -3/+6 |
| | | | | And reset nregs on updates. Prevents eventual assertion failure. | ||||
* | radeonsi: Fixups for drawing with an index buffer. | Michel Dänzer | 2012-05-14 | 3 | -14/+13 |
| | | | | | Mostly using the DRAW_INDEX_2 type 3 packet instead of DRAW_INDEX, which is no longer supported on SI. | ||||
* | vl: Initialize pipe_vertex_buffer.user_buffer fields. | Vinson Lee | 2012-05-14 | 1 | -0/+4 |
| | | | | | | | Fix uninitialized scalar variable defects reported by Coverity. Signed-off-by: Vinson Lee <[email protected]> Reviewed-by: José Fonseca <[email protected]> | ||||
* | llvmpipe: Calculate fixed point coordinates for triangle setup earlier. | James Benton | 2012-05-14 | 1 | -56/+106 |
| | | | | | | | | | | | | 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 <[email protected]> Reviewed-by: Brian Paul <[email protected]> | ||||
* | radeon/llvm: Coding style fixes for R600CodeEmitter.cpp | Tom Stellard | 2012-05-14 | 1 | -148/+90 |
| | |||||
* | radeon/llvm: Lower bitcast instructions to copies | Tom Stellard | 2012-05-14 | 1 | -0/+10 |
| | |||||
* | radeonsi: remove slab allocator for pipe_resource (used mainly for user buffers) | Marek Olšák | 2012-05-13 | 3 | -41/+3 |
| | |||||
* | r600g: remove slab allocator for pipe_resource (used mainly for user buffers) | Marek Olšák | 2012-05-13 | 3 | -41/+4 |
| | |||||
* | r600g: handle R16G16B16_FLOAT and R32G32B32_FLOAT in translate_colorswap (EG) | Marek Olšák | 2012-05-12 | 1 | -0/+2 |
| | |||||
* | gallium: remove user_buffer_create from the interface | Marek Olšák | 2012-05-12 | 21 | -233/+1 |
| | | | | Nothing uses it now. | ||||
* | gallium/graw: stop using user_buffer_create | Marek Olšák | 2012-05-12 | 16 | -73/+106 |
| | | | | This is compile-tested. | ||||
* | gallium/util: remove unused parameter nr_vertex_buffers in util_draw_max_index | Marek Olšák | 2012-05-12 | 3 | -3/+0 |
| | |||||
* | clover: Fix build on i386. | Francisco Jerez | 2012-05-12 | 1 | -1/+2 |
| | |||||
* | clover: Check the total work-group size provided to clEnqueueNDRangeKernel. | Francisco Jerez | 2012-05-12 | 1 | -10/+17 |
| |