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 | |
| parent | 39f1954f667bf20cd0c25dfa5fb5267a3f9eb113 (diff) | |
sna/gen5: Add some more DBG
Signed-off-by: Chris Wilson <chris@chris-wilson.co.uk>
| -rw-r--r-- | src/sna/gen5_render.c | 12 | ||||
| -rw-r--r-- | src/sna/sna_blt.c | 2 |
2 files changed, 12 insertions, 2 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, diff --git a/src/sna/sna_blt.c b/src/sna/sna_blt.c index ec3278bf..1df23def 100644 --- a/src/sna/sna_blt.c +++ b/src/sna/sna_blt.c @@ -2667,7 +2667,7 @@ bool sna_blt_fill_boxes(struct sna *sna, uint8_t alu, __FUNCTION__, bpp, pixel, alu, nbox)); if (!kgem_bo_can_blt(kgem, bo)) { - DBG(("%s: fallback -- dst uses Y-tiling\n", __FUNCTION__)); + DBG(("%s: fallback -- cannot blt to dst\n", __FUNCTION__)); return false; } |