Home
last modified time | relevance | path

Searched refs:pq (Results 1 – 25 of 83) sorted by relevance

1234

/freebsd/crypto/openssl/ssl/
H A Dpriority_queue.c66 #define ASSERT_USED(pq, idx) \ argument
67 assert(pq->elements[pq->heap[idx].index].used); \
68 assert(pq->elements[pq->heap[idx].index].posn == idx)
69 #define ASSERT_ELEM_USED(pq, elem) \ argument
70 assert(pq->elements[elem].used)
72 #define ASSERT_USED(pq, idx) argument
73 #define ASSERT_ELEM_USED(pq, elem) argument
103 static ossl_inline void pqueue_swap_elem(OSSL_PQUEUE *pq, size_t i, size_t j) in pqueue_swap_elem() argument
105 struct pq_heap_st *h = pq->heap, t_h; in pqueue_swap_elem()
106 struct pq_elem_st *e = pq->elements; in pqueue_swap_elem()
[all …]
H A Dpqueue.c38 pqueue *pq = OPENSSL_zalloc(sizeof(*pq)); in pqueue_new() local
40 return pq; in pqueue_new()
43 void pqueue_free(pqueue *pq) in pqueue_free() argument
45 OPENSSL_free(pq); in pqueue_free()
48 pitem *pqueue_insert(pqueue *pq, pitem *item) in pqueue_insert() argument
52 if (pq->items == NULL) { in pqueue_insert()
53 pq->items = item; in pqueue_insert()
57 for (curr = NULL, next = pq->items; in pqueue_insert()
67 pq->items = item; in pqueue_insert()
84 pitem *pqueue_peek(pqueue *pq) in pqueue_peek() argument
[all …]
/freebsd/sys/contrib/dev/broadcom/brcm80211/brcmutil/
H A Dutils.c55 struct sk_buff *brcmu_pktq_penq(struct pktq *pq, int prec, in brcmu_pktq_penq() argument
60 if (pktq_full(pq) || pktq_pfull(pq, prec)) in brcmu_pktq_penq()
63 q = &pq->q[prec].skblist; in brcmu_pktq_penq()
65 pq->len++; in brcmu_pktq_penq()
67 if (pq->hi_prec < prec) in brcmu_pktq_penq()
68 pq->hi_prec = (u8) prec; in brcmu_pktq_penq()
74 struct sk_buff *brcmu_pktq_penq_head(struct pktq *pq, int prec, in brcmu_pktq_penq_head() argument
79 if (pktq_full(pq) || pktq_pfull(pq, prec)) in brcmu_pktq_penq_head()
82 q = &pq->q[prec].skblist; in brcmu_pktq_penq_head()
84 pq->len++; in brcmu_pktq_penq_head()
[all …]
/freebsd/sys/contrib/dev/broadcom/brcm80211/include/
H A Dbrcmu_utils.h76 static inline int pktq_plen(struct pktq *pq, int prec) in pktq_plen() argument
78 return pq->q[prec].skblist.qlen; in pktq_plen()
81 static inline int pktq_pavail(struct pktq *pq, int prec) in pktq_pavail() argument
83 return pq->q[prec].max - pq->q[prec].skblist.qlen; in pktq_pavail()
86 static inline bool pktq_pfull(struct pktq *pq, int prec) in pktq_pfull() argument
88 return pq->q[prec].skblist.qlen >= pq->q[prec].max; in pktq_pfull()
91 static inline bool pktq_pempty(struct pktq *pq, int prec) in pktq_pempty() argument
93 return skb_queue_empty(&pq->q[prec].skblist); in pktq_pempty()
96 static inline struct sk_buff *pktq_ppeek(struct pktq *pq, int prec) in pktq_ppeek() argument
98 return skb_peek(&pq->q[prec].skblist); in pktq_ppeek()
[all …]
/freebsd/crypto/openssl/include/internal/
H A Dpriority_queue.h27 ossl_pqueue_##type##_free(PRIORITY_QUEUE_OF(type) *pq) \
29 ossl_pqueue_free((OSSL_PQUEUE *)pq); \
32 ossl_pqueue_##type##_pop_free(PRIORITY_QUEUE_OF(type) *pq, \
35 ossl_pqueue_pop_free((OSSL_PQUEUE *)pq, (void (*)(void *))freefunc); \
38 ossl_pqueue_##type##_reserve(PRIORITY_QUEUE_OF(type) *pq, size_t n) \
40 return ossl_pqueue_reserve((OSSL_PQUEUE *)pq, n); \
43 ossl_pqueue_##type##_num(const PRIORITY_QUEUE_OF(type) *pq) \
45 return ossl_pqueue_num((OSSL_PQUEUE *)pq); \
48 ossl_pqueue_##type##_push(PRIORITY_QUEUE_OF(type) *pq, \
51 return ossl_pqueue_push((OSSL_PQUEUE *)pq, (voi
[all...]
/freebsd/sys/dev/netmap/
H A Dif_ptnet.c189 static int ptnet_drain_transmit_queue(struct ptnet_queue *pq,
218 static int ptnet_rx_eof(struct ptnet_queue *pq, unsigned int budget,
259 static inline void ptnet_kick(struct ptnet_queue *pq) in ptnet_kick() argument
262 pq->stats.kicks ++; in ptnet_kick()
264 bus_write_4(pq->sc->iomem, pq->kick, 0); in ptnet_kick()
367 struct ptnet_queue *pq = sc->queues + i; in ptnet_attach() local
369 pq->sc = sc; in ptnet_attach()
370 pq->kring_id = i; in ptnet_attach()
371 pq->kick = PTNET_IO_KICK_BASE + 4 * i; in ptnet_attach()
372 pq->atok = sc->csb_gh + i; in ptnet_attach()
[all …]
/freebsd/crypto/openssl/test/
H A Dpriority_queue_test.c54 PRIORITY_QUEUE_OF(size_t) *pq = NULL; in test_size_t_priority_queue_int()
82 if (!TEST_ptr(pq = ossl_pqueue_size_t_new(&size_t_compare)) in test_size_t_priority_queue_int()
83 || !TEST_size_t_eq(ossl_pqueue_size_t_num(pq), 0)) in test_size_t_priority_queue_int()
86 if (reserve && !TEST_true(ossl_pqueue_size_t_reserve(pq, count))) in test_size_t_priority_queue_int()
90 if (!TEST_true(ossl_pqueue_size_t_push(pq, values + i, ref + i))) in test_size_t_priority_queue_int()
93 if (!TEST_size_t_eq(*ossl_pqueue_size_t_peek(pq), *sorted) in test_size_t_priority_queue_int()
94 || !TEST_size_t_eq(ossl_pqueue_size_t_num(pq), count)) in test_size_t_priority_queue_int()
101 if (!TEST_ptr_eq(ossl_pqueue_size_t_remove(pq, ref[i]), in test_size_t_priority_queue_int()
110 for (i = 0; ossl_pqueue_size_t_peek(pq) != NULL; i++) in test_size_t_priority_queue_int()
111 if (!TEST_size_t_eq(*ossl_pqueue_size_t_peek(pq), sorted[i]) in test_size_t_priority_queue_int()
[all …]
H A Dproperty_test.c480 OSSL_PROPERTY_LIST *pq = NULL; in test_property() local
487 ossl_property_free(pq); in test_property()
490 ossl_property_free(pq); in test_property()
496 OSSL_PROPERTY_LIST *pq = NULL; in test_property() local
507 ossl_property_free(pq); in test_property()
518 ossl_property_free(pq); in test_property()
522 ossl_property_free(pq); in test_property()
528 OSSL_PROPERTY_LIST *pq = NULL; in test_property() local
539 ossl_property_free(pq); in test_property()
550 ossl_property_free(pq); in test_property()
[all …]
/freebsd/sys/vm/
H A Dvm_pagequeue.h305 #define vm_pagequeue_assert_locked(pq) mtx_assert(&(pq)->pq_mutex, MA_OWNED) argument
306 #define vm_pagequeue_lock(pq) mtx_lock(&(pq)->pq_mutex) argument
307 #define vm_pagequeue_lockptr(pq) (&(pq)->pq_mutex) argument
308 #define vm_pagequeue_trylock(pq) mtx_trylock(&(pq)->pq_mutex) argument
309 #define vm_pagequeue_unlock(pq) mtx_unlock(&(pq)->pq_mutex) argument
336 vm_pagequeue_cnt_add(struct vm_pagequeue *pq, int addend) in vm_pagequeue_cnt_add() argument
339 vm_pagequeue_assert_locked(pq); in vm_pagequeue_cnt_add()
340 pq->pq_cnt += addend; in vm_pagequeue_cnt_add()
342 #define vm_pagequeue_cnt_inc(pq) vm_pagequeue_cnt_add((pq), 1) argument
343 #define vm_pagequeue_cnt_dec(pq) vm_pagequeue_cnt_add((pq), -1) argument
[all …]
H A Dvm_pageout.c236 struct vm_pagequeue *pq; member
243 vm_pageout_init_scan(struct scan_state *ss, struct vm_pagequeue *pq, in vm_pageout_init_scan() argument
247 vm_pagequeue_assert_locked(pq); in vm_pageout_init_scan()
252 TAILQ_INSERT_HEAD(&pq->pq_pl, marker, plinks.q); in vm_pageout_init_scan()
254 TAILQ_INSERT_AFTER(&pq->pq_pl, after, marker, plinks.q); in vm_pageout_init_scan()
258 ss->pq = pq; in vm_pageout_init_scan()
262 vm_pagequeue_unlock(pq); in vm_pageout_init_scan()
268 struct vm_pagequeue *pq; in vm_pageout_end_scan() local
270 pq in vm_pageout_end_scan()
294 struct vm_pagequeue *pq; vm_pageout_collect_batch() local
720 struct vm_pagequeue *pq; vm_pageout_launder() local
985 struct vm_pagequeue *pq; vm_pageout_laundry_worker() local
1169 struct vm_pagequeue *pq; vm_pageout_scan_active() local
1370 vm_pageout_reinsert_inactive_page(struct vm_pagequeue * pq,vm_page_t marker,vm_page_t m) vm_pageout_reinsert_inactive_page() argument
1395 struct vm_pagequeue *pq; vm_pageout_reinsert_inactive() local
1425 struct vm_pagequeue *pq; vm_pageout_scan_inactive() local
1744 struct vm_pagequeue *pq; vm_pageout_inactive() local
[all...]
H A Dvm_page.c463 struct vm_pagequeue *pq; in vm_page_domain_init() local
484 pq = &vmd->vmd_pagequeues[i]; in vm_page_domain_init()
485 TAILQ_INIT(&pq->pq_pl); in vm_page_domain_init()
486 mtx_init(&pq->pq_mutex, pq->pq_name, "vm pagequeue", in vm_page_domain_init()
488 pq->pq_pdpages = 0; in vm_page_domain_init()
3709 _vm_page_pqstate_commit_dequeue(struct vm_pagequeue *pq, vm_page_t m, in _vm_page_pqstate_commit_dequeue() argument
3714 vm_pagequeue_assert_locked(pq); in _vm_page_pqstate_commit_dequeue()
3715 KASSERT(vm_page_pagequeue(m) == pq, in _vm_page_pqstate_commit_dequeue()
3716 ("%s: queue %p does not match page %p", __func__, pq, in _vm_page_pqstate_commit_dequeue()
3754 struct vm_pagequeue *pq; vm_page_pqstate_commit_dequeue() local
3780 _vm_page_pqstate_commit_requeue(struct vm_pagequeue * pq,vm_page_t m,vm_page_astate_t * old,vm_page_astate_t new) _vm_page_pqstate_commit_requeue() argument
3865 vm_pqbatch_process_page(struct vm_pagequeue * pq,vm_page_t m,uint8_t queue) vm_pqbatch_process_page() argument
3906 vm_pqbatch_process(struct vm_pagequeue * pq,struct vm_batchqueue * bq,uint8_t queue) vm_pqbatch_process() argument
3927 struct vm_pagequeue *pq; vm_page_pqbatch_submit() local
3976 struct vm_pagequeue *pq; vm_page_pqbatch_drain() local
[all...]
/freebsd/crypto/openssl/doc/internal/man3/
H A DDEFINE_PRIORITY_QUEUE_OF.pod23 size_t ossl_pqueue_TYPE_num(const PRIORITY_QUEUE_OF(type) *pq);
26 void ossl_pqueue_TYPE_free(PRIORITY_QUEUE_OF(type) *pq);
27 void ossl_pqueue_TYPE_pop_free(PRIORITY_QUEUE_OF(type) *pq,
29 int ossl_pqueue_TYPE_reserve(PRIORITY_QUEUE_OF(type) *pq, size_t n);
30 int ossl_pqueue_TYPE_push(PRIORITY_QUEUE_OF(type) *pq, type *data,
32 type *ossl_pqueue_TYPE_peek(const PRIORITY_QUEUE_OF(type) *pq);
33 type *ossl_pqueue_TYPE_pop(const PRIORITY_QUEUE_OF(type) *pq);
34 type *ossl_pqueue_TYPE_remove(const PRIORITY_QUEUE_OF(type) *pq, size_t elem);
51 B<ossl_pqueue_I<TYPE>_num>() returns the number of elements in I<pq>
52 or B<0> if I<pq> is NULL.
[all …]
/freebsd/lib/libusb/
H A Dlibusb20_ugen20.c1124 uint16_t quirk_index, struct libusb20_quirk *pq) in ugen20_root_get_dev_quirk() argument
1140 pq->vid = q.vid; in ugen20_root_get_dev_quirk()
1141 pq->pid = q.pid; in ugen20_root_get_dev_quirk()
1142 pq->bcdDeviceLow = q.bcdDeviceLow; in ugen20_root_get_dev_quirk()
1143 pq->bcdDeviceHigh = q.bcdDeviceHigh; in ugen20_root_get_dev_quirk()
1144 strlcpy(pq->quirkname, q.quirkname, sizeof(pq->quirkname)); in ugen20_root_get_dev_quirk()
1151 struct libusb20_quirk *pq) in ugen20_root_get_quirk_name() argument
1167 strlcpy(pq->quirkname, q.quirkname, sizeof(pq->quirkname)); in ugen20_root_get_quirk_name()
1174 struct libusb20_quirk *pq) in ugen20_root_add_dev_quirk() argument
1181 q.vid = pq->vid; in ugen20_root_add_dev_quirk()
[all …]
H A Dlibusb20_int.h63 …b20_root_get_dev_quirk_t)(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
64 …20_root_get_quirk_name_t)(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
65 typedef int (libusb20_root_add_dev_quirk_t)(struct libusb20_backend *pbe, struct libusb20_quirk *pq…
66 …ef int (libusb20_root_remove_dev_quirk_t)(struct libusb20_backend *pbe, struct libusb20_quirk *pq);
H A Dlibusb20.h289 …libusb20_be_get_dev_quirk(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
290 …ibusb20_be_get_quirk_name(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
291 int libusb20_be_add_dev_quirk(struct libusb20_backend *pbe, struct libusb20_quirk *pq);
292 int libusb20_be_remove_dev_quirk(struct libusb20_backend *pbe, struct libusb20_quirk *pq);
/freebsd/sys/dev/usb/
H A Dusb_transfer.c2080 struct usb_xfer_queue *pq; in usbd_transfer_pending() local
2099 pq = &info->done_q; in usbd_transfer_pending()
2101 if (pq->curr == xfer) { in usbd_transfer_pending()
2363 struct usb_xfer_queue *pq = &info->done_q; in usbd_callback_ss_done_defer() local
2367 if (pq->curr != xfer) { in usbd_callback_ss_done_defer()
2368 usbd_transfer_enqueue(pq, xfer); in usbd_callback_ss_done_defer()
2370 if (!pq->recurse_1) { in usbd_callback_ss_done_defer()
2380 pq->recurse_2 = 0; in usbd_callback_ss_done_defer()
2395 usbd_callback_wrapper(struct usb_xfer_queue *pq) in usbd_callback_wrapper() argument
2397 struct usb_xfer *xfer = pq->curr; in usbd_callback_wrapper()
[all …]
H A Dusb_transfer.h128 void usb_command_wrapper(struct usb_xfer_queue *pq,
131 void usbd_pipe_start(struct usb_xfer_queue *pq);
134 void usbd_transfer_enqueue(struct usb_xfer_queue *pq,
/freebsd/contrib/ntp/libntp/
H A Dlibssl_compat.c170 const BIGNUM ** pq in sslshim_RSA_get0_factors() argument
177 if (pq) in sslshim_RSA_get0_factors()
178 *pq = prsa->q; in sslshim_RSA_get0_factors()
261 const BIGNUM ** pq, in sslshim_DSA_get0_pqg() argument
269 if (pq != NULL) in sslshim_DSA_get0_pqg()
270 *pq = pdsa->q; in sslshim_DSA_get0_pqg()
/freebsd/crypto/openssl/crypto/encode_decode/
H A Ddecoder_pkey.c226 OSSL_PROPERTY_LIST *pq; member
291 if (data->pq != NULL && props != NULL) { in collect_decoder_keymgmt()
292 di->score = ossl_property_match_count(data->pq, props); in collect_decoder_keymgmt()
441 OSSL_PROPERTY_LIST *pq = NULL, *p2 = NULL; in ossl_decoder_ctx_setup_for_pkey() local
483 p2 = pq = ossl_parse_query(libctx, propquery, 1); in ossl_decoder_ctx_setup_for_pkey()
487 if (pq == NULL) { in ossl_decoder_ctx_setup_for_pkey()
488 pq = *plp; in ossl_decoder_ctx_setup_for_pkey()
490 p2 = ossl_property_merge(pq, *plp); in ossl_decoder_ctx_setup_for_pkey()
491 ossl_property_free(pq); in ossl_decoder_ctx_setup_for_pkey()
494 pq = p2; in ossl_decoder_ctx_setup_for_pkey()
[all …]
/freebsd/sbin/pfctl/
H A Dpfctl_qstats.c143 struct pfioc_qstats pq; local
149 memset(&pq, 0, sizeof(pq));
177 pq.nr = nr;
178 pq.ticket = pa.ticket;
179 pq.buf = &qstats.data;
180 pq.nbytes = sizeof(qstats.data);
181 pq.version = altq_stats_version(pa.altq.scheduler);
182 if (ioctl(dev, DIOCGETQSTATS, &pq)) {
/freebsd/crypto/openssl/crypto/property/
H A Dproperty.c642 OSSL_PROPERTY_LIST *pq = NULL, *p2 = NULL; in ossl_method_store_fetch() local
674 p2 = pq = ossl_parse_query(store->ctx, prop_query, 0); in ossl_method_store_fetch()
682 if (pq == NULL) { in ossl_method_store_fetch()
683 pq = *plp; in ossl_method_store_fetch()
685 p2 = ossl_property_merge(pq, *plp); in ossl_method_store_fetch()
686 ossl_property_free(pq); in ossl_method_store_fetch()
689 pq = p2; in ossl_method_store_fetch()
700 if (pq == NULL) { in ossl_method_store_fetch()
717 optional = ossl_property_has_optional(pq); in ossl_method_store_fetch()
721 score = ossl_property_match_count(pq, imp in ossl_method_store_fetch()
[all...]
/freebsd/sys/contrib/device-tree/Bindings/ata/
H A Dfsl-sata.txt10 "fsl,pq-sata"
23 compatible = "fsl,mpc8379-sata", "fsl,pq-sata";
/freebsd/contrib/arm-optimized-routines/math/aarch64/experimental/advsimd/
H A Derfinvf_5u.c133 float32x4_t pq = vld1q_f32 (d->PQ); in V_NAME_F1() local
140 p2 = lookup (pq, idx_lo), q0 = lookup (pq, idx_hi), in V_NAME_F1()
/freebsd/contrib/llvm-project/llvm/include/llvm/CodeGen/
H A DLatencyPriorityQueue.h27 explicit latency_sort(LatencyPriorityQueue *pq) : PQ(pq) {} in latency_sort()
/freebsd/contrib/sendmail/src/
H A Drecipient.c403 ADDRESS **pq; local
417 for (pq = sendq; (q = *pq) != NULL; pq = &q->q_next)
473 ADDRESS **pq; local
736 for (pq = sendq; (q = *pq) != NULL; pq = &q->q_next)
799 prev = pq;
803 SM_ASSERT(pq != NULL);
813 new->q_next = *pq;
827 *pq = new;

1234