Home
last modified time | relevance | path

Searched refs:csum_flags (Results 1 – 25 of 73) sorted by relevance

123

/f-stack/freebsd/netgraph/
H A Dng_checksum.c328 if (m->m_pkthdr.csum_flags & CSUM_IP) { in checksum_ipv4()
337 m->m_pkthdr.csum_flags &= ~CSUM_IP; in checksum_ipv4()
354 if (m->m_pkthdr.csum_flags & CSUM_TCP) { in checksum_ipv4()
365 m->m_pkthdr.csum_flags &= ~CSUM_TCP; in checksum_ipv4()
371 m->m_pkthdr.csum_flags &= ~CSUM_UDP; in checksum_ipv4()
375 if (m->m_pkthdr.csum_flags & CSUM_UDP) { in checksum_ipv4()
391 m->m_pkthdr.csum_flags &= ~CSUM_UDP; in checksum_ipv4()
397 m->m_pkthdr.csum_flags &= ~CSUM_TCP; in checksum_ipv4()
569 m->m_pkthdr.csum_flags |= priv->conf->csum_flags; in ng_checksum_rcvdata()
624 m->m_pkthdr.csum_flags &= in ng_checksum_rcvdata()
[all …]
H A Dng_checksum.h73 uint64_t csum_flags; member
H A Dng_patch.h116 uint64_t csum_flags; member
/f-stack/freebsd/netinet/
H A Dip_output.c151 m->m_pkthdr.csum_flags |= in ip_output_pfil()
155 m->m_pkthdr.csum_flags |= in ip_output_pfil()
184 m->m_pkthdr.csum_flags |= in ip_output_pfil()
189 if (m->m_pkthdr.csum_flags & CSUM_SCTP) in ip_output_pfil()
192 m->m_pkthdr.csum_flags |= in ip_output_pfil()
739 m->m_pkthdr.csum_flags |= CSUM_IP; in ip_output()
783 m->m_pkthdr.csum_flags &= ~CSUM_IP; in ip_output()
793 if (m->m_pkthdr.csum_flags & in ip_output()
1032 m->m_pkthdr.csum_flags &= ~CSUM_IP; in ip_fragment()
1050 m0->m_pkthdr.csum_flags &= ~CSUM_IP; in ip_fragment()
[all …]
H A Dip_divert.c214 if (m->m_pkthdr.csum_flags & CSUM_DELAY_DATA) { in divert_packet()
216 m->m_pkthdr.csum_flags &= ~CSUM_DELAY_DATA; in divert_packet()
219 if (m->m_pkthdr.csum_flags & CSUM_SCTP) { in divert_packet()
221 m->m_pkthdr.csum_flags &= ~CSUM_SCTP; in divert_packet()
H A Dtcp_lro.c403 int csum_flags; in tcp_lro_rx_ipv4() local
418 csum_flags = m->m_pkthdr.csum_flags; in tcp_lro_rx_ipv4()
419 if (csum_flags & CSUM_IP_CHECKED) { in tcp_lro_rx_ipv4()
420 if (__predict_false((csum_flags & CSUM_IP_VALID) == 0)) { in tcp_lro_rx_ipv4()
499 le->m_head->m_pkthdr.csum_flags = CSUM_DATA_VALID | in tcp_flush_out_le()
524 le->m_head->m_pkthdr.csum_flags = CSUM_DATA_VALID | in tcp_flush_out_le()
1425 if (__predict_false(mb->m_pkthdr.csum_flags == 0 || in tcp_lro_queue_mbuf()
H A Dip_reass.c387 m->m_pkthdr.csum_flags = 0; in ip_reass()
410 q->m_pkthdr.csum_flags = 0; in ip_reass()
470 m->m_pkthdr.csum_flags &= q->m_pkthdr.csum_flags; in ip_reass()
/f-stack/freebsd/net/
H A Dif_infiniband.c149 int csum_flags = 0; in update_mbuf_csumflags() local
151 if (src->m_pkthdr.csum_flags & CSUM_IP) in update_mbuf_csumflags()
152 csum_flags |= (CSUM_IP_CHECKED|CSUM_IP_VALID); in update_mbuf_csumflags()
153 if (src->m_pkthdr.csum_flags & CSUM_DELAY_DATA) in update_mbuf_csumflags()
154 csum_flags |= (CSUM_DATA_VALID|CSUM_PSEUDO_HDR); in update_mbuf_csumflags()
155 if (src->m_pkthdr.csum_flags & CSUM_SCTP) in update_mbuf_csumflags()
156 csum_flags |= CSUM_SCTP_VALID; in update_mbuf_csumflags()
157 dst->m_pkthdr.csum_flags |= csum_flags; in update_mbuf_csumflags()
158 if (csum_flags & CSUM_DATA_VALID) in update_mbuf_csumflags()
H A Dif_vxlan.c2532 csum_flags = csum_flags_to_inner_flags(m->m_pkthdr.csum_flags, in vxlan_encap4()
2535 csum_flags) { in vxlan_encap4()
2543 m->m_pkthdr.csum_flags, csum_flags, in vxlan_encap4()
2550 m->m_pkthdr.csum_flags = csum_flags; in vxlan_encap4()
2551 if (csum_flags & in vxlan_encap4()
2644 csum_flags = csum_flags_to_inner_flags(m->m_pkthdr.csum_flags, in vxlan_encap6()
2647 csum_flags) { in vxlan_encap6()
2655 m->m_pkthdr.csum_flags, csum_flags, in vxlan_encap6()
2662 m->m_pkthdr.csum_flags = csum_flags; in vxlan_encap6()
2663 if (csum_flags & in vxlan_encap6()
[all …]
H A Dif_loop.c245 m->m_pkthdr.csum_flags = LO_CSUM_SET; in looutput()
247 m->m_pkthdr.csum_flags &= ~LO_CSUM_FEATURES; in looutput()
258 m->m_pkthdr.csum_flags = LO_CSUM_SET; in looutput()
262 m->m_pkthdr.csum_flags = LO_CSUM_SET; in looutput()
264 m->m_pkthdr.csum_flags &= ~LO_CSUM_FEATURES6; in looutput()
H A Dif_ethersubr.c130 int csum_flags = 0; in update_mbuf_csumflags() local
132 if (src->m_pkthdr.csum_flags & CSUM_IP) in update_mbuf_csumflags()
133 csum_flags |= (CSUM_IP_CHECKED|CSUM_IP_VALID); in update_mbuf_csumflags()
134 if (src->m_pkthdr.csum_flags & CSUM_DELAY_DATA) in update_mbuf_csumflags()
135 csum_flags |= (CSUM_DATA_VALID|CSUM_PSEUDO_HDR); in update_mbuf_csumflags()
136 if (src->m_pkthdr.csum_flags & CSUM_SCTP) in update_mbuf_csumflags()
137 csum_flags |= CSUM_SCTP_VALID; in update_mbuf_csumflags()
138 dst->m_pkthdr.csum_flags |= csum_flags; in update_mbuf_csumflags()
139 if (csum_flags & CSUM_DATA_VALID) in update_mbuf_csumflags()
827 MPASS((m->m_pkthdr.csum_flags & CSUM_SND_TAG) == 0); in ether_input()
H A Ddebugnet_inet.c142 if ((m->m_pkthdr.csum_flags & CSUM_IP_CHECKED) != 0) { in debugnet_handle_ip()
143 if ((m->m_pkthdr.csum_flags & CSUM_IP_VALID) == 0) { in debugnet_handle_ip()
198 if ((m->m_pkthdr.csum_flags & CSUM_PSEUDO_HDR) != 0) { in debugnet_handle_ip()
199 if ((m->m_pkthdr.csum_flags & CSUM_DATA_VALID) == 0) { in debugnet_handle_ip()
/f-stack/freebsd/netipsec/
H A Dudpencap.c201 if (m->m_pkthdr.csum_flags & CSUM_DATA_VALID) in udp_ipsec_input()
202 m->m_pkthdr.csum_flags &= ~(CSUM_DATA_VALID | CSUM_PSEUDO_HDR); in udp_ipsec_input()
275 m->m_pkthdr.csum_flags |= (CSUM_DATA_VALID | in udp_ipsec_adjust_cksum()
287 m->m_pkthdr.csum_flags = in udp_ipsec_adjust_cksum()
291 m->m_pkthdr.csum_flags &= ~CSUM_DELAY_DATA; in udp_ipsec_adjust_cksum()
H A Dipsec_output.c325 if (m->m_pkthdr.csum_flags & CSUM_DELAY_DATA) { in ipsec4_common_output()
333 m->m_pkthdr.csum_flags &= ~CSUM_DELAY_DATA; in ipsec4_common_output()
336 if (m->m_pkthdr.csum_flags & CSUM_SCTP) { in ipsec4_common_output()
347 m->m_pkthdr.csum_flags &= ~CSUM_SCTP; in ipsec4_common_output()
632 if (m->m_pkthdr.csum_flags & CSUM_DELAY_DATA_IPV6) { in ipsec6_common_output()
641 m->m_pkthdr.csum_flags &= ~CSUM_DELAY_DATA_IPV6; in ipsec6_common_output()
644 if (m->m_pkthdr.csum_flags & CSUM_SCTP_IPV6) { in ipsec6_common_output()
652 m->m_pkthdr.csum_flags &= ~CSUM_SCTP_IPV6; in ipsec6_common_output()
/f-stack/freebsd/netinet6/
H A Dip6_forward.c342 if (m->m_pkthdr.csum_flags & CSUM_DELAY_DATA_IPV6) { in ip6_forward()
343 m->m_pkthdr.csum_flags |= in ip6_forward()
348 if (m->m_pkthdr.csum_flags & CSUM_SCTP_IPV6) in ip6_forward()
349 m->m_pkthdr.csum_flags |= CSUM_SCTP_VALID; in ip6_forward()
H A Dip6_output.c224 if ((csum_flags & CSUM_DELAY_DATA_IPV6) || in ip6_output_delayed_csum()
226 (csum_flags & CSUM_SCTP_IPV6) || in ip6_output_delayed_csum()
237 if (csum_flags & CSUM_DELAY_DATA_IPV6) { in ip6_output_delayed_csum()
243 if (csum_flags & CSUM_SCTP_IPV6) { in ip6_output_delayed_csum()
245 m->m_pkthdr.csum_flags &= ~CSUM_SCTP_IPV6; in ip6_output_delayed_csum()
385 m->m_pkthdr.csum_flags |= CSUM_SND_TAG; in ip6_output_send()
1047 m->m_pkthdr.csum_flags |= in ip6_output()
1053 m->m_pkthdr.csum_flags |= CSUM_SCTP_VALID; in ip6_output()
1079 m->m_pkthdr.csum_flags |= in ip6_output()
1085 m->m_pkthdr.csum_flags |= CSUM_SCTP_VALID; in ip6_output()
[all …]
/f-stack/freebsd/mips/cavium/octe/
H A Dethernet-rx.c290 m->m_pkthdr.csum_flags = 0; /* XXX */ in cvm_oct_tasklet_rx()
292 m->m_pkthdr.csum_flags = CSUM_IP_CHECKED | CSUM_IP_VALID | CSUM_DATA_VALID | CSUM_PSEUDO_HDR; in cvm_oct_tasklet_rx()
296 m->m_pkthdr.csum_flags = 0; /* XXX */ in cvm_oct_tasklet_rx()
/f-stack/lib/
H A Dff_veth.c211 if (mb->m_pkthdr.csum_flags & CSUM_IP) { in ff_mbuf_tx_offload()
215 if (mb->m_pkthdr.csum_flags & CSUM_TCP) { in ff_mbuf_tx_offload()
219 if (mb->m_pkthdr.csum_flags & CSUM_UDP) { in ff_mbuf_tx_offload()
223 if (mb->m_pkthdr.csum_flags & CSUM_SCTP) { in ff_mbuf_tx_offload()
227 if (mb->m_pkthdr.csum_flags & CSUM_TSO) { in ff_mbuf_tx_offload()
324 m->m_pkthdr.csum_flags = CSUM_IP_CHECKED | CSUM_IP_VALID | in ff_mbuf_gethdr()
/f-stack/dpdk/drivers/net/ionic/
H A Dionic_rxtx.c792 if (cq_desc->csum_flags & IONIC_RXQ_COMP_CSUM_F_VLAN) { in ionic_rx_clean()
798 if (cq_desc->csum_flags & IONIC_RXQ_COMP_CSUM_F_CALC) { in ionic_rx_clean()
799 if (cq_desc->csum_flags & IONIC_RXQ_COMP_CSUM_F_IP_OK) in ionic_rx_clean()
801 else if (cq_desc->csum_flags & IONIC_RXQ_COMP_CSUM_F_IP_BAD) in ionic_rx_clean()
804 if ((cq_desc->csum_flags & IONIC_RXQ_COMP_CSUM_F_TCP_OK) || in ionic_rx_clean()
805 (cq_desc->csum_flags & IONIC_RXQ_COMP_CSUM_F_UDP_OK)) in ionic_rx_clean()
807 else if ((cq_desc->csum_flags & in ionic_rx_clean()
809 (cq_desc->csum_flags & in ionic_rx_clean()
/f-stack/tools/compat/include/netgraph/
H A Dng_patch.h83 uint32_t csum_flags; member
/f-stack/dpdk/drivers/net/enic/
H A Denic_rxtx_vec_avx2.c526 __m256i csum_flags = in enic_noscatter_vec_recv_pkts() local
529 csum_flags = _mm256_slli_epi32(csum_flags, 1); in enic_noscatter_vec_recv_pkts()
531 rss_flags = _mm256_or_si256(rss_flags, csum_flags); in enic_noscatter_vec_recv_pkts()
/f-stack/freebsd/arm64/broadcom/genet/
H A Dif_genet.c196 static int gen_parse_tx(struct mbuf *m, int csum_flags);
987 uint32_t csuminfo, length_status, csum_flags = 0, csumdata; in gen_encap() local
1030 csum_flags = m->m_pkthdr.csum_flags; in gen_encap()
1039 offset = gen_parse_tx(m, csum_flags); in gen_encap()
1041 if ((csum_flags & CSUM_DELAY_ANY) != 0) { in gen_encap()
1045 if (csum_flags & (CSUM_UDP | CSUM_IP6_UDP)) in gen_encap()
1107 if ((csum_flags & CSUM_DELAY_ANY) != 0) in gen_encap()
1146 gen_parse_tx(struct mbuf *m, int csum_flags) in gen_parse_tx() argument
1333 m->m_pkthdr.csum_flags = CSUM_DATA_VALID | in gen_rxintr()
/f-stack/freebsd/netinet/tcp_stacks/
H A Drack_bbr_common.c310 if (m->m_pkthdr.csum_flags & CSUM_DATA_VALID_IPV6) { in ctf_process_inbound_raw()
311 if (m->m_pkthdr.csum_flags & CSUM_PSEUDO_HDR) in ctf_process_inbound_raw()
357 if (m->m_pkthdr.csum_flags & CSUM_DATA_VALID) { in ctf_process_inbound_raw()
358 if (m->m_pkthdr.csum_flags & CSUM_PSEUDO_HDR) in ctf_process_inbound_raw()
/f-stack/freebsd/contrib/ipfilter/netinet/
H A Dip_fil_freebsd.c1071 if ((m->m_pkthdr.csum_flags & (CSUM_IP_CHECKED|CSUM_IP_VALID)) ==
1075 …DT2(ipf_fi_bad_checkv4sum_csum_ip_checked, fr_info_t *, fin, u_int, m->m_pkthdr.csum_flags & (CSUM…
1078 if (m->m_pkthdr.csum_flags & CSUM_DATA_VALID) {
1095 if (m->m_pkthdr.csum_flags & CSUM_PSEUDO_HDR)
1111 if (m->m_pkthdr.csum_flags == CSUM_DELAY_DATA) {
1114 } else if (m->m_pkthdr.csum_flags == CSUM_TCP ||
1115 m->m_pkthdr.csum_flags == CSUM_UDP) {
1118 } else if (m->m_pkthdr.csum_flags == CSUM_IP) {
/f-stack/freebsd/arm/allwinner/
H A Dif_awg.c610 u_int csum_flags; in awg_encap() local
655 if ((m->m_pkthdr.csum_flags & CSUM_IP) != 0) { in awg_encap()
656 if ((m->m_pkthdr.csum_flags & (CSUM_TCP|CSUM_UDP)) != 0) in awg_encap()
657 csum_flags = TX_CHECKSUM_CTL_FULL; in awg_encap()
659 csum_flags = TX_CHECKSUM_CTL_IP; in awg_encap()
660 flags |= (csum_flags << TX_CHECKSUM_CTL_SHIFT); in awg_encap()
1237 m->m_pkthdr.csum_flags = CSUM_IP_CHECKED; in awg_rxintr()
1239 m->m_pkthdr.csum_flags |= CSUM_IP_VALID; in awg_rxintr()
1241 m->m_pkthdr.csum_flags |= in awg_rxintr()

123