gmane.comp.video.dri.devel

[Bug 64257] RS880 issues with r600-llvm-compiler

2013-05-18T23:24:59

https://bugs.freedesktop.org/show_bug.cgi?id=64257

--- Comment #11 from Tom Stellard <tstellar< at >gmail.com> ---
(In reply to comment #10)

It's possible that the recent scheduling changes have caused an unrelated
regression.  Does kwin render correctly if you use the LLVM 3.3 branch?

[Bug 60879] [radeonsi] X11 can't start with acceleration enabled

2013-05-18T23:18:02

https://bugs.freedesktop.org/show_bug.cgi?id=60879

--- Comment #33 from Tom Stellard <tstellar< at >gmail.com> ---
(In reply to comment #32)

All that is supported in the git tree is stores to global memory.  I have
global loads, work item functions, and a fair amount of arithmetic operations
working in a local branch, and I hope to get that pushed to mainline in the
next week or two.

[PATCH] drm/radeon: Fix VRAM size calculation for VRAM >= 4GB

Niels Ole Salscheider — 2013-05-18T19:19:23

Add ULL prefix to avoid overflow.

Signed-off-by: Niels Ole Salscheider <niels_ole< at >salscheider-online.de>
---
 drivers/gpu/drm/radeon/evergreen.c  | 4 ++--
 drivers/gpu/drm/radeon/radeon_ttm.c | 2 +-
 drivers/gpu/drm/radeon/si.c         | 4 ++--
 3 files changed, 5 insertions(+), 5 deletions(-)

diff --git a/drivers/gpu/drm/radeon/evergreen.c b/drivers/gpu/drm/radeon/evergreen.c
index 105bafb..06c261b 100644
--- a/drivers/gpu/drm/radeon/evergreen.c
+++ b/drivers/gpu/drm/radeon/evergreen.c
< at >< at > -3405,8 +3405,8 < at >< at > int evergreen_mc_init(struct radeon_device *rdev)
 rdev->mc.real_vram_size = RREG32(CONFIG_MEMSIZE);
 } else {
 /* size in MB on evergreen/cayman/tn */
-rdev->mc.mc_vram_size = RREG32(CONFIG_MEMSIZE) * 1024 * 1024;
-rdev->mc.real_vram_size = RREG32(CONFIG_MEMSIZE) * 1024 * 1024;
+rdev->mc.mc_vram_size = RREG32(CONFIG_MEMSIZE) * 1024ULL * 1024ULL;
+rdev->mc.real_vram_size = RREG32(CONFIG_MEMSIZE) * 1024ULL * 1024ULL;
 }
 rdev->mc.visible_vram_size = rdev->mc.aper_size;
 r700_vram_gtt_loc

[RFC 4/4] DRM: tda998x: add missing include

Sebastian Hesselbarth — 2013-05-18T17:12:19

The RFC sent by Russell King was missing an include for tda998x. This
is just a compatible clone to remember Russell to add that later.

Signed-off-by: Sebastian Hesselbarth <sebastian.hesselbarth< at >gmail.com>
---
Cc: Russell King <linux< at >arm.linux.org.uk>
Cc: linux-arm-kernel< at >lists.infradead.org
Cc: dri-devel< at >lists.freedesktop.org
Cc: Jason Cooper <jason< at >lakedaemon.net>
Cc: Jean-Francois Moine <moinejf< at >free.fr>
---
 include/drm/i2c/tda998x.h |   23 +++++++++++++++++++++++
 1 file changed, 23 insertions(+)
 create mode 100644 include/drm/i2c/tda998x.h

diff --git a/include/drm/i2c/tda998x.h b/include/drm/i2c/tda998x.h
new file mode 100644
index 0000000..41f799f
--- /dev/null
+++ b/include/drm/i2c/tda998x.h
< at >< at > -0,0 +1,23 < at >< at >
+#ifndef __TDA998X_H__
+#define __TDA998X_H__
+
+enum tda998x_audio_format {
+AFMT_I2S,
+AFMT_SPDIF,
+};
+
+struct tda998x_encoder_params {
+int audio_cfg;
+int audio_clk_cfg;
+enum tda998x_audio_format audio_format;
+int audio_sample_rate;
+char audio_frame[6];
+int swap_a, mirr_a;
+

[RFC 3/4] DRM: add OF support for Dove DRM driver

Sebastian Hesselbarth — 2013-05-18T17:12:18

This adds OF support for the Dove DRM driver recently posted as RFC by
Russell King.

Signed-off-by: Sebastian Hesselbarth <sebastian.hesselbarth< at >gmail.com>
---
Cc: Russell King <linux< at >arm.linux.org.uk>
Cc: linux-arm-kernel< at >lists.infradead.org
Cc: dri-devel< at >lists.freedesktop.org
Cc: Jason Cooper <jason< at >lakedaemon.net>
Cc: Jean-Francois Moine <moinejf< at >free.fr>
---
 drivers/gpu/drm/dove/Kconfig     |    4 ++
 drivers/gpu/drm/dove/Makefile    |    1 +
 drivers/gpu/drm/dove/dove_card.c |  110 ++++++++++++++++++++++++++++++++++++++
 3 files changed, 115 insertions(+)
 create mode 100644 drivers/gpu/drm/dove/dove_card.c

diff --git a/drivers/gpu/drm/dove/Kconfig b/drivers/gpu/drm/dove/Kconfig
index 718d3c5..a943ea5 100644
--- a/drivers/gpu/drm/dove/Kconfig
+++ b/drivers/gpu/drm/dove/Kconfig
< at >< at > -28,4 +28,8 < at >< at > config DRM_DOVE_TDA1998X
 config DRM_DOVE_CURSOR
 bool "Enable Dove DRM hardware cursor support"
 
+config DRM_DOVE_OF
+bool "Enable Dove DRM OF video card"
+depends on OF
+
 endif
diff --git a/drivers/gpu/

[RFC 0/4] Add DT support to rmk's Dove DRM driver

Sebastian Hesselbarth — 2013-05-18T17:12:15

This RFC adds DT support to the DRM driver for Marvell Dove SoCs
posted by Russell King recently. For those booting DT with appended
ATAGs, remember to reduce probed memory by passing mem=1008M as
kernel parameter.

There was an include missing in Russell's RFC that is also added.

Sebastian Hesselbarth (4):
  ARM: dove: add lcd controller DT nodes
  ARM: dove: add video card node for SolidRun CuBox
  DRM: add OF support for Dove DRM driver
  DRM: tda998x: add missing include

 arch/arm/boot/dts/dove-cubox.dts |   16 +++++-
 arch/arm/boot/dts/dove.dtsi      |   16 ++++++
 drivers/gpu/drm/dove/Kconfig     |    4 ++
 drivers/gpu/drm/dove/Makefile    |    1 +
 drivers/gpu/drm/dove/dove_card.c |  110 ++++++++++++++++++++++++++++++++++++++
 include/drm/i2c/tda998x.h        |   23 ++++++++
 6 files changed, 169 insertions(+), 1 deletion(-)
 create mode 100644 drivers/gpu/drm/dove/dove_card.c
 create mode 100644 include/drm/i2c/tda998x.h
---
Cc: Russell King <linux< at >arm.linux.org.uk>
Cc: linux-arm-kernel< at >lists.infra

[RFC 1/4] ARM: dove: add lcd controller DT nodes

Sebastian Hesselbarth — 2013-05-18T17:12:16

This adds device tree nodes for the lcd controllers found on Marvell
Dove SoCs. For now, there is no DT documentation and clocks property
should refer to clock connected to extclk0 pin.

Signed-off-by: Sebastian Hesselbarth <sebastian.hesselbarth< at >gmail.com>
---
Cc: Russell King <linux< at >arm.linux.org.uk>
Cc: linux-arm-kernel< at >lists.infradead.org
Cc: dri-devel< at >lists.freedesktop.org
Cc: Jason Cooper <jason< at >lakedaemon.net>
Cc: Jean-Francois Moine <moinejf< at >free.fr>
---
 arch/arm/boot/dts/dove.dtsi |   16 ++++++++++++++++
 1 file changed, 16 insertions(+)

diff --git a/arch/arm/boot/dts/dove.dtsi b/arch/arm/boot/dts/dove.dtsi
index 6cab468..2053e86 100644
--- a/arch/arm/boot/dts/dove.dtsi
+++ b/arch/arm/boot/dts/dove.dtsi
< at >< at > -258,5 +258,21 < at >< at >
 dmacap,xor;
 };
 };
