summaryrefslogtreecommitdiff
path: root/src/sna/gen4_render.c
diff options
context:
space:
mode:
authorChris Wilson <chris@chris-wilson.co.uk>2012-12-29 15:53:23 +0000
committerChris Wilson <chris@chris-wilson.co.uk>2012-12-29 16:06:19 +0000
commit1c2ece369177ea6c3fd2f254b2554ceadf5590de (patch)
tree37361ffac8d5c7b7b15fe28e4d58a9001a19aed3 /src/sna/gen4_render.c
parent09ca8feb3455c979e799ddf26daae8f2de2813e1 (diff)
sna/gen4+: Try using the BLT before doing a tiled copy
Signed-off-by: Chris Wilson <chris@chris-wilson.co.uk>
Diffstat (limited to 'src/sna/gen4_render.c')
-rw-r--r--src/sna/gen4_render.c8
1 files changed, 8 insertions, 0 deletions
diff --git a/src/sna/gen4_render.c b/src/sna/gen4_render.c
index 84d78531..3486e086 100644
--- a/src/sna/gen4_render.c
+++ b/src/sna/gen4_render.c
@@ -2478,6 +2478,14 @@ fallback_tiled_dst:
if (tmp.redirect.real_bo)
kgem_bo_destroy(&sna->kgem, tmp.dst.bo);
fallback_tiled:
+ if (sna_blt_compare_depth(&src->drawable, &dst->drawable) &&
+ sna_blt_copy_boxes(sna, alu,
+ src_bo, src_dx, src_dy,
+ dst_bo, dst_dx, dst_dy,
+ dst->drawable.bitsPerPixel,
+ box, n))
+ return true;
+
return sna_tiling_copy_boxes(sna, alu,
src, src_bo, src_dx, src_dy,
dst, dst_bo, dst_dx, dst_dy,