diff options
| author | Chris Wilson <chris@chris-wilson.co.uk> | 2013-07-12 23:20:56 +0100 |
|---|---|---|
| committer | Chris Wilson <chris@chris-wilson.co.uk> | 2013-07-12 23:21:27 +0100 |
| commit | 835ceccb27afa18704c34dc3283476340f999317 (patch) | |
| tree | c6d1ed7489ebe23706210fc6bc262407a8665016 /src/sna/gen5_render.c | |
| parent | 39f1954f667bf20cd0c25dfa5fb5267a3f9eb113 (diff) | |
sna/gen5: Add some more DBG
Signed-off-by: Chris Wilson <chris@chris-wilson.co.uk>
Diffstat (limited to 'src/sna/gen5_render.c')
| -rw-r--r-- | src/sna/gen5_render.c | 12 |
1 files changed, 11 insertions, 1 deletions
diff --git a/src/sna/gen5_render.c b/src/sna/gen5_render.c index b31ac1e9..2b75ff6b 100644 --- a/src/sna/gen5_render.c +++ b/src/sna/gen5_render.c @@ -2247,6 +2247,13 @@ gen5_render_copy_boxes(struct sna *sna, uint8_t alu, { struct sna_composite_op tmp; + DBG(("%s alu=%d, src=%d:handle=%d, dst=%d:handle=%d boxes=%d x [((%d, %d), (%d, %d))...], flags=%x\n", + __FUNCTION__, alu, + src->drawable.serialNumber, src_bo->handle, + dst->drawable.serialNumber, dst_bo->handle, + n, box->x1, box->y1, box->x2, box->y2, + flags)); + if (sna_blt_compare_depth(&src->drawable, &dst->drawable) && sna_blt_copy_boxes(sna, alu, src_bo, src_dx, src_dy, @@ -2359,8 +2366,10 @@ fallback_blt: if (!kgem_check_bo(&sna->kgem, dst_bo, src_bo, NULL)) { kgem_submit(&sna->kgem); - if (!kgem_check_bo(&sna->kgem, dst_bo, src_bo, NULL)) + if (!kgem_check_bo(&sna->kgem, dst_bo, src_bo, NULL)) { + DBG(("%s: aperture check failed\n", __FUNCTION__)); goto fallback_tiled_src; + } } dst_dx += tmp.dst.x; @@ -2420,6 +2429,7 @@ fallback_tiled: box, n)) return true; + DBG(("%s: tiled fallback\n", __FUNCTION__)); return sna_tiling_copy_boxes(sna, alu, src, src_bo, src_dx, src_dy, dst, dst_bo, dst_dx, dst_dy, |