Home
last modified time | relevance | path

Searched refs:dip (Results 1 – 25 of 26) sorted by relevance

12

/f-stack/dpdk/examples/l3fwd/
H A Dl3fwd_lpm_neon.h18 int32x4_t *dip, in processx4_step1() argument
45 dip[0] = vld1q_s32(dst); in processx4_step1()
54 int32x4_t dip, in processx4_step2() argument
62 dip = vreinterpretq_s32_u8(vrev32q_u8(vreinterpretq_u8_s32(dip))); in processx4_step2()
66 rte_lpm_lookupx4(qconf->ipv4_lookup_struct, dip, dst.u32, in processx4_step2()
71 dst.x = dip; in processx4_step2()
93 int32x4_t dip; in l3fwd_lpm_send_packets() local
111 processx4_step1(&pkts_burst[j], &dip, &ipv4_flag); in l3fwd_lpm_send_packets()
112 processx4_step2(qconf, dip, ipv4_flag, portid, in l3fwd_lpm_send_packets()
116 processx4_step1(&pkts_burst[j], &dip, &ipv4_flag); in l3fwd_lpm_send_packets()
[all …]
H A Dl3fwd_lpm_sse.h15 __m128i *dip, in processx4_step1() argument
42 dip[0] = _mm_set_epi32(x3, x2, x1, x0); in processx4_step1()
51 __m128i dip, in processx4_step2() argument
62 dip = _mm_shuffle_epi8(dip, bswap_mask); in processx4_step2()
66 rte_lpm_lookupx4(qconf->ipv4_lookup_struct, dip, dst.u32, in processx4_step2()
72 dst.x = dip; in processx4_step2()
90 __m128i dip[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets() local
95 processx4_step1(&pkts_burst[j], &dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
99 processx4_step2(qconf, dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
H A Dl3fwd_lpm_altivec.h17 vector unsigned int *dip, in processx4_step1() argument
48 dip[0] = (vector unsigned int){x0, x1, x2, x3}; in processx4_step1()
57 vector unsigned int dip, in processx4_step2() argument
71 dip = (vector unsigned int)vec_perm(*(vector unsigned char *)&dip, in processx4_step2()
76 rte_lpm_lookupx4(qconf->ipv4_lookup_struct, (xmm_t)dip, in processx4_step2()
82 dst.x = (xmm_t)dip; in processx4_step2()
104 vector unsigned int dip[MAX_PKT_BURST / FWDSTEP]; in l3fwd_lpm_send_packets() local
109 processx4_step1(&pkts_burst[j], &dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
113 processx4_step2(qconf, dip[j / FWDSTEP], in l3fwd_lpm_send_packets()
/f-stack/dpdk/lib/librte_node/
H A Dip4_lookup_neon.h26 int32x4_t dip; in ip4_lookup_node_process_vec() local
45 dip = vdupq_n_s32(0); in ip4_lookup_node_process_vec()
81 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 0); in ip4_lookup_node_process_vec()
89 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 1); in ip4_lookup_node_process_vec()
97 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 2); in ip4_lookup_node_process_vec()
105 dip = vsetq_lane_s32(ipv4_hdr->dst_addr, dip, 3); in ip4_lookup_node_process_vec()
107 dip = vreinterpretq_s32_u8( in ip4_lookup_node_process_vec()
108 vrev32q_u8(vreinterpretq_u8_s32(dip))); in ip4_lookup_node_process_vec()
114 rte_lpm_lookupx4(lpm, dip, result.u32, drop_nh); in ip4_lookup_node_process_vec()
H A Dip4_lookup_sse.h25 __m128i dip; /* SSE register */ in ip4_lookup_node_process_vec() local
104 dip = _mm_set_epi32(ip3, ip2, ip1, ip0); in ip4_lookup_node_process_vec()
109 dip = _mm_shuffle_epi8(dip, bswap_mask); in ip4_lookup_node_process_vec()
116 rte_lpm_lookupx4(lpm, dip, dst.u32, drop_nh); in ip4_lookup_node_process_vec()
/f-stack/dpdk/app/test-sad/
H A Dmain.c192 &tbl[j].tuple.v6.dip); in parse_file()
195 &tbl[j].tuple.v4.dip); in parse_file()
276 tbl[i].tuple.v6.dip[j] = in get_random_rules()
291 memcpy(tbl[i].tuple.v6.dip, in get_random_rules()
450 print_addr(af, dip); in print_tuple()
466 const void *dip, *sip; in print_result() local
474 dip = (config.ipv6 == 0) ? &v4->dip : (const void *)v6->dip; in print_result()
479 print_tuple(af, spi, dip, sip); in print_result()
498 print_tuple(af, spi, dip, sip); in print_result()
502 dip = (config.ipv6 == 0) ? &v4->dip : (const void *)v6->dip; in print_result()
[all …]
/f-stack/freebsd/contrib/openzfs/include/os/linux/zfs/sys/
H A Dzfs_ctldir.h63 extern int zfsctl_root_lookup(struct inode *dip, const char *name,
68 extern int zfsctl_snapdir_lookup(struct inode *dip, const char *name,
73 extern int zfsctl_snapdir_remove(struct inode *dip, const char *name,
75 extern int zfsctl_snapdir_mkdir(struct inode *dip, const char *dirname,
85 extern int zfsctl_shares_lookup(struct inode *dip, char *name,
H A Dzfs_vnops_os.h49 extern int zfs_tmpfile(struct inode *dip, vattr_t *vapzfs, int excl,
H A Dzpl.h62 extern int zpl_xattr_security_init(struct inode *ip, struct inode *dip,
/f-stack/freebsd/contrib/openzfs/module/os/linux/zfs/
H A Dzpl_ctldir.c117 zpl_root_lookup(struct inode *dip, struct dentry *dentry, unsigned int flags) in zpl_root_lookup() argument
124 error = -zfsctl_root_lookup(dip, dname(dentry), &ip, 0, cr, NULL, NULL); in zpl_root_lookup()
208 zpl_snapdir_lookup(struct inode *dip, struct dentry *dentry, in zpl_snapdir_lookup() argument
218 error = -zfsctl_snapdir_lookup(dip, dname(dentry), &ip, in zpl_snapdir_lookup()
322 zpl_snapdir_rmdir(struct inode *dip, struct dentry *dentry) in zpl_snapdir_rmdir() argument
328 error = -zfsctl_snapdir_remove(dip, dname(dentry), cr, 0); in zpl_snapdir_rmdir()
336 zpl_snapdir_mkdir(struct inode *dip, struct dentry *dentry, umode_t mode) in zpl_snapdir_mkdir() argument
345 zpl_vap_init(vap, dip, mode | S_IFDIR, cr); in zpl_snapdir_mkdir()
347 error = -zfsctl_snapdir_mkdir(dip, dname(dentry), vap, &ip, cr, 0); in zpl_snapdir_mkdir()
421 zpl_shares_lookup(struct inode *dip, struct dentry *dentry, in zpl_shares_lookup() argument
[all …]
H A Dzfs_ctldir.c756 zfsvfs_t *zfsvfs = ITOZSB(dip); in zfsctl_root_lookup()
762 *ipp = dip->i_sb->s_root->d_inode; in zfsctl_root_lookup()
789 zfsvfs_t *zfsvfs = ITOZSB(dip); in zfsctl_snapdir_lookup()
895 zfsctl_snapdir_remove(struct inode *dip, const char *name, cred_t *cr, in zfsctl_snapdir_remove() argument
898 zfsvfs_t *zfsvfs = ITOZSB(dip); in zfsctl_snapdir_remove()
920 error = zfsctl_snapshot_name(ITOZSB(dip), name, in zfsctl_snapdir_remove()
944 zfsctl_snapdir_mkdir(struct inode *dip, const char *dirname, vattr_t *vap, in zfsctl_snapdir_mkdir() argument
947 zfsvfs_t *zfsvfs = ITOZSB(dip); in zfsctl_snapdir_mkdir()
972 error = zfsctl_snapdir_lookup(dip, dirname, ipp, in zfsctl_snapdir_mkdir()
1203 zfsctl_shares_lookup(struct inode *dip, char *name, struct inode **ipp, in zfsctl_shares_lookup() argument
[all …]
H A Dzpl_xattr.c903 zpl_xattr_security_init(struct inode *ip, struct inode *dip, in zpl_xattr_security_init() argument
906 return security_inode_init_security(ip, dip, qstr, in zpl_xattr_security_init()
/f-stack/dpdk/lib/librte_ipsec/
H A Drte_ipsec_sad.h34 uint32_t dip; member
40 uint8_t dip[16]; member
H A Dipsec_sad.c322 sizeof(((struct rte_ipsec_sadv6_key *)0)->dip); in rte_ipsec_sad_create()
325 sizeof(((struct rte_ipsec_sadv4_key *)0)->dip); in rte_ipsec_sad_create()
/f-stack/freebsd/contrib/openzfs/config/
H A Dkernel-security-inode-init.m413 struct inode *dip __attribute__ ((unused)) = NULL;
17 security_inode_init_security(ip, dip, str, func, NULL);
/f-stack/dpdk/doc/guides/prog_guide/
H A Dipsec_lib.rst220 key.v4.dip = rte_cpu_to_be_32(dip_val);
228 By performance reason it is better to keep spi/dip/sip in net byte order
241 key.v4.dip = rte_cpu_to_be_32(necessary_dip);
268 uint32_t dip;
278 uint8_t dip[16];
293 keys[i].v4.dip = ipv4_hdr[i]->dst_addr;
/f-stack/dpdk/examples/ipsec-secgw/
H A Dsad.h111 v4[nb_v4].dip = ipv4->dst_addr; in sad_lookup()
126 memcpy(v6[nb_v6].dip, ipv6->dst_addr, in sad_lookup()
/f-stack/freebsd/contrib/device-tree/src/arm/
H A Dkirkwood-openblocks_a6.dts65 pmx_dip_switches: pmx-dip-switches {
H A Dkirkwood-openblocks_a7.dts75 pmx_dip_switches: pmx-dip-switches {
/f-stack/dpdk/examples/performance-thread/l3fwd-thread/
H A Dmain.c1413 __m128i *dip, in processx4_step1() argument
1440 dip[0] = _mm_set_epi32(x3, x2, x1, x0); in processx4_step1()
1448 processx4_step2(__m128i dip, in processx4_step2() argument
1459 dip = _mm_shuffle_epi8(dip, bswap_mask); in processx4_step2()
1463 rte_lpm_lookupx4(RTE_PER_LCORE(lcore_conf)->ipv4_lookup_struct, dip, in processx4_step2()
1470 dst.x = dip; in processx4_step2()
1708 __m128i dip[MAX_PKT_BURST / FWDSTEP]; in process_burst() local
1756 processx4_step1(&pkts_burst[j], &dip[j / FWDSTEP], in process_burst()
1761 processx4_step2(dip[j / FWDSTEP], ipv4_flag[j / FWDSTEP], in process_burst()
/f-stack/freebsd/netpfil/ipfw/
H A Dip_fw_table_algo.c3073 struct in_addr dip; member
3153 i = (f->dip.s_addr) ^ (f->sip.s_addr) ^ (f->e.dport) ^ (f->e.sport); in hash_flow4()
3208 f.dip.s_addr &= id->dst_ip; in ta_lookup_fhash()
3279 memset(&fe4->dip, 0xFF, sizeof(fe4->dip)); in ta_init_fhash()
3368 tfe->a.a4.dip.s_addr = htonl(fe4->dip.s_addr); in ta_dump_fhash_tentry()
3404 fe4->dip.s_addr = ntohl(tfe->a.a4.dip.s_addr); in tei_to_fhash_ent()
/f-stack/tools/compat/include/netinet/
H A Dip_fw.h858 struct in_addr dip; member
/f-stack/freebsd/netinet/
H A Dip_fw.h858 struct in_addr dip; member
/f-stack/dpdk/drivers/net/hinic/base/
H A Dhinic_pmd_niccfg.h705 struct pa_u32_s dip; /* 32bit */ member
/f-stack/tools/ipfw/
H A Dtables.c1329 memcpy(&tfe->a.a4.dip, &tmp, 4); in tentry_fill_key_type()
1921 paddr = &tfe->a.a4.dip; in table_show_entry()

12