From mboxrd@z Thu Jan  1 00:00:00 1970
Return-Path: <viktorin@rehivetech.com>
Received: from wes1-so1.wedos.net (wes1-so1.wedos.net [46.28.106.15])
 by dpdk.org (Postfix) with ESMTP id A2387568F
 for <dev@dpdk.org>; Sat, 19 Mar 2016 20:58:10 +0100 (CET)
Received: from pcviktorin.fit.vutbr.cz (pcviktorin.fit.vutbr.cz
 [147.229.13.147])
 by wes1-so1.wedos.net (Postfix) with ESMTPSA id 3qSCZB348Lz5GS;
 Sat, 19 Mar 2016 20:58:10 +0100 (CET)
From: Jan Viktorin <viktorin@rehivetech.com>
To: dev@dpdk.org
Cc: Jan Viktorin <viktorin@rehivetech.com>, thomas.monjalon@6wind.com,
 jerin.jacob@caviumnetworks.com, tomaszx.kulasek@intel.com,
 jianbo.liu@linaro.org
Date: Sat, 19 Mar 2016 20:58:03 +0100
Message-Id: <1458417485-29436-3-git-send-email-viktorin@rehivetech.com>
X-Mailer: git-send-email 2.7.0
In-Reply-To: <1458417485-29436-1-git-send-email-viktorin@rehivetech.com>
References: <1458417485-29436-1-git-send-email-viktorin@rehivetech.com>
In-Reply-To: <1458379590-18618-1-git-send-email-viktorin@rehivetech.com>
References: <1458379590-18618-1-git-send-email-viktorin@rehivetech.com>
Subject: [dpdk-dev] [PATCH v3 2/4] arm: detect NEON cpu feature by checking
	__ARM_NEON
X-BeenThere: dev@dpdk.org
X-Mailman-Version: 2.1.15
Precedence: list
List-Id: patches and discussions about DPDK <dev.dpdk.org>
List-Unsubscribe: <http://dpdk.org/ml/options/dev>,
 <mailto:dev-request@dpdk.org?subject=unsubscribe>
List-Archive: <http://dpdk.org/ml/archives/dev/>
List-Post: <mailto:dev@dpdk.org>
List-Help: <mailto:dev-request@dpdk.org?subject=help>
List-Subscribe: <http://dpdk.org/ml/listinfo/dev>,
 <mailto:dev-request@dpdk.org?subject=subscribe>
X-List-Received-Date: Sat, 19 Mar 2016 19:58:10 -0000

The __ARM_NEON declares that the arm_neon.h is available which is not true for
the __ARM_NEON_FP. The __ARM_NEON_FP is not provided by aarch64 gcc.

 $ arm-linux-gnueabi-gcc -dM -E - < /dev/null  | grep "_FP\|_NEON"
 #define __ARM_FP 12
 #define __ARM_NEON_FP 4
 #define __VFP_FP__ 1

 $ arm-linux-gnueabi-gcc -mfpu=neon -dM -E - < /dev/null  | grep "_FP\|_NEON"
 #define __ARM_FP 12
 #define __ARM_NEON_FP 4
 #define __ARM_NEON__ 1
 #define __VFP_FP__ 1
 #define __ARM_NEON 1

 $ aarch64-linux-gnu-gcc -dM -E - < /dev/null | grep "NEON\|FP"
 #define __FP_FAST_FMAF 1
 #define __ARM_NEON 1
 #define __FP_FAST_FMA 1

Signed-off-by: Jan Viktorin <viktorin@rehivetech.com>
---
 mk/rte.cpuflags.mk | 2 +-
 1 file changed, 1 insertion(+), 1 deletion(-)

diff --git a/mk/rte.cpuflags.mk b/mk/rte.cpuflags.mk
index 19a3e7e..529bcef 100644
--- a/mk/rte.cpuflags.mk
+++ b/mk/rte.cpuflags.mk
@@ -111,7 +111,7 @@ CPUFLAGS += VSX
 endif
 
 # ARM flags
-ifneq ($(filter $(AUTO_CPUFLAGS),__ARM_NEON_FP),)
+ifneq ($(filter $(AUTO_CPUFLAGS),__ARM_NEON),)
 CPUFLAGS += NEON
 endif
 
-- 
2.7.0