[V5,1/2] tests/cvl_advanced_rss_gtpogre: add case parse_pfcp_over_gre_packet
Commit Message
Signed-off-by: Xiang An <xiangx.an@intel.com>
---
tests/TestSuite_cvl_advanced_rss_gtpogre.py | 55 +++++++++++++++++++++++++++++
1 file changed, 55 insertions(+)
Comments
> -----Original Message-----
> From: dts <dts-bounces@dpdk.org> On Behalf Of Xiang An
> Sent: 2021年6月7日 14:31
> To: dts@dpdk.org
> Cc: Peng, Yuan <yuan.peng@intel.com>; An, XiangX <xiangx.an@intel.com>
> Subject: [dts] [PATCH V5 1/2] tests/cvl_advanced_rss_gtpogre: add case
> parse_pfcp_over_gre_packet
>
> Signed-off-by: Xiang An <xiangx.an@intel.com>
> ---
> tests/TestSuite_cvl_advanced_rss_gtpogre.py | 55
> +++++++++++++++++++++++++++++
> 1 file changed, 55 insertions(+)
>
> diff --git a/tests/TestSuite_cvl_advanced_rss_gtpogre.py
> b/tests/TestSuite_cvl_advanced_rss_gtpogre.py
> index 4a889ea..17029a8 100755
> --- a/tests/TestSuite_cvl_advanced_rss_gtpogre.py
> +++ b/tests/TestSuite_cvl_advanced_rss_gtpogre.py
> @@ -3503,7 +3503,62 @@ class TestCVLAdvancedRSSGTPoGRE(TestCase):
> self.switch_testpmd(enable_rss=True)
>
> self.rssprocess.handle_rss_distribute_cases(cases_info=inner_l4_protocal_hash)
>
> + def change_dpdk_code(self):
> + """
> + change dpdk's code to show the PFCP ptype
> + """
> + file1 = "drivers/net/ice/ice_rxtx.c"
> + file2 = "drivers/net/ice/ice_rxtx_vec_avx2.c"
> + match1 = "rte_le_to_cpu_16(rxdp\[j\].wb.ptype_flex_flags0)\];"
> + match2 = "const uint16_t ptype0 = _mm256_extract_epi16(ptypes0_1, 1);"
> + insert1 = "printf(\"ptype: %d\\\\n\", ICE_RX_FLEX_DESC_PTYPE_M &
> rte_le_to_cpu_16(rxdp\[j\].wb.ptype_flex_flags0));"
> + insert2 = "printf(\"ptype: %d\\\\n\", ptype0);"
> +
> + self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx.c_bak", "# ")
> + self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx.c
> drivers/net/ice/ice_rxtx.c_bak", "# ")
> + self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx_vec_avx2.c_bak", "#
> ")
> + self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx_vec_avx2.c
> drivers/net/ice/ice_rxtx_vec_avx2.c_bak", "# ")
> + self.dut.send_expect("sed -i '/%s/a\%s' %s"%(match1,insert1,file1), "# ")
> + self.dut.send_expect("sed -i '/%s/a\%s' %s"%(match2,insert2,file2), "# ")
Only test avx2 ? does avx512 support it ?it should be considered too.
> +
> + def recovery_dpdk_code(self):
> + """
> + Recovery dpdk's code after the case finished
> + """
> + self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx.c", "# ")
> + self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx.c_bak
> drivers/net/ice/ice_rxtx.c", "# ")
> + self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx_vec_avx2.c", "# ")
> + self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx_vec_avx2.c_bak
> drivers/net/ice/ice_rxtx_vec_avx2.c", "# ")
> +
> + def test_parse_pfcp_over_gre_packet(self):
> + self.pmd_output.quit()
> + self.change_dpdk_code()
> + self.dut.build_install_dpdk(self.dut.target)
> +
> + pkt1 =
> 'Ether(dst="00:11:22:33:44:55")/IP(proto=0x2F)/GRE(proto=0x0800)/IP()/UDP(sp
> ort=22, dport=8805)/PFCP(S=0)'
> + pkt2 =
> 'Ether(dst="00:11:22:33:44:55")/IP(proto=0x2F)/GRE(proto=0x0800)/IP()/UDP(sp
> ort=22, dport=8805)/PFCP(S=1, seid=123)'
> + pkt3 =
> 'Ether(dst="00:11:22:33:44:55")/IPv6(nh=0x2F)/GRE(proto=0x86dd)/IPv6()/UDP(
> sport=22, dport=8805)/PFCP(S=0)'
> + pkt4 =
> 'Ether(dst="00:11:22:33:44:55")/IPv6(nh=0x2F)/GRE(proto=0x86dd)/IPv6()/UDP(
> sport=22, dport=8805)/PFCP(S=1, seid=256)'
> + pkts = [pkt1, pkt2, pkt3, pkt4]
> + p = Packet()
> + for i in pkts:
> + p.append_pkt(i)
> + self.switch_testpmd(enable_rss=True)
> + p.send_pkt(self.tester, tx_port=self.tester_iface0)
> + out = self.pmd_output.get_output(timeout=1)
> +
> + self.verify('ptype: 351' in out,'some subcase failed')
> + self.verify('ptype: 352' in out,'some subcase failed')
> + self.verify('ptype: 353' in out,'some subcase failed')
> + self.verify('ptype: 354' in out,'some subcase failed')
> +
> def tear_down(self):
> + #Judge the currently running case
> + if self.running_case == "test_parse_pfcp_over_gre_packet" :
> + self.pmd_output.quit()
> + self.recovery_dpdk_code()
> + self.dut.build_install_dpdk(self.dut.target)
> + self.switch_testpmd(enable_rss=False)
> # destroy all flow rule on port 0
> self.dut.send_command("flow flush 0", timeout=1)
> self.dut.send_command("clear port stats all", timeout=1)
> --
> 1.8.3.1
@@ -3503,7 +3503,62 @@ class TestCVLAdvancedRSSGTPoGRE(TestCase):
self.switch_testpmd(enable_rss=True)
self.rssprocess.handle_rss_distribute_cases(cases_info=inner_l4_protocal_hash)
+ def change_dpdk_code(self):
+ """
+ change dpdk's code to show the PFCP ptype
+ """
+ file1 = "drivers/net/ice/ice_rxtx.c"
+ file2 = "drivers/net/ice/ice_rxtx_vec_avx2.c"
+ match1 = "rte_le_to_cpu_16(rxdp\[j\].wb.ptype_flex_flags0)\];"
+ match2 = "const uint16_t ptype0 = _mm256_extract_epi16(ptypes0_1, 1);"
+ insert1 = "printf(\"ptype: %d\\\\n\", ICE_RX_FLEX_DESC_PTYPE_M & rte_le_to_cpu_16(rxdp\[j\].wb.ptype_flex_flags0));"
+ insert2 = "printf(\"ptype: %d\\\\n\", ptype0);"
+
+ self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx.c_bak", "# ")
+ self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx.c drivers/net/ice/ice_rxtx.c_bak", "# ")
+ self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx_vec_avx2.c_bak", "# ")
+ self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx_vec_avx2.c drivers/net/ice/ice_rxtx_vec_avx2.c_bak", "# ")
+ self.dut.send_expect("sed -i '/%s/a\%s' %s"%(match1,insert1,file1), "# ")
+ self.dut.send_expect("sed -i '/%s/a\%s' %s"%(match2,insert2,file2), "# ")
+
+ def recovery_dpdk_code(self):
+ """
+ Recovery dpdk's code after the case finished
+ """
+ self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx.c", "# ")
+ self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx.c_bak drivers/net/ice/ice_rxtx.c", "# ")
+ self.dut.send_expect("rm -rf drivers/net/ice/ice_rxtx_vec_avx2.c", "# ")
+ self.dut.send_expect("cp -rf drivers/net/ice/ice_rxtx_vec_avx2.c_bak drivers/net/ice/ice_rxtx_vec_avx2.c", "# ")
+
+ def test_parse_pfcp_over_gre_packet(self):
+ self.pmd_output.quit()
+ self.change_dpdk_code()
+ self.dut.build_install_dpdk(self.dut.target)
+
+ pkt1 = 'Ether(dst="00:11:22:33:44:55")/IP(proto=0x2F)/GRE(proto=0x0800)/IP()/UDP(sport=22, dport=8805)/PFCP(S=0)'
+ pkt2 = 'Ether(dst="00:11:22:33:44:55")/IP(proto=0x2F)/GRE(proto=0x0800)/IP()/UDP(sport=22, dport=8805)/PFCP(S=1, seid=123)'
+ pkt3 = 'Ether(dst="00:11:22:33:44:55")/IPv6(nh=0x2F)/GRE(proto=0x86dd)/IPv6()/UDP(sport=22, dport=8805)/PFCP(S=0)'
+ pkt4 = 'Ether(dst="00:11:22:33:44:55")/IPv6(nh=0x2F)/GRE(proto=0x86dd)/IPv6()/UDP(sport=22, dport=8805)/PFCP(S=1, seid=256)'
+ pkts = [pkt1, pkt2, pkt3, pkt4]
+ p = Packet()
+ for i in pkts:
+ p.append_pkt(i)
+ self.switch_testpmd(enable_rss=True)
+ p.send_pkt(self.tester, tx_port=self.tester_iface0)
+ out = self.pmd_output.get_output(timeout=1)
+
+ self.verify('ptype: 351' in out,'some subcase failed')
+ self.verify('ptype: 352' in out,'some subcase failed')
+ self.verify('ptype: 353' in out,'some subcase failed')
+ self.verify('ptype: 354' in out,'some subcase failed')
+
def tear_down(self):
+ #Judge the currently running case
+ if self.running_case == "test_parse_pfcp_over_gre_packet" :
+ self.pmd_output.quit()
+ self.recovery_dpdk_code()
+ self.dut.build_install_dpdk(self.dut.target)
+ self.switch_testpmd(enable_rss=False)
# destroy all flow rule on port 0
self.dut.send_command("flow flush 0", timeout=1)
self.dut.send_command("clear port stats all", timeout=1)