Home
last modified time | relevance | path

Searched refs:d (Results 1 – 25 of 1173) sorted by relevance

12345678910>>...47

/f-stack/freebsd/net/
H A Dbpf.c823 __func__, d->bd_pid, d->bd_writer, in bpf_check_upgrade()
1096 error = bpf_uiomove(d, d->bd_hbuf, d->bd_hlen, uio); in bpfread()
1100 d->bd_fbuf = d->bd_hbuf; in bpfread()
1124 if (d->bd_async && d->bd_sig && d->bd_sigio) in bpf_wakeup()
1125 pgsigio(&d->bd_sigio, d->bd_sig, 0); in bpf_wakeup()
1154 if (!bpf_canfreebuf(d) && d->bd_hlen != 0) in bpf_ready()
1306 d->bd_fbuf = d->bd_hbuf; in reset_d()
2176 if (!d->bd_hbuf_in_use && d->bd_hbuf) in filt_bpfread()
2505 d->bd_fbuf = d->bd_hbuf; in catchpacket()
2908 bzero(d, sizeof(*d)); in bpfstats_fill_xbpf()
[all …]
H A Dnetmap_user.h294 #define IS_NETMAP_DESC(d) ((d) && P2NMD(d)->self == P2NMD(d)) argument
789 d->self = d; in nm_parse()
892 d->first_tx_ring = d->last_tx_ring = d->req.nr_tx_rings; in nm_open()
893 d->first_rx_ring = d->last_rx_ring = d->req.nr_rx_rings; in nm_open()
924 d->first_tx_ring, d->last_tx_ring, d->req.nr_tx_rings, in nm_open()
960 if (d == NULL || d->self != d) in nm_close()
962 if (d->done_mmap && d->mem) in nm_close()
963 munmap(d->mem, d->memsize); in nm_close()
968 bzero(d, sizeof(*d)); in nm_close()
1007 (char *)d->mem + d->memsize; in nm_mmap()
[all …]
H A Dbpf_buffer.c135 if (d->bd_sbuf != NULL) in bpf_buffer_free()
143 d->bd_sbuf = d->bd_hbuf = d->bd_fbuf = (caddr_t)~0; in bpf_buffer_free()
178 BPFD_LOCK(d); in bpf_buffer_ioctl_sblen()
181 BPFD_UNLOCK(d); in bpf_buffer_ioctl_sblen()
194 d->bd_bufsize = size; in bpf_buffer_ioctl_sblen()
195 d->bd_fbuf = fbuf; in bpf_buffer_ioctl_sblen()
196 d->bd_sbuf = sbuf; in bpf_buffer_ioctl_sblen()
198 d->bd_hbuf = NULL; in bpf_buffer_ioctl_sblen()
199 d->bd_slen = 0; in bpf_buffer_ioctl_sblen()
200 d->bd_hlen = 0; in bpf_buffer_ioctl_sblen()
[all …]
H A Dbpf_zerocopy.c513 BPFD_LOCK(d); in bpf_zerocopy_ioctl_rotzbuf()
514 if (d->bd_hbuf == NULL && d->bd_slen != 0) { in bpf_zerocopy_ioctl_rotzbuf()
515 ROTATE_BUFFERS(d); in bpf_zerocopy_ioctl_rotzbuf()
520 BPFD_UNLOCK(d); in bpf_zerocopy_ioctl_rotzbuf()
568 BPFD_LOCK(d); in bpf_zerocopy_ioctl_setzbuf()
569 if (d->bd_hbuf != NULL || d->bd_sbuf != NULL || d->bd_fbuf != NULL || in bpf_zerocopy_ioctl_setzbuf()
570 d->bd_bif != NULL) { in bpf_zerocopy_ioctl_setzbuf()
571 BPFD_UNLOCK(d); in bpf_zerocopy_ioctl_setzbuf()
583 d->bd_slen = 0; in bpf_zerocopy_ioctl_setzbuf()
584 d->bd_hlen = 0; in bpf_zerocopy_ioctl_setzbuf()
[all …]
/f-stack/freebsd/contrib/ngatm/netnatm/api/
H A Dcc_dump.c75 if (d->len >= d->maxsiz - 1) { in cc_dumpf()
76 d->ret = d->func(d->cc, d->uarg, d->buf); in cc_dumpf()
83 n = vsnprintf(d->buf + d->len, d->maxsiz - d->len, fmt, ap); in cc_dumpf()
90 if ((size_t)n < d->maxsiz - d->len) { in cc_dumpf()
96 d->buf[d->len] = '\0'; in cc_dumpf()
97 d->ret = d->func(d->cc, d->uarg, d->buf); in cc_dumpf()
101 d->len = 0; in cc_dumpf()
104 n = vsnprintf(d->buf, d->maxsiz, fmt, ap); in cc_dumpf()
113 d->len = d->maxsiz - 1; in cc_dumpf()
329 if (d.len > 0 && d.ret == 0) in cc_dump()
[all …]
/f-stack/dpdk/lib/librte_telemetry/
H A Dtelemetry_data.c20 d->data_len = 0; in rte_tel_data_start_array()
28 d->data_len = 0; in rte_tel_data_start_dict()
36 d->data_len = strlcpy(d->data.str, str, sizeof(d->data.str)); in rte_tel_data_string()
63 d->data.array[d->data_len++].ival = x; in rte_tel_data_add_array_int()
74 d->data.array[d->data_len++].u64val = x; in rte_tel_data_add_array_u64()
90 d->data.array[d->data_len].container.data = val; in rte_tel_data_add_array_container()
91 d->data.array[d->data_len++].container.keep = !!keep; in rte_tel_data_add_array_container()
99 struct tel_dict_entry *e = &d->data.dict[d->data_len]; in rte_tel_data_add_dict_string()
120 struct tel_dict_entry *e = &d->data.dict[d->data_len]; in rte_tel_data_add_dict_int()
137 struct tel_dict_entry *e = &d->data.dict[d->data_len]; in rte_tel_data_add_dict_u64()
[all …]
/f-stack/dpdk/lib/librte_distributor/
H A Drte_distributor.c370 d->activesum -= d->active[wkr]; in handle_returns()
372 d->activesum += d->active[wkr]; in handle_returns()
419 d->bufs[wkr].bufptr64[i] = d->backlog[wkr].pkts[i] | in release()
421 d->in_flight_tags[wkr][i] = d->backlog[wkr].tags[i]; in release()
707 d->returns.start = d->returns.count = 0; in rte_distributor_clear_returns()
744 free(d); in rte_distributor_create()
749 return d; in rte_distributor_create()
759 d = mz->addr; in rte_distributor_create()
760 strlcpy(d->name, name, sizeof(d->name)); in rte_distributor_create()
777 memset(d->active, 0, sizeof(d->active)); in rte_distributor_create()
[all …]
H A Drte_distributor_single.c123 d->in_flight_tags[wkr] = 0; in handle_worker_shutdown()
177 if (d->backlog[wkr].count) in process_returns()
199 d->returns.start = ret_start; in process_returns()
200 d->returns.count = ret_count; in process_returns()
219 return process_returns(d); in rte_distributor_process_single()
270 if (d->backlog[wkr].count) in rte_distributor_process_single()
374 d->returns.start = d->returns.count = 0; in rte_distributor_clear_returns_single()
376 memset(d->returns.mbufs, 0, sizeof(d->returns.mbufs)); in rte_distributor_clear_returns_single()
409 d = mz->addr; in rte_distributor_create_single()
410 strlcpy(d->name, name, sizeof(d->name)); in rte_distributor_create_single()
[all …]
/f-stack/app/redis-5.0.5/src/
H A Ddict.c114 dict *d = zmalloc(sizeof(*d)); in dictCreate() local
202 de = d->ht[0].table[d->rehashidx]; in dictRehash()
223 d->ht[0] = d->ht[1]; in dictRehash()
261 if (d->iterators == 0) dictRehash(d,1); in _dictRehashStep()
309 ht = dictIsRehashing(d) ? &d->ht[1] : &d->ht[0]; in dictAddRaw()
471 _dictClear(d,&d->ht[0],NULL); in dictRelease()
472 _dictClear(d,&d->ht[1],NULL); in dictRelease()
546 iter->d = d; in dictGetIterator()
625 he = (h >= d->ht[0].size) ? d->ht[1].table[h - d->ht[0].size] : in dictGetRandomKey()
989 _dictClear(d,&d->ht[0],callback); in dictEmpty()
[all …]
H A Ddict.h53 double d; member
89 dict *d; member
106 (d)->type->valDestructor((d)->privdata, (entry)->v.val)
110 (entry)->v.val = (d)->type->valDup((d)->privdata, _val_); \
126 (d)->type->keyDestructor((d)->privdata, (entry)->key)
130 (entry)->key = (d)->type->keyDup((d)->privdata, _key_); \
137 (d)->type->keyCompare((d)->privdata, key1, key2) : \
140 #define dictHashKey(d, key) (d)->type->hashFunction(key) argument
146 #define dictSlots(d) ((d)->ht[0].size+(d)->ht[1].size) argument
147 #define dictSize(d) ((d)->ht[0].used+(d)->ht[1].used) argument
[all …]
H A Dsha1.c81 R0(a,b,c,d,e, 0); R0(e,a,b,c,d, 1); R0(d,e,a,b,c, 2); R0(c,d,e,a,b, 3); in SHA1Transform()
82 R0(b,c,d,e,a, 4); R0(a,b,c,d,e, 5); R0(e,a,b,c,d, 6); R0(d,e,a,b,c, 7); in SHA1Transform()
83 R0(c,d,e,a,b, 8); R0(b,c,d,e,a, 9); R0(a,b,c,d,e,10); R0(e,a,b,c,d,11); in SHA1Transform()
84 R0(d,e,a,b,c,12); R0(c,d,e,a,b,13); R0(b,c,d,e,a,14); R0(a,b,c,d,e,15); in SHA1Transform()
85 R1(e,a,b,c,d,16); R1(d,e,a,b,c,17); R1(c,d,e,a,b,18); R1(b,c,d,e,a,19); in SHA1Transform()
86 R2(a,b,c,d,e,20); R2(e,a,b,c,d,21); R2(d,e,a,b,c,22); R2(c,d,e,a,b,23); in SHA1Transform()
87 R2(b,c,d,e,a,24); R2(a,b,c,d,e,25); R2(e,a,b,c,d,26); R2(d,e,a,b,c,27); in SHA1Transform()
88 R2(c,d,e,a,b,28); R2(b,c,d,e,a,29); R2(a,b,c,d,e,30); R2(e,a,b,c,d,31); in SHA1Transform()
89 R2(d,e,a,b,c,32); R2(c,d,e,a,b,33); R2(b,c,d,e,a,34); R2(a,b,c,d,e,35); in SHA1Transform()
90 R2(e,a,b,c,d,36); R2(d,e,a,b,c,37); R2(c,d,e,a,b,38); R2(b,c,d,e,a,39); in SHA1Transform()
[all …]
/f-stack/freebsd/contrib/openzfs/cmd/zpool/
H A DMakefile.am44 zpool.d/enc \
45 zpool.d/encdev \
50 zpool.d/label \
52 zpool.d/lsblk \
53 zpool.d/media \
54 zpool.d/model \
56 zpool.d/ses \
57 zpool.d/size \
58 zpool.d/slot \
59 zpool.d/smart \
[all …]
/f-stack/freebsd/opencrypto/
H A Drmd160.c178 d = state[3]; in RMD160Transform()
182 R(a, b, c, d, e, F0, K0, 11, 0); in RMD160Transform()
183 R(e, a, b, c, d, F0, K0, 14, 1); in RMD160Transform()
184 R(d, e, a, b, c, F0, K0, 15, 2); in RMD160Transform()
185 R(c, d, e, a, b, F0, K0, 12, 3); in RMD160Transform()
186 R(b, c, d, e, a, F0, K0, 5, 4); in RMD160Transform()
187 R(a, b, c, d, e, F0, K0, 8, 5); in RMD160Transform()
188 R(e, a, b, c, d, F0, K0, 7, 6); in RMD160Transform()
189 R(d, e, a, b, c, F0, K0, 9, 7); in RMD160Transform()
272 d = state[3]; in RMD160Transform()
[all …]
/f-stack/dpdk/drivers/common/dpaax/
H A Ddpaa_of.c36 free(d[num]); in of_close_dir()
37 free(d); in of_close_dir()
93 return d; in node2dir()
203 if (d->reg) in linear_dir()
206 d->reg = f; in linear_dir()
315 for (d = next_linear(d); d && (!d->compatible || in of_find_compatible_node()
318 d = next_linear(d)) in of_find_compatible_node()
320 if (d) in of_find_compatible_node()
367 if (d->lphandle && (d->lphandle->len == 4) && in of_find_node_by_phandle()
426 while ((d = d->parent)) in of_n_addr_cells()
[all …]
/f-stack/freebsd/contrib/openzfs/module/icp/algs/edonr/
H A Dedonr_byteorder.h124 #define ld_swap32(s, d) aix_ld_swap32(s, d) argument
125 #define st_swap32(s, d) aix_st_swap32(s, d) argument
126 #define ld_swap64(s, d) aix_ld_swap64(s, d) argument
127 #define st_swap64(s, d) aix_st_swap64(s, d) argument
141 #define st_swap64(s, d) sparc_st_swap64(s, d) argument
162 #define ld_swap32(s, d) sparc_ld_swap32(s, d) argument
163 #define st_swap32(s, d) sparc_st_swap32(s, d) argument
208 #define ld_swap32(s, d) (d = *(s)) argument
209 #define st_swap32(s, d) (*(d) = s) argument
212 #define ld_swap64(s, d) (d = *(s)) argument
[all …]
/f-stack/app/nginx-1.16.1/src/core/
H A Dngx_sha1.c25 ctx->d = 0x10325476; in ngx_sha1_init()
109 result[14] = (u_char) (ctx->d >> 8); in ngx_sha1_final()
110 result[15] = (u_char) ctx->d; in ngx_sha1_final()
126 #define F1(b, c, d) (((b) & (c)) | ((~(b)) & (d))) argument
127 #define F2(b, c, d) ((b) ^ (c) ^ (d)) argument
128 #define F3(b, c, d) (((b) & (c)) | ((b) & (d)) | ((c) & (d))) argument
159 uint32_t a, b, c, d, e, temp; in ngx_sha1_body() local
170 d = ctx->d; in ngx_sha1_body()
177 saved_d = d; in ngx_sha1_body()
280 d += saved_d; in ngx_sha1_body()
[all …]
H A Dngx_md5.c24 ctx->d = 0x10325476; in ngx_md5_init()
105 result[12] = (u_char) ctx->d; in ngx_md5_final()
106 result[13] = (u_char) (ctx->d >> 8); in ngx_md5_final()
107 result[14] = (u_char) (ctx->d >> 16); in ngx_md5_final()
108 result[15] = (u_char) (ctx->d >> 24); in ngx_md5_final()
172 uint32_t a, b, c, d; in ngx_md5_body() local
184 d = ctx->d; in ngx_md5_body()
190 saved_d = d; in ngx_md5_body()
194 STEP(F, a, b, c, d, SET(0), 0xd76aa478, 7); in ngx_md5_body()
271 d += saved_d; in ngx_md5_body()
[all …]
/f-stack/freebsd/contrib/dev/acpica/include/
H A Dacmacros.h201 #define ACPI_MOVE_16_TO_32(d, s) {(*(UINT32 *)(void *)(d))=0;\ argument
205 #define ACPI_MOVE_16_TO_64(d, s) {(*(UINT64 *)(void *)(d))=0;\ argument
218 #define ACPI_MOVE_32_TO_64(d, s) {(*(UINT64 *)(void *)(d))=0;\ argument
249 #define ACPI_MOVE_16_TO_16(d, s) *(UINT16 *)(void *)(d) = *(UINT16 *)(void *)(s) argument
277 #define ACPI_MOVE_16_TO_32(d, s) {(*(UINT32 *)(void *)(d)) = 0; ACPI_MOVE_16_TO_16(d, s);} argument
278 #define ACPI_MOVE_16_TO_64(d, s) {(*(UINT64 *)(void *)(d)) = 0; ACPI_MOVE_16_TO_16(d, s);} argument
289 #define ACPI_MOVE_32_TO_64(d, s) {(*(UINT64 *)(void *)(d)) = 0; ACPI_MOVE_32_TO_32(d, s);} argument
547 #define ARGI_LIST4(a, b, c, d) (ARG_1(d)|ARG_2(c)|ARG_3(b)|ARG_4(a)) argument
554 #define ARGP_LIST4(a, b, c, d) (ARG_1(a)|ARG_2(b)|ARG_3(c)|ARG_4(d)) argument
609 #define ACPI_IS_OCTAL_DIGIT(d) (((char)(d) >= '0') && ((char)(d) <= '7')) argument
[all …]
/f-stack/freebsd/kern/
H A Dmd5c.c110 #define FF(a, b, c, d, x, s, ac) { \ argument
115 #define GG(a, b, c, d, x, s, ac) { \ argument
120 #define HH(a, b, c, d, x, s, ac) { \ argument
125 #define II(a, b, c, d, x, s, ac) { \ argument
248 FF (a, b, c, d, x[ 0], S11, 0xd76aa478); /* 1 */
249 FF (d, a, b, c, x[ 1], S12, 0xe8c7b756); /* 2 */
250 FF (c, d, a, b, x[ 2], S13, 0x242070db); /* 3 */
251 FF (b, c, d, a, x[ 3], S14, 0xc1bdceee); /* 4 */
252 FF (a, b, c, d, x[ 4], S11, 0xf57c0faf); /* 5 */
253 FF (d, a, b, c, x[ 5], S12, 0x4787c62a); /* 6 */
[all …]
H A Dmd4c.c80 #define FF(a, b, c, d, x, s) { \ argument
81 (a) += F ((b), (c), (d)) + (x); \
84 #define GG(a, b, c, d, x, s) { \ argument
88 #define HH(a, b, c, d, x, s) { \ argument
192 FF (a, b, c, d, x[ 0], S11); /* 1 */ in MD4Transform()
193 FF (d, a, b, c, x[ 1], S12); /* 2 */ in MD4Transform()
194 FF (c, d, a, b, x[ 2], S13); /* 3 */ in MD4Transform()
195 FF (b, c, d, a, x[ 3], S14); /* 4 */ in MD4Transform()
196 FF (a, b, c, d, x[ 4], S11); /* 5 */ in MD4Transform()
197 FF (d, a, b, c, x[ 5], S12); /* 6 */ in MD4Transform()
[all …]
/f-stack/freebsd/contrib/ipfilter/netinet/
H A Dip_dstlist.c553 if (d->ipld_nodes == d->ipld_maxnodes) {
571 d->ipld_dests[d->ipld_nodes] = node;
739 bcopy(&d->ipld_dests[i + 1], &d->ipld_dests[i],
932 softd->tails[d->ipld_unit + 1] = d->ipld_pnext;
935 *d->ipld_pnext = d->ipld_next;
937 d->ipld_next->ipld_pnext = d->ipld_pnext;
974 d->ipld_maxnodes * sizeof(*d->ipld_dests));
977 KFREE(d);
1052 for (d = softd->dstlist[unit + 1]; d != NULL; d = d->ipld_next) {
1088 return d;
[all …]
/f-stack/freebsd/contrib/libsodium/src/libsodium/crypto_generichash/blake2b/ref/
H A Dblake2b-compress-avx2.h42 #define BLAKE2B_G1_V1(a, b, c, d, m) \ argument
46 d = XOR(d, a); \
47 d = ROT32(d); \
48 c = ADD(c, d); \
53 #define BLAKE2B_G2_V1(a, b, c, d, m) \ argument
57 d = XOR(d, a); \
58 d = ROT16(d); \
59 c = ADD(c, d); \
66 d = _mm256_permute4x64_epi64(d, _MM_SHUFFLE(2, 1, 0, 3)); \
73 d = _mm256_permute4x64_epi64(d, _MM_SHUFFLE(0, 3, 2, 1)); \
[all …]
/f-stack/freebsd/contrib/openzfs/module/icp/algs/sha1/
H A Dsha1.c492 d = ROTATE_LEFT(d, 30);
507 d = ROTATE_LEFT(d, 30);
522 d = ROTATE_LEFT(d, 30);
540 d = ROTATE_LEFT(d, 30);
561 d = ROTATE_LEFT(d, 30);
581 d = ROTATE_LEFT(d, 30);
601 d = ROTATE_LEFT(d, 30);
621 d = ROTATE_LEFT(d, 30);
642 d = ROTATE_LEFT(d, 30);
662 d = ROTATE_LEFT(d, 30);
[all …]
/f-stack/freebsd/netgraph/
H A Dng_mppc.c132 #define MPPC_CCOUNT_INC(d) ((d) = (((d) + 1) & MPPC_CCOUNT_MASK)) argument
338 rc4_init(&d->rc4, d->key, keylen); in ng_mppc_rcvmsg()
343 d->cc = 0; in ng_mppc_rcvmsg()
490 header = d->cc; in ng_mppc_compress()
493 if (d->flushed || ((d->cfg.bits & MPPE_STATELESS) != 0)) { in ng_mppc_compress()
592 d->cfg.startkey, d->key, &d->rc4); in ng_mppc_compress()
596 rc4_init(&d->rc4, d->key, KEYLEN(d->cfg.bits)); in ng_mppc_compress()
689 d->cfg.startkey, d->key, &d->rc4); in ng_mppc_decompress()
696 rc4_init(&d->rc4, d->key, KEYLEN(d->cfg.bits)); in ng_mppc_decompress()
725 d->cfg.startkey, d->key, &d->rc4); in ng_mppc_decompress()
[all …]
/f-stack/freebsd/crypto/des/
H A Ddes_setkey.c175 DES_LONG c,d,t,s,t2; in des_set_key_unchecked() local
184 c2l(in,d); in des_set_key_unchecked()
189 PERM_OP (d,c,t,4,0x0f0f0f0fL); in des_set_key_unchecked()
191 HPERM_OP(d,t,-2,0xcccc0000L); in des_set_key_unchecked()
192 PERM_OP (d,c,t,1,0x55555555L); in des_set_key_unchecked()
195 d= (((d&0x000000ffL)<<16L)| (d&0x0000ff00L) | in des_set_key_unchecked()
202 { c=((c>>2L)|(c<<26L)); d=((d>>2L)|(d<<26L)); } in des_set_key_unchecked()
204 { c=((c>>1L)|(c<<27L)); d=((d>>1L)|(d<<27L)); } in des_set_key_unchecked()
206 d&=0x0fffffffL; in des_set_key_unchecked()
215 des_skb[5][((d>> 7L)&0x03)|((d>> 8L)&0x3c)]| in des_set_key_unchecked()
[all …]

12345678910>>...47