Home
last modified time | relevance | path

Searched refs:p (Results 1 – 25 of 558) sorted by relevance

12345678910>>...23

/xnu-11215/libkern/os/
H A Datomic_private.h263 #define os_atomic_load_is_plain(p) (sizeof(*(p)) <= sizeof(void *)) argument
264 #define os_atomic_store_is_plain(p) os_atomic_load_is_plain(p) argument
392 #define os_atomic_add(p, v, m) _os_atomic_c11_op(p, v, m, fetch_add, +) argument
411 #define os_atomic_inc(p, m) _os_atomic_c11_op(p, 1, m, fetch_add, +) argument
433 #define os_atomic_sub(p, v, m) _os_atomic_c11_op(p, v, m, fetch_sub, -) argument
452 #define os_atomic_dec(p, m) _os_atomic_c11_op(p, 1, m, fetch_sub, -) argument
474 #define os_atomic_and(p, v, m) _os_atomic_c11_op(p, v, m, fetch_and, &) argument
517 #define os_atomic_or_orig(p, v, m) _os_atomic_c11_op_orig(p, v, m, fetch_or) argument
518 #define os_atomic_or(p, v, m) _os_atomic_c11_op(p, v, m, fetch_or, |) argument
540 #define os_atomic_xor(p, v, m) _os_atomic_c11_op(p, v, m, fetch_xor, ^) argument
[all …]
/xnu-11215/bsd/kern/
H A Dkern_proc.c351 for (; p != current_proc(); p = p->p_pptr) { in inferior()
378 for (; p != t; p = p->p_pptr) { in isinferior()
758 return proc_ref_try_fast(p) ? p : PROC_NULL; in proc_self()
1548 if (p && p->p_stats) { in proc_increment_ru_oublock()
1865 memcpy(p->p_uuid, uuid, sizeof(p->p_uuid)); in proc_setexecutableuuid()
2012 memcpy(buf, &p->p_argc, sizeof(p->p_argc)); in proc_selfexecutableargs()
2046 if (p && (p->p_flag & P_LP64)) { in IS_64BIT_PROCESS()
2157 if (p == PROC_NULL || proc_is_shadow(p)) { in proc_find()
2213 p = proc_ref(p, true); in proc_findthread()
3835 p = proc_ref(p, true); in proc_rebootscan()
[all …]
H A Dkern_shutdown.c422 if (((p->p_flag & P_SYSTEM) != 0) || (p->p_ppid == 0) in sd_filt1()
423 || (p == self) || (p->p_stat == SZOMB) in sd_filt1()
478 if (((p->p_flag & P_SYSTEM) != 0) || (p->p_ppid == 0) in sd_filt2()
479 || (p == self) || (p->p_stat == SZOMB) in sd_filt2()
595 if (p && p != self) { in proc_shutdown()
630 for (p = allproc.lh_first; p; p = p->p_list.le_next) { in proc_shutdown()
635 for (p = zombproc.lh_first; p; p = p->p_list.le_next) { in proc_shutdown()
651 for (p = allproc.lh_first; p; p = p->p_list.le_next) { in proc_shutdown()
689 for (p = allproc.lh_first; p; p = p->p_list.le_next) { in proc_shutdown()
694 for (p = zombproc.lh_first; p; p = p->p_list.le_next) { in proc_shutdown()
[all …]
H A Dkern_memorystatus.c247 if (proc_ref(p, true) != p) { in _memstat_write_memlimit_to_ledger_locked()
2112 proc_getpid(p), (*p->p_name ? p->p_name : "unknown"), in memorystatus_do_kill()
3324 if (proc_ref(p, true) == p) { in memorystatus_dirty_set()
3450 (*p->p_name ? p->p_name : "unknown"), proc_getpid(p)); in memorystatus_on_terminate()
4549 …((p && *p->p_name) ? p->p_name : "unknown"), (p ? proc_getpid(p) : -1), (memlimit_is_active ? "Act… in memorystatus_log_exception()
4566 ((p && *p->p_name) ? p->p_name : "unknown"), (p ? proc_getpid(p) : -1), diag_threshold_value); in memorystatus_log_diag_threshold_exception()
6018 if (proc_ref(p, true) == p) { in memorystatus_kill_top_process()
6223 if (proc_ref(p, true) == p) { in memorystatus_kill_processes_aggressive()
6413 if (proc_ref(p, true) == p) { in memorystatus_kill_hiwat_proc()
6572 if (proc_ref(p, true) == p) { in memorystatus_kill_elevated_process()
[all …]
H A Dkern_sig.c416 (void)p; in signal_is_restricted()
474 proc_name_address(p), proc_pid(p), signum); in sigaction()
751 proc_reset_sigact(p, p->p_sigcatch); in execsigs()
1375 proc_t p; in kill() local
1703 if (p == kernproc || p == initproc) { in killpg1()
1781 proc_t p; in threadsignal() local
3231 proc_t p; in filt_sigdetach() local
3322 if (!itimerdecr(p, &p->p_vtimer_user, microsecs)) { in bsd_ast()
3338 if (!itimerdecr(p, &p->p_vtimer_prof, microsecs)) { in bsd_ast()
3357 timersub(&p->p_rlim_cpu, &tv, &p->p_rlim_cpu); in bsd_ast()
[all …]
H A Dkern_exit.c1505 __FUNCTION__, p->p_comm, proc_getpid(p), rv); in exit_with_reason()
1776 (void)p; in proc_crash_coredump()
1888 if (p->p_crash_behavior != 0 || p == initproc) { in proc_prepareexit()
1942 proc_getpid(p), proc_name, p->p_exit_reason->osr_namespace, p->p_exit_reason->osr_code, in proc_prepareexit()
2481 calcru(p, &p->p_stats->p_ru.ru_utime, &p->p_stats->p_ru.ru_stime, NULL); in proc_exit()
2482 p->p_ru->ru = p->p_stats->p_ru; in proc_exit()
2484 ruadd(&(p->p_ru->ru), &p->p_stats->p_cru); in proc_exit()
2846 proc_t p; in wait1continue() local
2879 proc_t p; in wait4_nocancel() local
3095 proc_t p; in waitidcontinue() local
[all …]
H A Dkern_resource.c211 p = curp; in getpriority()
251 for (p = allproc.lh_first; p != 0; p = p->p_list.le_next) { in getpriority()
276 p = curp; in getpriority()
297 p = curp; in getpriority()
318 p = curp; in getpriority()
340 p = curp; in getpriority()
441 p = curp; in setpriority()
508 p = curp; in setpriority()
545 p = curp; in setpriority()
565 p = curp; in setpriority()
[all …]
H A Dkern_time.c323 proc_spinlock(p); in getitimer()
535 struct proc *p, in realitexpire() argument
547 if (--p->p_ractive > 0 || r != p) { in realitexpire()
569 proc_rele(p); in realitexpire()
589 proc_rele(p); in realitexpire()
594 timevaladd(&p->p_rtime, &p->p_realtimer.it_interval); in realitexpire()
599 timevaladd(&p->p_rtime, &p->p_realtimer.it_interval); in realitexpire()
605 p->p_rtime = p->p_realtimer.it_interval; in realitexpire()
614 p->p_ractive++; in realitexpire()
619 proc_rele(p); in realitexpire()
[all …]
H A Dkern_memorystatus_internal.h231 #define MEMSTAT_PERCENT_TOTAL_PAGES(p) ((uint32_t)(p * atop_64(max_mem) / 100)) argument
283 _memstat_proc_is_aging(proc_t p) in _memstat_proc_is_aging() argument
289 _memstat_proc_is_tracked(proc_t p) in _memstat_proc_is_tracked() argument
295 _memstat_proc_is_dirty(proc_t p) in _memstat_proc_is_dirty() argument
301 _memstat_proc_can_idle_exit(proc_t p) in _memstat_proc_can_idle_exit() argument
314 _memstat_proc_is_managed(proc_t p) in _memstat_proc_is_managed() argument
320 _memstat_proc_is_frozen(proc_t p) in _memstat_proc_is_frozen() argument
326 _memstat_proc_is_suspended(proc_t p) in _memstat_proc_is_suspended() argument
346 _memstat_proc_set_resumed(proc_t p) in _memstat_proc_set_resumed() argument
363 _memstat_proc_is_elevated(proc_t p) in _memstat_proc_is_elevated() argument
[all …]
H A Dkern_cs.c219 proc_lock(p); in cs_allow_invalid()
237 proc_unlock(p); in cs_allow_invalid()
259 vaddr, proc_getpid(p), p->p_comm); in cs_invalid_page()
262 proc_lock(p); in cs_invalid_page()
297 proc_unlock(p); in cs_invalid_page()
302 vaddr, proc_getpid(p), p->p_comm, (unsigned int)proc_getcsflags(p), in cs_invalid_page()
355 if (p != NULL && (proc_getcsflags(p) & CS_ENFORCEMENT)) { in cs_process_enforcement()
391 if (p != NULL && (proc_getcsflags(p) & CS_VALID)) { in cs_valid()
412 if (p != NULL && (proc_getcsflags(p) & CS_REQUIRE_LV)) { in cs_require_lv()
425 if (p != NULL && (proc_getcsflags(p) & CS_FORCED_LV)) { in csproc_forced_lv()
[all …]
H A Dkern_prot.c137 *retval = p->p_debugger; in setprivexec()
157 *retval = proc_getpid(p); in getpid()
176 *retval = p->p_ppid; in getppid()
195 *retval = p->p_pgrpid; in getpgrp()
222 pt = p; in getpgid()
484 setsid_internal(proc_t p) in setsid_internal() argument
488 if (p->p_pgrpid == proc_getpid(p) || in setsid_internal()
495 (void)enterpgrp(p, proc_getpid(p), 1); in setsid_internal()
658 proc_issetugid(proc_t p) in proc_issetugid() argument
1361 error = proc_suser(p); in setgroups_internal()
[all …]
H A Dproc_info.c2784 proc_t p; in proc_pidfdinfo() local
2946 proc_rele(p); in proc_pidfdinfo()
3078 proc_t p; in proc_pidfileportinfo() local
3125 proc_rele(p); in proc_pidfileportinfo()
3438 proc_t p; in proc_terminate() local
3459 proc_rele(p); in proc_terminate()
3796 proc_lock(p); in proc_archinfo()
3816 proc_lock(p); in proc_pidexitreasoninfo()
3887 proc_lock(p); in proc_pidnoteexit()
3962 proc_t p; in proc_piddynkqueueinfo() local
[all …]
H A Dkern_aio.c526 aio_proc_lock(p); in aio_cancel()
566 aio_proc_lock(p); in _aio_close()
614 aio_proc_lock(p); in aio_error()
741 aio_proc_lock(p); in aio_return()
792 _aio_exec(proc_t p) in _aio_exec() argument
797 _aio_exit(p); in _aio_exec()
811 _aio_exit(proc_t p) in _aio_exit() argument
825 aio_proc_lock(p); in _aio_exit()
1125 error = msleep1(&p->AIO_SUSPEND_SLEEP_CHAN, aio_proc_mutex(p), in aio_suspend_nocancel()
1838 proc_fdlock(p); in aio_validate()
[all …]
/xnu-11215/tests/
H A Davx.c198 ++p; __asm__ volatile ("vmovaps %0, %%ymm8" :: "m" (*(__m256i*)p) : "ymm8"); p++; in restore_ymm()
215 for (j = 0; j < (int) (sizeof(p) / sizeof(p[0])); j++) { in populate_ymm()
216 p[j] = getpid(); in populate_ymm()
219 p[0] = 0x22222222; in populate_ymm()
220 p[7] = 0x77777777; in populate_ymm()
226 p[0] = 0x44444444; in populate_ymm()
227 p[7] = 0xEEEEEEEE; in populate_ymm()
234 p[0] = 0x88888888; in populate_ymm()
235 p[7] = 0xAAAAAAAA; in populate_ymm()
499 ++p; __asm__ volatile ("vmovaps %0, %%zmm8" :: "m" (*(__m512i*)p) : "zmm8"); p++; in restore_zmm()
[all …]
/xnu-11215/bsd/net/
H A Dif_bond.c1614 return p; in ifbond_lookup_port()
1651 if (p == NULL) { in bond_receive_lacpdu()
1732 if (p == NULL || p->po_enabled == 0 in bond_receive_la_marker_pdu()
1826 if (p == NULL || bondport_collecting(p) == 0) { in bond_input_packet_list()
2047 return p; in bondport_create()
2653 bzero(&p->po_partner_state, sizeof(p->po_partner_state)); in bond_set_static_mode()
3494 return p; in ifbond_list_find_moved_port()
4029 bzero(&p->po_partner_state, sizeof(p->po_partner_state)); in bondport_RecordDefault()
4581 bondport_get_name(p), p->po_periodic_interval); in bondport_periodic_transmit_machine()
4698 bondport_get_name(p), p->po_n_transmit); in bondport_transmit_machine()
[all …]
H A Dpf_if.c377 aw->p.dyn = dyn; in pfi_dynaddr_setup()
559 pfi_buffer = p; in pfi_address_add()
566 bzero(p, sizeof(*p)); in pfi_address_add()
567 p->pfra_af = af; in pfi_address_add()
580 ((caddr_t)p)[p->pfra_net / 8] &= ~(0xFF >> (p->pfra_net % 8)); in pfi_address_add()
611 aw->p.dyncnt = aw->p.dyn->pfid_acnt4 + aw->p.dyn->pfid_acnt6; in pfi_dynaddr_copyout()
662 bzero(p->pfik_packets, sizeof(p->pfik_packets)); in pfi_update_status()
663 bzero(p->pfik_bytes, sizeof(p->pfik_bytes)); in pfi_update_status()
676 for (p = RB_MIN(pfi_ifhead, &pfi_ifs); p; p = nextp) { in pfi_get_ifaces()
733 if (strlcmp(p->pfik_name, filter, sizeof(p->pfik_name))) { in pfi_skip_if()
[all …]
/xnu-11215/tests/bounded_ptr_src/
H A Dctor.nullptr.cpp22 _assert(p == nullptr); in tests()
26 _assert(p == nullptr); in tests()
30 _assert(p == nullptr); in tests()
34 _assert(p == nullptr); in tests()
46 _assert(p == nullptr); in tests()
50 _assert(p == nullptr); in tests()
54 _assert(p == nullptr); in tests()
58 _assert(p == nullptr); in tests()
70 _assert(p == nullptr); in tests()
74 _assert(p == nullptr); in tests()
[all …]
/xnu-11215/bsd/skywalk/packet/
H A Dpacket_queue.h69 if ((KPKTQ_NEXT(p) = KPKTQ_FIRST(q)) == NULL) { \
71 (q)->kq_last = &KPKTQ_NEXT(p); \
73 KPKTQ_FIRST(q) = (p); \
78 ASSERT(KPKTQ_NEXT(p) == NULL); \
79 *(q)->kq_last = (p); \
80 (q)->kq_last = &KPKTQ_NEXT(p); \
86 *(q)->kq_last = (p); \
132 (p) = KPKTQ_NEXT(p))
136 (p) && ((tvar) = KPKTQ_NEXT(p), 1); \
137 (p) = (tvar))
[all …]
/xnu-11215/bsd/netkey/
H A Dkeydb.c106 struct secashead *p; in keydb_newsecashead() local
111 if (!p) { in keydb_newsecashead()
117 LIST_INIT(&p->savtree[i]); in keydb_newsecashead()
119 return p; in keydb_newsecashead()
128 struct secreplay *p; in keydb_newsecreplay() local
134 if (!p) { in keydb_newsecreplay()
148 p->bitmap = tmp_bitmap; in keydb_newsecreplay()
149 p->wsize = wsize; in keydb_newsecreplay()
151 return p; in keydb_newsecreplay()
157 if (p->bitmap) { in keydb_delsecreplay()
[all …]
/xnu-11215/bsd/dev/dtrace/
H A Ddtrace_ptss.c71 page->next = p->p_dtrace_ptss_pages; in dtrace_ptss_claim_entry_locked()
72 p->p_dtrace_ptss_pages = page; in dtrace_ptss_claim_entry_locked()
103 dtrace_ptss_claim_entry(struct proc* p) in dtrace_ptss_claim_entry() argument
115 lck_mtx_lock(&p->p_dtrace_sprlock); in dtrace_ptss_claim_entry()
145 if (p && p->p_dtrace_ptss_pages && e) { in dtrace_ptss_release_entry()
171 task_t task = proc_task(p); in dtrace_ptss_allocate_page()
265 task_t task = proc_task(p); in dtrace_ptss_free_page()
285 dtrace_ptss_enable(struct proc* p) in dtrace_ptss_enable() argument
307 dtrace_ptss_exec_exit(struct proc* p) in dtrace_ptss_exec_exit() argument
316 p->p_dtrace_ptss_free_list = NULL; in dtrace_ptss_exec_exit()
[all …]
/xnu-11215/bsd/netinet/
H A Dip_dummynet.c570 h->p = p; in heap_init()
609 h->p[son].object = p; in heap_insert()
621 HEAP_SWAP(h->p[son], h->p[father], tmp); in heap_insert()
660 h->p[father] = h->p[child]; in heap_extract()
670 h->p[father] = h->p[maxelt]; in heap_extract()
917 p->pipe_nr, p->if_name)); in ready_event_wfq()
963 p->V = MAX64( p->V, neh->p[0].key ); in ready_event_wfq()
1914 x->c_1 = p->max_p / (p->max_th - p->min_th); in config_red()
2173 h->p[i] = h->p[h->elements]; in fs_remove_from_heap()
2195 h->p[i] = h->p[h->elements]; in pipe_remove_from_heap()
[all …]
/xnu-11215/libkern/
H A Dmkext.c216 int i, p, cmp; in insert_node() local
221 p = N + 1 + key[0]; in insert_node()
227 p = sp->rchild[p]; in insert_node()
229 sp->rchild[p] = r; in insert_node()
235 p = sp->lchild[p]; in insert_node()
259 if (sp->rchild[sp->parent[p]] == p) { in insert_node()
277 q = sp->lchild[p]; in delete_node()
279 q = sp->rchild[p]; in delete_node()
281 q = sp->lchild[p]; in delete_node()
295 if (sp->rchild[sp->parent[p]] == p) { in delete_node()
[all …]
/xnu-11215/bsd/net/pktsched/
H A Dpktsched_netem.c854 if (h->p[parent].key < h->p[child].key) { in heap_insert()
857 HEAP_SWAP(h->p[child], h->p[parent], tmp); in heap_insert()
871 *key = h->p[0].key; in heap_peek()
872 *pkt = h->p[0].pkt; in heap_peek()
885 *key = h->p[0].key; in heap_extract()
893 if (child != max && h->p[child + 1].key < h->p[child].key) { in heap_extract()
896 h->p[parent] = h->p[child]; in heap_extract()
904 h->p[parent] = h->p[max]; in heap_extract()
1437 if (p->ifnetem_jitter_ms * 3 > p->ifnetem_latency_ms) { in netem_check_params()
1440 p->ifnetem_jitter_ms, p->ifnetem_latency_ms); in netem_check_params()
[all …]
/xnu-11215/bsd/skywalk/channel/
H A Dchannel_syscalls.c272 proc_fdlock(p); in __channel_open()
275 proc_fdunlock(p); in __channel_open()
280 sk_proc_name_address(p), sk_proc_pid(p), (int)init.ci_nx_port, in __channel_open()
353 "th 0x%llx h %u kh %u", sk_proc_name_address(p), sk_proc_pid(p), in channel_sync_log1()
367 sk_proc_name_address(p), sk_proc_pid(p), sync, i, na->na_name, in channel_sync_log2()
600 SK_DSC(p, in __channel_sync()
609 SK_DSC(p, in __channel_sync()
647 SK_DSC(p, in __channel_sync()
656 SK_DSC(p, in __channel_sync()
728 sopt.sopt_p = p; in __channel_get_opt()
[all …]
/xnu-11215/bsd/skywalk/nexus/
H A Dnexus_syscalls.c145 proc_fdlock(p); in __nexus_open()
147 fp_drop(p, fd, fp, 1); in __nexus_open()
148 proc_fdunlock(p); in __nexus_open()
153 sk_proc_name_address(p), sk_proc_pid(p), fd, guard); in __nexus_open()
162 fp_free(p, fd, fp); in __nexus_open()
233 fp_drop(p, uap->ctl, fp, 0); in __nexus_register()
288 fp_drop(p, uap->ctl, fp, 0); in __nexus_deregister()
350 fp_drop(p, uap->ctl, fp, 0); in __nexus_create()
401 fp_drop(p, uap->ctl, fp, 0); in __nexus_destroy()
447 sopt.sopt_p = p; in __nexus_get_opt()
[all …]

12345678910>>...23