summaryrefslogtreecommitdiffstats
path: root/src/gallium/state_trackers
Commit message (Collapse)AuthorAgeFilesLines
* clover: Add function for building a clover::module for non-TGSI targets v6Tom Stellard2012-06-013-14/+158
| | | | | | | | | | | | | | | | | | | | | | | | v2: -Separate IR type and LLVM triple -Do the OpenCL C->LLVM IR and linking steps for all PIPE_SHADER_IR types. v3: - Coding style fixes - Removed compatibility code for LLVM < 3.1 - Split build_module_llvm() into three functions: compile(), link(), and build_module_llvm() v4: - Use struct pipe_compute_program v5: - Don't malloc memory for struct pipe_llvm_program v6: - Fix serialization of llvm bytecode Reviewed-by: Francisco Jerez <[email protected]>
* clover: Remove target argument from compile_program_tgsi()Tom Stellard2012-06-013-5/+3
| | | | Reviewed-by: Francisco Jerez <[email protected]>
* clover: Add constructors to some of the module classes v3Tom Stellard2012-06-011-0/+13
| | | | | | | | | | | | This is for the llvm code that can't use extended initializers. v2: - Use const references for vector arguments - Move constructor defs before data members - Initialize all values in the default constructors v3: - Fix typo
* clover: Add necessary flags to libclllvm_la_CXXFLAGSTom Stellard2012-06-011-1/+5
| | | | | | | $(LLVM_CFLAGS) for LLVM defines -DLIBCLC_PATH for libclc path -DCLANG_RESOURCE_DIR for clang includes $(DEFINES) for -DHAVE_LLVM
* clover: Add a function for retrieving a device's preferred ir v3Tom Stellard2012-06-012-8/+11
| | | | | | | | | | | | | | | | | | | A device now has two function for getting information about the IR it needs to return. ir_format() => returns the preferred IR ir_target() => returns the triple for the target that is understood by clang/llvm. v2: - renamed ir_target() to ir_format() - renamed llvm_triple() to ir_target() v3: - Remove unnecessary include - Do proper conversion from std::vector<char> to std::string Reviewed-by: Francisco Jerez <[email protected]>
* gallium: add st_api feature mask to prevent advertising MS visualsChristoph Bumiller2012-05-292-12/+20
| | | | | | | | | | | | | | v2: use a define for the maximum sample count v3: also test odd sample counts (r300 supports MS3) While multisample renderbuffers are supported by mesa, MS visuals are not, so we need a way to tell dri/st not to advertise them even if the gallium driver does support multisampled surfaces. Otherwise applications selecting these non-functional visuals would run into trouble ... Reviewed-by: Brian Paul <[email protected]>
* gallium/auxiliary/pipe-loader: Fix usage of anonymous union.Francisco Jerez2012-05-161-1/+1
| | | | | | | | | 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]>
* st/xorg: Better handling of EXA copies.Michel Dänzer2012-05-164-225/+41
| | | | | Always use the resource_copy_region hook. If a source and destination rectangle overlap, copy to/from a temporary pixmap.
* Add .gitignore files for recently-added gallium projectsPaul Berry2012-05-151-0/+1
| | | | | | | 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]>
* clover: Fix build on i386.Francisco Jerez2012-05-121-1/+2
|
* clover: Check the total work-group size provided to clEnqueueNDRangeKernel.Francisco Jerez2012-05-121-10/+17
|
* clover, gallium: add PIPE_COMPUTE_CAP_MAX_THREADS_PER_BLOCKChristoph Bumiller2012-05-123-1/+9
| | | | | | | This is not necessarily the product of MAX_BLOCK_SIZE[i]. Reviewed-by: Tom Stellard <[email protected]> Reviewed-by: Francisco Jerez <[email protected]>
* scons: Fix missing gbm symbols in st/egl.José Fonseca2012-05-121-3/+5
|
* vega: fix 565 color unpacking bugAndreas Betz2012-05-111-2/+2
| | | | | | NOTE: This is a candidate for the 8.0 branch. Signed-off-by: Brian Paul <[email protected]>
* Merge branch 'gallium-userbuf'Marek Olšák2012-05-117-143/+53
|\ | | | | | | | | | | | | | | Conflicts: src/gallium/docs/source/screen.rst src/gallium/drivers/nv50/nv50_state.c src/gallium/include/pipe/p_defines.h src/mesa/state_tracker/st_draw.c
| * st/xorg: don't use user_buffer_createMarek Olšák2012-04-301-51/+16
| |
| * st/xa: don't use user_buffer_createMarek Olšák2012-04-301-44/+15
| |
| * st/vega: don't use user_buffer_createMarek Olšák2012-04-302-36/+10
| |
| * st/vega: use cso_draw_arraysMarek Olšák2012-04-301-3/+3
| |
| * st/xorg: fix compilation - wrong libkms include fileMarek Olšák2012-04-302-2/+2
| |
| * gallium: change set_constant_buffer to be UBO-friendlyMarek Olšák2012-04-304-7/+7
| |
* | clover: Implement CL_MEM_COPY_HOST_PTR.Francisco Jerez2012-05-114-7/+20
| |
* | clover: Import OpenCL state tracker.Francisco Jerez2012-05-1142-1/+7966
| |
* | gallium/gbm: Switch to auxiliary/pipe-loader.Francisco Jerez2012-05-112-4/+4
| | | | | | | | Reviewed-by: Jakob Bornecrantz <[email protected]>
* | gallium/tgsi: Split sampler views from shader resources.Francisco Jerez2012-05-111-6/+7
| | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | | This commit splits the current concept of resource into "sampler views" and "shader resources": "Sampler views" are textures or buffers that are bound to a given shader stage and can be read from in conjunction with a sampler object. They are analogous to OpenGL texture objects or Direct3D SRVs. "Shader resources" are textures or buffers that can be read and written from a shader. There's no support for floating point coordinates, address wrap modes or filtering, and, unlike sampler views, shader resources are global for the whole graphics pipeline. They are analogous to OpenGL image objects (as in ARB_shader_image_load_store) or Direct3D UAVs. Most hardware is likely to implement shader resources and sampler views as separate objects, so, having the distinction at the API level simplifies things slightly for the driver. This patch introduces the SVIEW register file with a declaration token and syntax analogous to the already existing RES register file. After this change, the SAMPLE_* opcodes no longer accept a resource as input, but rather a SVIEW object. To preserve the functionality of reading from a sampler view with integer coordinates, the SAMPLE_I(_MS) opcodes are introduced which are similar to LOAD(_MS) but take a SVIEW register instead of a RES register as argument.
* | egl-fbdev: Fix compile-error by including errno.hDavid Herrmann2012-04-301-0/+1
|/ | | | | | | | | | | | | We use errno and EINVAL so include errno.h. This patch introduced this bug: http://cgit.freedesktop.org/mesa/mesa/commit/src/gallium/state_trackers/egl/fbdev/native_fbdev.c?id=b60120608f6ddf4098bc324363197c979ee04cb7 Signed-off-by: David Herrmann <[email protected]> Cc: Chia-I Wu <[email protected]> Cc: Dave Airlie <[email protected]> Cc: Adam Jackson <[email protected]> Cc: Jesse Barnes <[email protected]>
* gallium: remove PIPE_TRANSFER_NOOVERWRITE, use equivalent UNSYNCHRONIZEDMarek Olšák2012-04-181-1/+1
|
* st/vega: silence enum cast warningsDylan Noblesmith2012-04-131-4/+5
| | | | | | | | | | | | clang warns on these: stroker.c:626:19: warning: implicit conversion from enumeration type 'VGPathCommand' to different enumeration type 'VGPathSegment' [-Wconversion] No change in the underlying value. Reviewed-by: Brian Paul <[email protected]>
* st/vega: fix uninitialized valuesDylan Noblesmith2012-04-131-2/+2
| | | | | | | | | | | | | | | | | | C still treats array arguments exactly like pointer arguments. By sheer coincidence, this still worked fine on 64-bit machines where 2 * sizeof(float) == sizeof(void*), but not on 32-bit. Noticed by clang: text.c:76:51: warning: sizeof on array function parameter will return size of 'const VGfloat *' (aka 'const float *') instead of 'const VGfloat [2]' [-Wsizeof-array-argument] memcpy(glyph->glyph_origin, glyphOrigin, sizeof(glyphOrigin)); NOTE: This is a candidate for the 8.0 branch. Reviewed-by: Brian Paul <[email protected]>
* st/xa: Link with -Wl,-r instead of -r.Johannes Obermayr2012-04-071-1/+1
| | | | | This is required to link with clang: /usr/bin/ld: warning: cannot find entry symbol _start; defaulting to 0000000000400160.
* xatracker: fix the build of a 32bit lib on a 64bit osAlexandre Demers2012-04-051-1/+1
| | | | | | we were missing cflags. Signed-off-by: Zack Rusin <[email protected]>
* st/egl: Update to the new wl_shm_pool interfaceBenjamin Franzke2012-04-031-3/+8
|
* st/vdpau: fix deadlock in PresentationQueueQuerySurfaceStatusChristian König2012-04-031-1/+2
| | | | Signed-off-by: Christian König <[email protected]>
* vl: move winsys helper out of winsys directoryChristian König2012-03-2810-21/+8
| | | | | | | | | They aren't winsys of their own, just help dealing with them. v2: add some more comments in vl_winsys.h Signed-off-by: Christian König <[email protected]>
* st/egl: Also remove wl_buffer_damage in wayland backendBenjamin Franzke2012-03-271-1/+0
| | | | As commit 03eca9d92d407c71a59ff8a43067759769da0ae4 does for egl_dri2.
* st/vdpau: clear video surface at least onceChristian König2012-03-263-0/+31
| | | | | | | | So if anything goes wrong we won't display a random image. v2: flush before using the surface with the decoder. Signed-off-by: Christian König <[email protected]>
* st/vdpau: invert interlaced buffer checksChristian König2012-03-261-1/+1
| | | | | | That wasn't working as supposed. Signed-off-by: Christian König <[email protected]>
* drisw: fix image stride calculation for 16-bit.Dave Airlie2012-03-251-3/+3
| | | | | | | | | | | If you ran g-s in 16-bpp we'd do a bunch of memory corruption. now it just misrenders for some other reasons. applies to stable. Signed-off-by: Dave Airlie <[email protected]> Reviewed-by: Brian Paul <[email protected]>
* st/vdpau: improve frame dumping functionality a bitChristian König2012-03-221-3/+6
| | | | | | | Just a workaround until we get a real unit- testing tool for VDPAU. Signed-off-by: Christian König <[email protected]>
* st/vdpau: add VC-1 startcode if none is found in the streamChristian König2012-03-221-7/+42
| | | | | | v2: only advanced profile needs that. Signed-off-by: Christian König <[email protected]>
* egl/drm: Include errno.hJosé Fonseca2012-03-111-0/+1
| | | | Fixes scons build.
* Set close on exec flag FD_CLOEXECDavid Fries2012-03-114-4/+38
| | | | | | | | | Set the close on exec flag when opening dri character devices, so they will be closed and free any resouces allocated in exec. Signed-off-by: David Fries <[email protected]> Reviewed-by: Adam Jackson <[email protected]> Signed-off-by: Dave Airlie <[email protected]>
* st/vdpau: fix two small memory leaksChristian König2012-03-092-2/+6
| | | | Signed-off-by: Christian König <[email protected]>
* st/vdpau: add xine workaroundChristian König2012-03-091-1/+1
| | | | | | | For reasons I don't understand xine tries to set the surface format by using a zero pitch. Signed-off-by: Christian König <[email protected]>
* gallium: remove format aliasesChristian König2012-03-081-1/+1
| | | | | | They are incomplete and don't make to much sense. Signed-off-by: Christian König <[email protected]>
* st/vdpau: cleanup YCBCR matching functionsChristian König2012-03-081-6/+6
| | | | Signed-off-by: Christian König <[email protected]>
* st/vdpau: fix chroma_format handling in ↵Christian König2012-03-081-4/+18
| | | | | | VideoSurfaceQueryGetPutBitsYCbCrCapabilities Signed-off-by: Christian König <[email protected]>
* wayland: Use new wl_display_disconnectBenjamin Franzke2012-03-052-2/+2
| | | | | | This replaces the previously used wl_display_destroy. wl_display_destroy was povided by wayland-client.so and wayland-server.so, to resolve that conflict its renamed client-side.
* st/vdpau: make the interface thread saveChristian König2012-03-059-35/+175
| | | | Signed-off-by: Christian König <[email protected]>
* st/vdpau: implement support for high-precision output timingChristian König2012-03-051-10/+3
| | | | Signed-off-by: Christian König <[email protected]>
generated by cgit v1.2.3 (git 2.39.1) at 2024-12-24 05:47:09 +0000