+
+lcd0: lcd-controller< at >820000 {
+compatible = "marvell,dove-lcd";
+reg = <0x820000 0x200>;
+interrupts = <47>;
+clocks = <0>;
+status = "disabled";
+};
+
+lcd1: lcd-controller< at >810000 {
+compatible = "marvell,dove-lcd";
+

[RFC 2/4] ARM: dove: add video card node for SolidRun CuBox

Sebastian Hesselbarth — 2013-05-18T17:12:17

This adds a video card node required for rmk's dove_drm driver. Reg
property matches reserved memory region (currently 16M at top of memory),
clocks property should carry extclk0 for now.

Signed-off-by: Sebastian Hesselbarth <sebastian.hesselbarth< at >gmail.com>
---
Cc: Russell King <linux< at >arm.linux.org.uk>
Cc: linux-arm-kernel< at >lists.infradead.org
Cc: dri-devel< at >lists.freedesktop.org
Cc: Jason Cooper <jason< at >lakedaemon.net>
Cc: Jean-Francois Moine <moinejf< at >free.fr>
---
 arch/arm/boot/dts/dove-cubox.dts |   16 +++++++++++++++-
 1 file changed, 15 insertions(+), 1 deletion(-)

diff --git a/arch/arm/boot/dts/dove-cubox.dts b/arch/arm/boot/dts/dove-cubox.dts
index ed2b7b2..f26d0d2 100644
--- a/arch/arm/boot/dts/dove-cubox.dts
+++ b/arch/arm/boot/dts/dove-cubox.dts
< at >< at > -8,7 +8,7 < at >< at >
 
 memory {
 device_type = "memory";
-reg = <0x00000000 0x40000000>;
+reg = <0x00000000 0x3f000000>;
 };
 
 chosen {
< at >< at > -52,10 +52,24 < at >< at >
 #clock-cells = <0>;
 };
 };
