[PATCH] Test USE_GCC_INLINE_ASM instead of USE_NEON_INLINE_ASM. The former is now Autoconf enabled, and does what it says on the tin.
Jonathan Morton
jmorton at sd070.hel.movial.fi
Thu May 7 01:54:15 PDT 2009
---
pixman/pixman-arm-neon.c | 23 +++++++----------------
1 files changed, 7 insertions(+), 16 deletions(-)
diff --git a/pixman/pixman-arm-neon.c b/pixman/pixman-arm-neon.c
index 56fb247..51f7d55 100644
--- a/pixman/pixman-arm-neon.c
+++ b/pixman/pixman-arm-neon.c
@@ -33,15 +33,6 @@
#include <arm_neon.h>
-#if !defined(__ARMCC_VERSION) && !defined(FORCE_NO_NEON_INLINE_ASM)
-// [both armcc & gcc set __GNUC__]
-// Use GNU style inline asm on gcc, for best performance
-// Use intrinsics on armcc
-// This switch determines if any GNU style inline asm is allowed
-#define USE_NEON_INLINE_ASM
-#endif
-
-
static force_inline uint8x8x4_t unpack0565(uint16x8_t rgb)
{
uint16x8_t gb, b;
@@ -161,7 +152,7 @@ fbCompositeSrcAdd_8000x8000neon (pixman_op_t op,
uint8_t *keep_dst;
-#ifndef USE_NEON_INLINE_ASM
+#ifndef USE_GCC_INLINE_ASM
uint8x8_t sval,dval,temp;
sval = vld1_u8((void*)src);
@@ -306,7 +297,7 @@ fbCompositeSrc_8888x8888neon (pixman_op_t op,
uint32_t *keep_dst;
-#ifndef USE_NEON_INLINE_ASM
+#ifndef USE_GCC_INLINE_ASM
uint8x8x4_t sval,dval,temp;
sval = vld4_u8((void*)src);
@@ -467,7 +458,7 @@ fbCompositeSrc_x888x0565neon (pixman_op_t op,
do {
while (w>=8)
{
-#ifndef USE_NEON_INLINE_ASM
+#ifndef USE_GCC_INLINE_ASM
vst1q_u16(dst, pack0565(vld4_u8((void*)src)));
#else
asm volatile (
@@ -577,7 +568,7 @@ fbCompositeSrc_8888x8x8888neon (pixman_op_t op,
uint32_t *keep_dst;
-#ifndef USE_NEON_INLINE_ASM
+#ifndef USE_GCC_INLINE_ASM
uint8x8x4_t sval,dval,temp;
sval = vld4_u8((void*)src);
@@ -783,7 +774,7 @@ fbCompositeSolidMask_nx8x0565neon (pixman_op_t op,
maskLine += maskStride;
w = width;
-#ifndef USE_NEON_INLINE_ASM
+#ifndef USE_GCC_INLINE_ASM
uint8x8_t alpha;
uint16x8_t dval, temp;
uint8x8x4_t sval8temp;
@@ -920,7 +911,7 @@ fbCompositeSolidMask_nx8x0565neon (pixman_op_t op,
w = width;
-#ifndef USE_NEON_INLINE_ASM
+#ifndef USE_GCC_INLINE_ASM
uint8x8_t alpha;
uint16x8_t dval, temp;
uint8x8x4_t sval8temp;
@@ -1118,7 +1109,7 @@ fbCompositeSolidMask_nx8x8888neon (pixman_op_t op,
maskLine += maskStride;
w = width;
-#ifndef USE_NEON_INLINE_ASM
+#ifndef USE_GCC_INLINE_ASM
uint8x8_t alpha;
uint8x8x4_t dval, temp;
--
1.5.6.3
--=-VQiE51CRN9Xfgo9Uw6rE
Content-Disposition: attachment; filename="0002-Add-some-NEON-blitters-for-16-bit-framebuffers.patch"
Content-Type: text/x-patch; name="0002-Add-some-NEON-blitters-for-16-bit-framebuffers.patch"; charset="UTF-8"
Content-Transfer-Encoding: 8bit
More information about the cairo
mailing list