DPDK patches and discussions
 help / color / mirror / Atom feed
* [dpdk-dev]  [PATCH] sched: enable neon optimizations
@ 2017-04-27 13:00 Ashwin Sekhar T K
  2017-04-28  3:50 ` Jianbo Liu
  2017-04-28  6:15 ` [dpdk-dev] [PATCH v2] sched: add " Ashwin Sekhar T K
  0 siblings, 2 replies; 8+ messages in thread
From: Ashwin Sekhar T K @ 2017-04-27 13:00 UTC (permalink / raw)
  To: thomas, cristian.dumitrescu, jerin.jacob, jianbo.liu
  Cc: dev, Ashwin Sekhar T K

* Enabled CONFIG_RTE_SCHED_VECTOR for arm64
* Verified the changes with sched_autotest unit test case

Signed-off-by: Ashwin Sekhar T K <ashwin.sekhar@caviumnetworks.com>
---
 config/defconfig_arm64-armv8a-linuxapp-gcc |  2 +-
 lib/librte_sched/rte_sched.c               | 22 ++++++++++++++++++++++
 2 files changed, 23 insertions(+), 1 deletion(-)

diff --git a/config/defconfig_arm64-armv8a-linuxapp-gcc b/config/defconfig_arm64-armv8a-linuxapp-gcc
index 65888ce..021044a 100644
--- a/config/defconfig_arm64-armv8a-linuxapp-gcc
+++ b/config/defconfig_arm64-armv8a-linuxapp-gcc
@@ -48,4 +48,4 @@ CONFIG_RTE_LIBRTE_FM10K_PMD=n
 CONFIG_RTE_LIBRTE_SFC_EFX_PMD=n
 CONFIG_RTE_LIBRTE_AVP_PMD=n
 
-CONFIG_RTE_SCHED_VECTOR=n
+CONFIG_RTE_SCHED_VECTOR=y
diff --git a/lib/librte_sched/rte_sched.c b/lib/librte_sched/rte_sched.c
index 614705d..4ba476a 100644
--- a/lib/librte_sched/rte_sched.c
+++ b/lib/librte_sched/rte_sched.c
@@ -58,6 +58,8 @@
 
 #if defined(__SSE4__)
 #define SCHED_VECTOR_SSE4
+#elif defined(RTE_MACHINE_CPUFLAG_NEON)
+#define SCHED_VECTOR_NEON
 #endif
 
 #endif
@@ -1732,6 +1734,26 @@ grinder_pipe_exists(struct rte_sched_port *port, uint32_t base_pipe)
 	return 1;
 }
 
+#elif defined(SCHED_VECTOR_NEON)
+
+static inline int
+grinder_pipe_exists(struct rte_sched_port *port, uint32_t base_pipe)
+{
+	uint32x4_t index, pipes;
+	uint32_t *pos = (uint32_t *)port->grinder_base_bmp_pos;
+
+	index = vmovq_n_u32(base_pipe);
+	pipes = vld1q_u32(pos);
+	if (!vminvq_u32(veorq_u32(pipes, index)))
+		return 1;
+
+	pipes = vld1q_u32(pos + 4);
+	if (!vminvq_u32(veorq_u32(pipes, index)))
+		return 1;
+
+	return 0;
+}
+
 #else
 
 static inline int
-- 
2.7.4

^ permalink raw reply	[flat|nested] 8+ messages in thread

end of thread, other threads:[~2017-07-03 13:15 UTC | newest]

Thread overview: 8+ messages (download: mbox.gz / follow: Atom feed)
-- links below jump to the message on this page --
2017-04-27 13:00 [dpdk-dev] [PATCH] sched: enable neon optimizations Ashwin Sekhar T K
2017-04-28  3:50 ` Jianbo Liu
2017-04-28  5:27   ` Sekhar, Ashwin
2017-04-28  5:37     ` Jianbo Liu
2017-04-28  6:03       ` Sekhar, Ashwin
2017-04-28  6:15 ` [dpdk-dev] [PATCH v2] sched: add " Ashwin Sekhar T K
2017-04-28  8:50   ` Jianbo Liu
2017-07-03 13:15     ` Thomas Monjalon

This is a public inbox, see mirroring instructions
for how to clone and mirror all data and code used for this inbox;
as well as URLs for NNTP newsgroup(s).