Home
last modified time | relevance | path

Searched refs:cmp (Results 1 – 25 of 34) sorted by relevance

12

/dpdk/drivers/net/bnxt/
H A Dbnxt_rxr.h10 #define BNXT_TPA_START_AGG_ID_PRE_TH(cmp) \ argument
14 #define BNXT_TPA_START_AGG_ID_TH(cmp) \ argument
15 rte_le_to_cpu_16((cmp)->agg_id)
18 struct rx_tpa_start_cmpl *cmp) in bnxt_tpa_start_agg_id() argument
21 return BNXT_TPA_START_AGG_ID_TH(cmp); in bnxt_tpa_start_agg_id()
26 #define BNXT_TPA_END_AGG_BUFS(cmp) \ argument
31 ((cmp)->tpa_agg_bufs)
33 #define BNXT_TPA_END_AGG_ID(cmp) \ argument
37 #define BNXT_TPA_END_AGG_ID_TH(cmp) \ argument
38 rte_le_to_cpu_16((cmp)->agg_id)
[all …]
H A Dbnxt_cpr.h15 #define CMP_TYPE(cmp) \ argument
16 (((struct cmpl_base *)cmp)->type & CMPL_BASE_TYPE_MASK)
97 void bnxt_handle_async_event(struct bnxt *bp, struct cmpl_base *cmp);
98 void bnxt_handle_fwd_req(struct bnxt *bp, struct cmpl_base *cmp);
99 int bnxt_event_hwrm_resp_handler(struct bnxt *bp, struct cmpl_base *cmp);
H A Dbnxt_cpr.c134 struct cmpl_base *cmp) in bnxt_handle_async_event() argument
137 (struct hwrm_async_event_cmpl *)cmp; in bnxt_handle_async_event()
358 int bnxt_event_hwrm_resp_handler(struct bnxt *bp, struct cmpl_base *cmp) in bnxt_event_hwrm_resp_handler() argument
362 if (bp == NULL || cmp == NULL) { in bnxt_event_hwrm_resp_handler()
370 switch (CMP_TYPE(cmp)) { in bnxt_event_hwrm_resp_handler()
373 bnxt_handle_async_event(bp, cmp); in bnxt_event_hwrm_resp_handler()
378 bnxt_handle_fwd_req(bp, cmp); in bnxt_event_hwrm_resp_handler()
383 PMD_DRV_LOG(DEBUG, "Ignoring %02x completion\n", CMP_TYPE(cmp)); in bnxt_event_hwrm_resp_handler()
H A Dbnxt_irq.c26 struct cmpl_base *cmp; in bnxt_int_handler() local
50 cmp = &cpr->cp_desc_ring[cons]; in bnxt_int_handler()
52 if (!bnxt_cpr_cmp_valid(cmp, raw_cons, cp_ring_size)) in bnxt_int_handler()
55 bnxt_event_hwrm_resp_handler(bp, cmp); in bnxt_int_handler()
/dpdk/lib/gro/
H A Dgro_vxlan_udp4.c210 int cmp; in udp4_check_vxlan_neighbor() local
225 if (cmp > 0) in udp4_check_vxlan_neighbor()
228 else if (cmp < 0) in udp4_check_vxlan_neighbor()
238 int cmp, in merge_two_vxlan_udp4_packets() argument
301 int cmp; in gro_vxlan_udp4_reassemble() local
397 cmp = udp4_check_vxlan_neighbor(&(tbl->items[cur_idx]), in gro_vxlan_udp4_reassemble()
399 if (cmp) { in gro_vxlan_udp4_reassemble()
402 pkt, cmp, frag_offset, in gro_vxlan_udp4_reassemble()
456 int cmp; in gro_vxlan_udp4_merge_items() local
470 if (cmp) { in gro_vxlan_udp4_merge_items()
[all …]
H A Dgro_vxlan_tcp4.c220 int cmp; in check_vxlan_seq_option() local
228 cmp = check_seq_option(&item->inner_item, tcp_hdr, sent_seq, ip_id, in check_vxlan_seq_option()
230 if ((cmp > 0) && (outer_is_atomic || in check_vxlan_seq_option()
234 else if ((cmp < 0) && (outer_is_atomic || in check_vxlan_seq_option()
246 int cmp, in merge_two_vxlan_tcp4_packets() argument
251 if (merge_two_tcp4_packets(&item->inner_item, pkt, cmp, sent_seq, in merge_two_vxlan_tcp4_packets()
255 item->outer_ip_id = cmp > 0 ? outer_ip_id : item->outer_ip_id; in merge_two_vxlan_tcp4_packets()
305 int cmp; in gro_vxlan_tcp4_reassemble() local
417 cmp = check_vxlan_seq_option(&(tbl->items[cur_idx]), tcp_hdr, in gro_vxlan_tcp4_reassemble()
420 if (cmp) { in gro_vxlan_tcp4_reassemble()
[all …]
H A Dgro_udp4.c210 int cmp; in gro_udp4_reassemble() local
289 cmp = udp4_check_neighbor(&(tbl->items[cur_idx]), in gro_udp4_reassemble()
291 if (cmp) { in gro_udp4_reassemble()
293 pkt, cmp, frag_offset, in gro_udp4_reassemble()
346 int cmp; in gro_udp4_merge_items() local
357 cmp = udp4_check_neighbor(&(tbl->items[start_idx]), in gro_udp4_merge_items()
359 if (cmp) { in gro_udp4_merge_items()
362 pkt, cmp, frag_offset, in gro_udp4_merge_items()
H A Dgro_udp4.h195 int cmp, in merge_two_udp4_packets() argument
204 if (cmp > 0) { in merge_two_udp4_packets()
224 if (cmp > 0) { in merge_two_udp4_packets()
H A Dgro_tcp4.h207 int cmp, in merge_two_tcp4_packets() argument
215 if (cmp > 0) { in merge_two_tcp4_packets()
235 if (cmp > 0) { in merge_two_tcp4_packets()
H A Dgro_tcp4.c207 int cmp; in gro_tcp4_reassemble() local
296 cmp = check_seq_option(&(tbl->items[cur_idx]), tcp_hdr, in gro_tcp4_reassemble()
299 if (cmp) { in gro_tcp4_reassemble()
301 pkt, cmp, sent_seq, ip_id, 0)) in gro_tcp4_reassemble()
/dpdk/drivers/common/cnxk/
H A Droc_npa.h230 } cmp; in roc_npa_aura_batch_alloc_issue() local
241 cmp.u = 0; in roc_npa_aura_batch_alloc_issue()
242 cmp.compare_s.aura = roc_npa_aura_handle_to_aura(aura_handle); in roc_npa_aura_batch_alloc_issue()
243 cmp.compare_s.drop = drop; in roc_npa_aura_batch_alloc_issue()
244 cmp.compare_s.stype = ALLOC_STYPE_STF; in roc_npa_aura_batch_alloc_issue()
245 cmp.compare_s.dis_wait = dis_wait; in roc_npa_aura_batch_alloc_issue()
246 cmp.compare_s.count = num; in roc_npa_aura_batch_alloc_issue()
248 res = roc_atomic64_casl(cmp.u, (uint64_t)buf, addr); in roc_npa_aura_batch_alloc_issue()
/dpdk/drivers/net/virtio/
H A Dvirtio_rxtx_packed_avx.h28 uint16_t i, cmp; in virtqueue_enqueue_batch_packed_vec() local
50 cmp = _mm256_mask_cmpneq_epu16_mask(mask, mbufs, mbuf_ref); in virtqueue_enqueue_batch_packed_vec()
51 if (unlikely(cmp)) in virtqueue_enqueue_batch_packed_vec()
58 cmp = _mm256_mask_cmplt_epu16_mask(data_mask, mbufs, head_rooms); in virtqueue_enqueue_batch_packed_vec()
59 if (unlikely(cmp)) in virtqueue_enqueue_batch_packed_vec()
/dpdk/lib/eal/common/
H A Deal_common_class.c33 rte_class_find(const struct rte_class *start, rte_class_cmp_t cmp, in rte_class_find() argument
43 if (cmp(cls, data) == 0) in rte_class_find()
H A Deal_common_bus.c121 rte_bus_find(const struct rte_bus *start, rte_bus_cmp_t cmp, in rte_bus_find() argument
131 if (cmp(bus, data) == 0) in rte_bus_find()
/dpdk/lib/eal/include/
H A Drte_bus.h92 (*rte_bus_find_device_t)(const struct rte_device *start, rte_dev_cmp_t cmp,
367 struct rte_bus *rte_bus_find(const struct rte_bus *start, rte_bus_cmp_t cmp,
H A Drte_class.h80 rte_class_find(const struct rte_class *start, rte_class_cmp_t cmp,
/dpdk/drivers/raw/ioat/
H A Didxd_bus.c44 rte_dev_cmp_t cmp, const void *data);
324 dsa_find_device(const struct rte_device *start, rte_dev_cmp_t cmp, in dsa_find_device() argument
335 if (cmp(&dev->device, data) == 0) in dsa_find_device()
/dpdk/drivers/bus/vdev/
H A Dvdev_private.h16 rte_dev_cmp_t cmp,
/dpdk/drivers/dma/idxd/
H A Didxd_bus.c46 rte_dev_cmp_t cmp, const void *data);
356 dsa_find_device(const struct rte_device *start, rte_dev_cmp_t cmp, in dsa_find_device() argument
367 if (cmp(&dev->device, data) == 0) in dsa_find_device()
/dpdk/drivers/bus/vmbus/
H A Dvmbus_common.c273 vmbus_find_device(const struct rte_device *start, rte_dev_cmp_t cmp, in vmbus_find_device() argument
283 if (cmp(&dev->device, data) == 0) in vmbus_find_device()
/dpdk/lib/ethdev/
H A Dethdev_private.h51 eth_find_device(const struct rte_eth_dev *_start, rte_eth_cmp_t cmp,
/dpdk/drivers/bus/auxiliary/
H A Dauxiliary_common.c296 auxiliary_find_device(const struct rte_device *start, rte_dev_cmp_t cmp, in auxiliary_find_device() argument
309 if (cmp(&adev->device, data) == 0) in auxiliary_find_device()
/dpdk/lib/vhost/
H A Dvdpa.c312 vdpa_find_device(const struct rte_vdpa_device *start, rte_vdpa_cmp_t cmp, in vdpa_find_device() argument
324 if (cmp(dev, rte_dev) == 0) in vdpa_find_device()
/dpdk/lib/compressdev/
H A Drte_compressdev.c153 int cmp; in rte_compressdev_devices_get() local
155 cmp = strncmp(devs[i].device->driver->name, in rte_compressdev_devices_get()
159 if (cmp == 0) in rte_compressdev_devices_get()
/dpdk/drivers/bus/ifpga/
H A Difpga_bus.c411 rte_dev_cmp_t cmp, const void *data) in ifpga_find_device() argument
420 if (cmp(&afu_dev->device, data) == 0) in ifpga_find_device()

12