+
+video {
+compatible = "simple-bus";
+#address-cells

[Bug 60879] [radeonsi] X11 can't start with acceleration enabled

2013-05-18T19:31:20

https://bugs.freedesktop.org/show_bug.cgi?id=60879

--- Comment #32 from Hristo Venev <mustrumr97< at >gmail.com> ---
Created attachment 79504
  --> https://bugs.freedesktop.org/attachment.cgi?id=79504&action=edit
Results of OpenCL test

BREAKTHROUGH!

OpenCL works. Kinda. Tried the following kernel:
__kernel void add(__global const uint *a,  __global const uint *b, __global
uint *c){
    c[0]=1;
}
Complicated operations such as addition, memory loads, getting global ID, etc.
fail with Cannot select errors.
I have no idea if this has worked with earlier LLVM/mesa.

After the kernel is run, the 0-th element of c is equal to 1. I've attached
full source code and outputs for various kernels.

Re: [RFC 4/4] DRM: tda998x: add missing include

Rob Clark — 2013-05-18T19:11:03

ok, maybe I am misunderstanding you.  I think the parameters should be
filled in by the board file on a non-DT setup.  But the part in
drivers/gpu/drm/i2c should not pull them directly out of DT, or should
have an arrangement like

 #ifdef CONFIG_OF
 .. pull params out of DT ..
#else
 .. use params passed in from via params struct, which is populated in
board file ..
#endif

to accommodate non-DT builds.  (Although I think just having a helper
to populate 'struct tda998x_encoder_params' from DT seems cleaner.)


BR,
-R

Re: [RFC 4/4] DRM: tda998x: add missing include

Rob Clark — 2013-05-18T18:23:19

You might not want to directly have a hard DT dependency in tda998x,
as the encoder could be used on non-DT platforms.  Although a DT to
encoder-params helper might be a nice idea for platforms which do have
DT.

BR,
-R

[Bug 64738] graphics corruption with glamor

2013-05-18T12:39:11

https://bugs.freedesktop.org/show_bug.cgi?id=64738

--- Comment #5 from Alexander Tsoy <alexander< at >tsoy.me> ---
Created attachment 79497
  --> https://bugs.freedesktop.org/attachment.cgi?id=79497&action=edit
Screenshot of notification area

No claws-mail and gajim icons here.

[Bug 63579] Savage 2 Edges render white [r600g]

2013-05-18T12:37:46

https://bugs.freedesktop.org/show_bug.cgi?id=63579

--- Comment #20 from Alex Deucher <agd5f< at >yahoo.com> ---
yes:
http://cgit.freedesktop.org/mesa/mesa/commit/?id=f732036f12d67a96f546c11236fa635b3eda6e9c

[Bug 64257] RS880 issues with r600-llvm-compiler

2013-05-18T11:56:58

https://bugs.freedesktop.org/show_bug.cgi?id=64257

--- Comment #10 from Mike Lothian <mike< at >fireburn.co.uk> ---
I've now recompiled everything from upstream - kwin now renders however it has
a pinkish hugh to the bottom right - this didn't happen when I tested the
patches separately

[Bug 64738] graphics corruption with glamor

2013-05-18T11:44:51

https://bugs.freedesktop.org/show_bug.cgi?id=64738

--- Comment #4 from Alexander Tsoy <alexander< at >tsoy.me> ---
This graphics artifacts are persist until the window is redrawn.

[Bug 64738] graphics corruption with glamor

2013-05-18T11:41:46

https://bugs.freedesktop.org/show_bug.cgi?id=64738

--- Comment #3 from Alexander Tsoy <alexander< at >tsoy.me> ---
Created attachment 79496
  --> https://bugs.freedesktop.org/attachment.cgi?id=79496&action=edit
Xorg log

[Bug 64738] graphics corruption with glamor

2013-05-18T11:40:55

https://bugs.freedesktop.org/show_bug.cgi?id=64738

--- Comment #2 from Alexander Tsoy <alexander< at >tsoy.me> ---
Created attachment 79495
  --> https://bugs.freedesktop.org/attachment.cgi?id=79495&action=edit
screenshot [2]

[Bug 64738] graphics corruption with glamor

2013-05-18T11:40:27

https://bugs.freedesktop.org/show_bug.cgi?id=64738

--- Comment #1 from Alexander Tsoy <alexander< at >tsoy.me> ---
Created attachment 79494
  --> https://bugs.freedesktop.org/attachment.cgi?id=79494&action=edit
screenshot [1]

[Bug 64738] New: graphics corruption with glamor

2013-05-18T11:40:01

https://bugs.freedesktop.org/show_bug.cgi?id=64738

          Priority: medium
            Bug ID: 64738
          Assignee: dri-devel< at >lists.freedesktop.org
           Summary: graphics corruption with glamor
          Severity: normal
    Classification: Unclassified
                OS: All
          Reporter: alexander< at >tsoy.me
          Hardware: Other
            Status: NEW
           Version: git
         Component: Drivers/Gallium/radeonsi
           Product: Mesa

I have these problems with Cape Verde Pro (HD 7750) card:
1. Graphics corruption when scrolling in gtk2/gtk3 apps (screenshot [1])
2. Graphics corruption when moving windows in wm whithout compositing. Both gtk
and qt apps are affected. No such artifacts when compositing enabled, e.g. in
gnome 3. (screenshot [2])
3. Missing notification icons of gtk2 apps in awesome wm.

All of this things works great whithout glamor. Also no such problems with HD
6450 card with both EXA and glamor acceleration.

Software:
- mesa-9.2 from git
- llvm-3.{3,4}

Re: Introduce a new helper framework for buffer synchronization

Inki Dae — 2013-05-18T07:43:27

Hi Daniel,

2013/5/17 Daniel Vetter <daniel< at >ffwll.ch>




I'm not sure that I understood your concerns but it seems that you say we
have to prohibit userspace from blocking dma. Could you please give me more
detail for it? Without critical problem by userspace, this appoach is a
better way against the traditional at least for ARM based embedded system.
For this, I had already mentioned before like below,
               http://www.spinics.net/lists/dri-devel/msg38359.html

If you agree to my opinion, I'd like to say we could try to solve this
problem in the long term. If we prohibit such interfaces from be used
without sure reason, I carefully think we might to be just going thourgh
the motions: we have to use traditional way NECESSARILY. As previously
stated, could please tell me about that there are sure reasons we have to
prohibit the such user interfaces from being used necessarily and
there is really no any way we have to solve that? Basically, I have
designed and implemented that all resources to user f

Re: Introduce a new helper framework for buffer synchronization

Inki Dae — 2013-05-18T06:47:43

2013/5/15 Rob Clark <robdclark< at >gmail.com>

Right, this is very important. I think it's not esay to solve this
issue. Aand at least for ARM based embedded system, such feature is useful
to us; coupling cache operation and buffer synchronization. I'd like to
collect other opinions and advices to solve this issue.

Thanks,
Inki Dae


_______________________________________________
dri-devel mailing list
dri-devel< at >lists.freedesktop.org
http://lists.freedesktop.org/mailman/listinfo/dri-devel