Home
last modified time | relevance | path

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

123

/freebsd/crypto/openssl/ssl/
H A Dpqueue.c40 pqueue *pq = OPENSSL_zalloc(sizeof(*pq)); in pqueue_new() local
42 if (pq == NULL) in pqueue_new()
45 return pq; in pqueue_new()
48 void pqueue_free(pqueue *pq) in pqueue_free() argument
50 OPENSSL_free(pq); in pqueue_free()
53 pitem *pqueue_insert(pqueue *pq, pitem *item) in pqueue_insert() argument
57 if (pq->items == NULL) { in pqueue_insert()
58 pq->items = item; in pqueue_insert()
62 for (curr = NULL, next = pq->items; in pqueue_insert()
72 pq->items = item; in pqueue_insert()
[all …]
/freebsd/sys/dev/netmap/
H A Dif_ptnet.c191 static int ptnet_drain_transmit_queue(struct ptnet_queue *pq,
220 static int ptnet_rx_eof(struct ptnet_queue *pq, unsigned int budget,
261 static inline void ptnet_kick(struct ptnet_queue *pq) in ptnet_kick() argument
264 pq->stats.kicks ++; in ptnet_kick()
266 bus_write_4(pq->sc->iomem, pq->kick, 0); in ptnet_kick()
369 struct ptnet_queue *pq = sc->queues + i; in ptnet_attach() local
371 pq->sc = sc; in ptnet_attach()
372 pq->kring_id = i; in ptnet_attach()
373 pq in ptnet_attach()
521 struct ptnet_queue *pq = sc->queues + i; ptnet_detach() local
550 struct ptnet_queue *pq = sc->queues + i; ptnet_detach() local
640 struct ptnet_queue *pq = sc->queues + i; ptnet_irqs_init() local
655 struct ptnet_queue *pq = sc->queues + i; ptnet_irqs_init() local
681 struct ptnet_queue *pq = sc->queues + i; ptnet_irqs_init() local
708 struct ptnet_queue *pq = sc->queues + i; ptnet_irqs_fini() local
776 struct ptnet_queue *pq; ptnet_ioctl() local
974 struct ptnet_queue *pq = sc->queues + i; ptnet_qflush() local
1012 struct ptnet_queue *pq = sc->queues + i; ptnet_get_counter() local
1050 struct ptnet_queue *pq = sc->queues + i; ptnet_tick() local
1164 struct ptnet_queue *pq; ptnet_nm_register() local
1241 struct ptnet_queue *pq = sc->queues + kring->ring_id; ptnet_nm_txsync() local
1256 struct ptnet_queue *pq = sc->rxqueues + kring->ring_id; ptnet_nm_rxsync() local
1274 struct ptnet_queue *pq = sc->queues + i; ptnet_nm_intr() local
1282 struct ptnet_queue *pq = opaque; ptnet_tx_intr() local
1304 struct ptnet_queue *pq = opaque; ptnet_rx_intr() local
1339 ptnet_ring_update(struct ptnet_queue * pq,struct netmap_kring * kring,unsigned int head,unsigned int sync_flags) ptnet_ring_update() argument
1370 ptnet_drain_transmit_queue(struct ptnet_queue * pq,unsigned int budget,bool may_resched) ptnet_drain_transmit_queue() argument
1570 struct ptnet_queue *pq; ptnet_transmit() local
1671 ptnet_rx_eof(struct ptnet_queue * pq,unsigned int budget,bool may_resched) ptnet_rx_eof() argument
1907 struct ptnet_queue *pq = context; ptnet_rx_task() local
1916 struct ptnet_queue *pq = context; ptnet_tx_task() local
1942 struct ptnet_queue *pq = sc->queues + i; ptnet_poll() local
[all...]
/freebsd/sys/vm/
H A Dvm_pagequeue.h308 #define vm_pagequeue_assert_locked(pq) mtx_assert(&(pq)->pq_mutex, MA_OWNED) argument
309 #define vm_pagequeue_lock(pq) mtx_lock(&(pq)->pq_mutex) argument
310 #define vm_pagequeue_lockptr(pq) (&(pq)->pq_mutex) argument
311 #define vm_pagequeue_trylock(pq) mtx_trylock(&(pq)->pq_mutex) argument
312 #define vm_pagequeue_unlock(pq) mtx_unlock(&(pq)->pq_mutex) argument
339 vm_pagequeue_cnt_add(struct vm_pagequeue *pq, int addend) in vm_pagequeue_cnt_add() argument
342 vm_pagequeue_assert_locked(pq); in vm_pagequeue_cnt_add()
343 pq->pq_cnt += addend; in vm_pagequeue_cnt_add()
345 #define vm_pagequeue_cnt_inc(pq) vm_pagequeue_cnt_add((pq), 1) argument
346 #define vm_pagequeue_cnt_dec(pq) vm_pagequeue_cnt_add((pq), -1) argument
[all …]
H A Dvm_pageout.c212 struct vm_pagequeue *pq; member
219 vm_pageout_init_scan(struct scan_state *ss, struct vm_pagequeue *pq, in vm_pageout_init_scan() argument
223 vm_pagequeue_assert_locked(pq); in vm_pageout_init_scan()
228 TAILQ_INSERT_HEAD(&pq->pq_pl, marker, plinks.q); in vm_pageout_init_scan()
230 TAILQ_INSERT_AFTER(&pq->pq_pl, after, marker, plinks.q); in vm_pageout_init_scan()
234 ss->pq = pq; in vm_pageout_init_scan()
238 vm_pagequeue_unlock(pq); in vm_pageout_init_scan()
244 struct vm_pagequeue *pq; in vm_pageout_end_scan() local
246 pq = ss->pq; in vm_pageout_end_scan()
247 vm_pagequeue_assert_locked(pq); in vm_pageout_end_scan()
[all …]
H A Dvm_page.c445 struct vm_pagequeue *pq; in vm_page_domain_init() local
466 pq = &vmd->vmd_pagequeues[i]; in vm_page_domain_init()
467 TAILQ_INIT(&pq->pq_pl); in vm_page_domain_init()
468 mtx_init(&pq->pq_mutex, pq->pq_name, "vm pagequeue", in vm_page_domain_init()
470 pq->pq_pdpages = 0; in vm_page_domain_init()
3792 _vm_page_pqstate_commit_dequeue(struct vm_pagequeue *pq, vm_page_t m, in _vm_page_pqstate_commit_dequeue() argument
3797 vm_pagequeue_assert_locked(pq); in _vm_page_pqstate_commit_dequeue()
3798 KASSERT(vm_page_pagequeue(m) == pq, in _vm_page_pqstate_commit_dequeue()
3799 ("%s: queue %p does not match page %p", __func__, pq, m)); in _vm_page_pqstate_commit_dequeue()
3815 TAILQ_REMOVE(&pq->pq_pl, m, plinks.q); in _vm_page_pqstate_commit_dequeue()
[all …]
H A Dvm_meter.c428 vm_pagequeue_count(int pq) in vm_pagequeue_count() argument
435 v += vm_dom[i].vmd_pagequeues[pq].pq_cnt; in vm_pagequeue_count()
465 struct vm_pagequeue *pq; in sysctl_vm_pdpages() local
472 pq = &VM_DOMAIN(dom)->vmd_pagequeues[i]; in sysctl_vm_pdpages()
473 ret += pq->pq_pdpages; in sysctl_vm_pdpages()
/freebsd/lib/libusb/
H A Dlibusb20_ugen20.c980 uint16_t quirk_index, struct libusb20_quirk *pq) in ugen20_root_get_dev_quirk() argument
996 pq->vid = q.vid; in ugen20_root_get_dev_quirk()
997 pq->pid = q.pid; in ugen20_root_get_dev_quirk()
998 pq->bcdDeviceLow = q.bcdDeviceLow; in ugen20_root_get_dev_quirk()
999 pq->bcdDeviceHigh = q.bcdDeviceHigh; in ugen20_root_get_dev_quirk()
1000 strlcpy(pq->quirkname, q.quirkname, sizeof(pq->quirkname)); in ugen20_root_get_dev_quirk()
1007 struct libusb20_quirk *pq) in ugen20_root_get_quirk_name() argument
1023 strlcpy(pq->quirkname, q.quirkname, sizeof(pq->quirkname)); in ugen20_root_get_quirk_name()
1030 struct libusb20_quirk *pq) in ugen20_root_add_dev_quirk() argument
1037 q.vid = pq->vid; in ugen20_root_add_dev_quirk()
[all …]
H A Dlibusb20_int.h48 …b20_root_get_dev_quirk_t)(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
49 …20_root_get_quirk_name_t)(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
50 typedef int (libusb20_root_add_dev_quirk_t)(struct libusb20_backend *pbe, struct libusb20_quirk *pq…
51 …ef int (libusb20_root_remove_dev_quirk_t)(struct libusb20_backend *pbe, struct libusb20_quirk *pq);
H A Dlibusb20.h284 …libusb20_be_get_dev_quirk(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
285 …ibusb20_be_get_quirk_name(struct libusb20_backend *pbe, uint16_t index, struct libusb20_quirk *pq);
286 int libusb20_be_add_dev_quirk(struct libusb20_backend *pbe, struct libusb20_quirk *pq);
287 int libusb20_be_remove_dev_quirk(struct libusb20_backend *pbe, struct libusb20_quirk *pq);
H A Dlibusb20.c1202 uint16_t quirk_index, struct libusb20_quirk *pq) in libusb20_be_get_dev_quirk() argument
1204 return (pbe->methods->root_get_dev_quirk(pbe, quirk_index, pq)); in libusb20_be_get_dev_quirk()
1209 uint16_t quirk_index, struct libusb20_quirk *pq) in libusb20_be_get_quirk_name() argument
1211 return (pbe->methods->root_get_quirk_name(pbe, quirk_index, pq)); in libusb20_be_get_quirk_name()
1216 struct libusb20_quirk *pq) in libusb20_be_add_dev_quirk() argument
1218 return (pbe->methods->root_add_dev_quirk(pbe, pq)); in libusb20_be_add_dev_quirk()
1223 struct libusb20_quirk *pq) in libusb20_be_remove_dev_quirk() argument
1225 return (pbe->methods->root_remove_dev_quirk(pbe, pq)); in libusb20_be_remove_dev_quirk()
/freebsd/sys/dev/usb/
H A Dusb_transfer.c2078 struct usb_xfer_queue *pq; in usbd_transfer_pending() local
2097 pq = &info->done_q; in usbd_transfer_pending()
2099 if (pq->curr == xfer) { in usbd_transfer_pending()
2361 struct usb_xfer_queue *pq = &info->done_q; in usbd_callback_ss_done_defer() local
2365 if (pq->curr != xfer) { in usbd_callback_ss_done_defer()
2366 usbd_transfer_enqueue(pq, xfer); in usbd_callback_ss_done_defer()
2368 if (!pq->recurse_1) { in usbd_callback_ss_done_defer()
2378 pq->recurse_2 = 0; in usbd_callback_ss_done_defer()
2393 usbd_callback_wrapper(struct usb_xfer_queue *pq) in usbd_callback_wrapper() argument
2395 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/test/
H A Dproperty_test.c451 OSSL_PROPERTY_LIST *pq = NULL; in test_property() local
458 ossl_property_free(pq); in test_property()
461 ossl_property_free(pq); in test_property()
467 OSSL_PROPERTY_LIST *pq = NULL; in test_property() local
478 ossl_property_free(pq); in test_property()
489 ossl_property_free(pq); in test_property()
493 ossl_property_free(pq); in test_property()
499 OSSL_PROPERTY_LIST *pq = NULL; in test_property() local
510 ossl_property_free(pq); in test_property()
521 ossl_property_free(pq); in test_property()
[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.c522 OSSL_PROPERTY_LIST *pq = NULL, *p2 = NULL; in ossl_method_store_fetch() local
546 p2 = pq = ossl_parse_query(store->ctx, prop_query, 0); in ossl_method_store_fetch()
549 if (pq == NULL) { in ossl_method_store_fetch()
550 pq = *plp; in ossl_method_store_fetch()
552 p2 = ossl_property_merge(pq, *plp); in ossl_method_store_fetch()
553 ossl_property_free(pq); in ossl_method_store_fetch()
556 pq = p2; in ossl_method_store_fetch()
560 if (pq == NULL) { in ossl_method_store_fetch()
571 optional = ossl_property_has_optional(pq); in ossl_method_store_fetch()
575 score = ossl_property_match_count(pq, impl->properties); in ossl_method_store_fetch()
/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/llvm-project/llvm/include/llvm/CodeGen/
H A DLatencyPriorityQueue.h27 explicit latency_sort(LatencyPriorityQueue *pq) : PQ(pq) {} in latency_sort()
H A DResourcePriorityQueue.h32 explicit resource_sort(ResourcePriorityQueue *pq) : PQ(pq) {} in resource_sort()
/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/ntp/sntp/libopts/
H A Dcook.c152 contiguous_quote(char ** pps, char * pq, int * lnct_p) in contiguous_quote() argument
168 *pq = *(ps++); /* assign new quote character and return */ in contiguous_quote()
/freebsd/contrib/ntp/include/
H A Dlibssl_compat.h64 const BIGNUM **pq);
73 const BIGNUM **pq, const BIGNUM **pg);
/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;
/freebsd/sys/contrib/device-tree/src/arm64/amd/
H A Damd-seattle-xgbe-b.dtsi50 amd,serdes-pq-skew = <10>, <10>, <18>;
76 amd,serdes-pq-skew = <10>, <10>, <18>;
/freebsd/contrib/bc/tests/dc/errors/
H A D33.txt19 3857962W756.897937568235 _1^pq

123