/freebsd-11-stable/sys/compat/svr4/ |
H A D | svr4_misc.c | 121 svr4_sys_setitimer(td, uap) 122 struct thread *td; 125 td->td_retval[0] = 0; 131 svr4_sys_wait(td, uap) 132 struct thread *td; 137 error = kern_wait(td, WAIT_ANY, &st, 0, NULL); 155 td->td_retval[1] = st; 164 svr4_sys_execv(td, uap) 165 struct thread *td; 173 CHECKALTEXIST(td, ua [all...] |
/freebsd-11-stable/sys/cam/scsi/ |
H A D | scsi_sg.c | 433 sgopen(struct cdev *dev, int flags, int fmt, struct thread *td) argument 446 error = securelevel_gt(td->td_ucred, 1); 469 sgclose(struct cdev *dev, int flag, int fmt, struct thread *td) argument 502 sgioctl(struct cdev *dev, u_long cmd, caddr_t arg, int flag, struct thread *td) argument 537 td->td_retval[0] = softc->sg_user_timeout;
|
/freebsd-11-stable/sys/sys/ |
H A D | syscallsubr.h | 66 int kern___getcwd(struct thread *td, char *buf, enum uio_seg bufseg, 68 int kern_accept(struct thread *td, int s, struct sockaddr **name, 70 int kern_accept4(struct thread *td, int s, struct sockaddr **name, 72 int kern_accessat(struct thread *td, int fd, char *path, 74 int kern_adjtime(struct thread *td, struct timeval *delta, 76 int kern_alternate_path(struct thread *td, const char *prefix, const char *path, 78 int kern_bindat(struct thread *td, int dirfd, int fd, struct sockaddr *sa); 79 int kern_cap_ioctls_limit(struct thread *td, int fd, u_long *cmds, 81 int kern_cap_rights_limit(struct thread *td, int fd, cap_rights_t *rights); 82 int kern_chdir(struct thread *td, cha [all...] |
H A D | imgact.h | 100 void exec_cleanup(struct thread *td, struct vmspace *); 110 int pre_execve(struct thread *td, struct vmspace **oldvmspace); 111 void post_execve(struct thread *td, int error, struct vmspace *oldvmspace);
|
/freebsd-11-stable/sys/kern/ |
H A D | kern_exec.c | 119 static int do_execve(struct thread *td, struct image_args *args, 211 sys_execve(struct thread *td, struct execve_args *uap) argument 217 error = pre_execve(td, &oldvmspace); 223 error = kern_execve(td, &args, NULL, oldvmspace); 224 post_execve(td, error, oldvmspace); 236 sys_fexecve(struct thread *td, struct fexecve_args *uap) argument 242 error = pre_execve(td, &oldvmspace); 249 error = kern_execve(td, &args, NULL, oldvmspace); 251 post_execve(td, error, oldvmspace); 265 sys___mac_execve(struct thread *td, struc argument 287 pre_execve(struct thread *td, struct vmspace **oldvmspace) argument 308 post_execve(struct thread *td, int error, struct vmspace *oldvmspace) argument 337 kern_execve(struct thread *td, struct image_args *args, struct mac *mac_p, struct vmspace *oldvmspace) argument 353 do_execve(struct thread *td, struct image_args *args, struct mac *mac_p, struct vmspace *oldvmspace) argument 980 exec_cleanup(struct thread *td, struct vmspace *oldvmspace) argument 1275 exec_copyin_data_fds(struct thread *td, struct image_args *args, const void *data, size_t datalen, const int *fds, size_t fdslen) argument 1630 struct thread *td; local [all...] |
H A D | kern_sig.c | 106 static int killpg1(struct thread *td, int sig, int pgid, int all, 108 static int issignal(struct thread *td); 587 * Determine signal that should be delivered to thread td, the current 592 cursig(struct thread *td) argument 594 PROC_LOCK_ASSERT(td->td_proc, MA_OWNED); 595 mtx_assert(&td->td_proc->p_sigacts->ps_mtx, MA_OWNED); 596 THREAD_LOCK_ASSERT(td, MA_NOTOWNED); 597 return (SIGPENDING(td) ? issignal(td) : 0); 606 signotify(struct thread *td) argument 629 struct thread *td; local 683 kern_sigaction(struct thread *td, int sig, const struct sigaction *act, struct sigaction *oact, int flags) argument 835 sys_sigaction(struct thread *td, struct sigaction_args *uap) argument 863 freebsd4_sigaction(struct thread *td, struct freebsd4_sigaction_args *uap) argument 893 osigaction(struct thread *td, struct osigaction_args *uap) argument 927 osigreturn(struct thread *td, struct osigreturn_args *uap) argument 981 struct thread *td; local 1035 kern_sigprocmask(struct thread *td, int how, sigset_t *set, sigset_t *oset, int flags) argument 1109 sys_sigprocmask(struct thread *td, struct sigprocmask_args *uap) argument 1137 osigprocmask(struct thread *td, struct osigprocmask_args *uap) argument 1150 sys_sigwait(struct thread *td, struct sigwait_args *uap) argument 1178 sys_sigtimedwait(struct thread *td, struct sigtimedwait_args *uap) argument 1212 sys_sigwaitinfo(struct thread *td, struct sigwaitinfo_args *uap) argument 1235 proc_td_siginfo_capture(struct thread *td, siginfo_t *si) argument 1248 kern_sigtimedwait(struct thread *td, sigset_t waitset, ksiginfo_t *ksi, struct timespec *timeout) argument 1387 sys_sigpending(struct thread *td, struct sigpending_args *uap) argument 1406 osigpending(struct thread *td, struct osigpending_args *uap) argument 1433 osigvec(struct thread *td, struct osigvec_args *uap) argument 1471 osigblock(struct thread *td, struct osigblock_args *uap) argument 1487 osigsetmask(struct thread *td, struct osigsetmask_args *uap) argument 1509 sys_sigsuspend(struct thread *td, struct sigsuspend_args *uap) argument 1521 kern_sigsuspend(struct thread *td, sigset_t mask) argument 1583 osigsuspend(struct thread *td, struct osigsuspend_args *uap) argument 1601 osigstack(struct thread *td, struct osigstack_args *uap) argument 1634 sys_sigaltstack(struct thread *td, struct sigaltstack_args *uap) argument 1654 kern_sigaltstack(struct thread *td, stack_t *ss, stack_t *oss) argument 1690 killpg1(struct thread *td, int sig, int pgid, int all, ksiginfo_t *ksi) argument 1767 sys_kill(struct thread *td, struct kill_args *uap) argument 1817 sys_pdkill(struct thread *td, struct pdkill_args *uap) argument 1849 okillpg(struct thread *td, struct okillpg_args *uap) argument 1875 sys_sigqueue(struct thread *td, struct sigqueue_args *uap) argument 1885 kern_sigqueue(struct thread *td, pid_t pid, int signum, union sigval *value) argument 1968 postsig_done(int sig, struct thread *td, struct sigacts *ps) argument 1990 trapsignal(struct thread *td, ksiginfo_t *ksi) argument 2041 struct thread *td, *signal_td; local 2102 struct thread *td; local 2117 tdsignal(struct thread *td, int sig) argument 2128 tdksignal(struct thread *td, int sig, ksiginfo_t *ksi) argument 2135 tdsendsignal(struct proc *p, struct thread *td, int sig, ksiginfo_t *ksi) argument 2422 tdsigwakeup(struct thread *td, int sig, sig_t action, int intrval) argument 2503 sig_suspend_threads(struct thread *td, struct proc *p, int sending) argument 2554 ptracestop(struct thread *td, int sig, ksiginfo_t *si) argument 2670 struct thread *td; local 2698 tdsigcleanup(struct thread *td) argument 2746 struct thread *td; local 2788 struct thread *td; local 2816 issignal(struct thread *td) argument 3039 struct thread *td; local 3157 sigexit(struct thread *td, int sig) argument 3346 vnode_close_locked(struct thread *td, struct vnode *vp) argument 3361 corefile_open_last(struct thread *td, char *name, int indexpos, struct vnode **vpp) argument 3446 corefile_open(const char *comm, uid_t uid, pid_t pid, struct thread *td, int compress, struct vnode **vpp, char **namep) argument 3580 coredump(struct thread *td) argument 3721 nosys(struct thread *td, struct nosys_args *args) argument [all...] |
H A D | imgact_elf.c | 786 struct thread *td; local 836 td = curthread; 867 UIO_SYSSPACE, IO_NODELOCKED, td->td_ucred, 868 NOCRED, NULL, td); 1042 addr = round_page((vm_offset_t)vmspace->vm_daddr + lim_max(td, 1203 struct thread *td; member in struct:coredump_params 1286 p->active_cred, p->file_cred, NULL, p->td)); 1340 locked = PROC_LOCKED(p->td->td_proc); 1342 PROC_UNLOCK(p->td->td_proc); 1351 PROC_LOCK(p->td 1372 coredump(struct thread *td, struct vnode *vp, off_t limit, int flags) argument 1632 prepare_notes(struct thread *td, struct note_info_list *list, size_t *sizep) argument 1692 puthdr(struct thread *td, void *hdr, size_t hdrsize, int numsegs, size_t notesz) argument 1960 struct thread *td; local 1988 struct thread *td; local 2009 struct thread *td; local 2025 struct thread *td; local 2068 struct thread *td; local [all...] |
H A D | uipc_socket.c | 476 struct ucred *cred, struct thread *td) 516 so->so_fibnum = td->td_proc->p_fibnum; 531 error = (*prp->pr_usrreqs->pru_attach)(so, proto, td); 685 sobind(struct socket *so, struct sockaddr *nam, struct thread *td) argument 690 error = (*so->so_proto->pr_usrreqs->pru_bind)(so, nam, td); 696 sobindat(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument 701 error = (*so->so_proto->pr_usrreqs->pru_bindat)(fd, so, nam, td); 719 solisten(struct socket *so, int backlog, struct thread *td) argument 724 error = (*so->so_proto->pr_usrreqs->pru_listen)(so, backlog, td); 982 soconnect(struct socket *so, struct sockaddr *nam, struct thread *td) argument 475 socreate(int dom, struct socket **aso, int type, int proto, struct ucred *cred, struct thread *td) argument 989 soconnectat(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument 1053 sosend_dgram(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument 1218 sosend_generic(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument 1399 sosend(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument 3050 sopoll(struct socket *so, int events, struct ucred *active_cred, struct thread *td) argument 3063 sopoll_generic(struct socket *so, int events, struct ucred *active_cred, struct thread *td) argument 3155 pru_attach_notsupp(struct socket *so, int proto, struct thread *td) argument 3162 pru_bind_notsupp(struct socket *so, struct sockaddr *nam, struct thread *td) argument 3169 pru_bindat_notsupp(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument 3177 pru_connect_notsupp(struct socket *so, struct sockaddr *nam, struct thread *td) argument 3184 pru_connectat_notsupp(int fd, struct socket *so, struct sockaddr *nam, struct thread *td) argument 3199 pru_control_notsupp(struct socket *so, u_long cmd, caddr_t data, struct ifnet *ifp, struct thread *td) argument 3214 pru_listen_notsupp(struct socket *so, int backlog, struct thread *td) argument 3242 pru_send_notsupp(struct socket *so, int flags, struct mbuf *m, struct sockaddr *addr, struct mbuf *control, struct thread *td) argument 3283 pru_sosend_notsupp(struct socket *so, struct sockaddr *addr, struct uio *uio, struct mbuf *top, struct mbuf *control, int flags, struct thread *td) argument 3299 pru_sopoll_notsupp(struct socket *so, int events, struct ucred *cred, struct thread *td) argument [all...] |
H A D | init_main.c | 389 null_fetch_syscall_args(struct thread *td __unused) 396 null_set_syscall_retval(struct thread *td __unused, int error __unused) 454 struct thread *td; local 461 td = &thread0; 505 td->td_tid = PID_MAX + 1; 506 LIST_INSERT_HEAD(TIDHASH(td->td_tid), td, td_hash); 507 td->td_state = TDS_RUNNING; 508 td->td_pri_class = PRI_TIMESHARE; 509 td 627 struct thread *td; local 733 struct thread *td; local 853 struct thread *td; local 896 struct thread *td; local [all...] |
/freebsd-11-stable/sys/compat/linux/ |
H A D | linux_emul.c | 65 em_find(struct thread *td) argument 69 em = td->td_emuldata; 91 linux_proc_init(struct thread *td, struct thread *newtd, int flags) argument 119 p = td->td_proc; 125 em = em_find(td); 152 struct thread *td = curthread; local 158 td->td_tid, p->p_pid, p); 163 (p->p_sysent->sv_thread_detach)(td); 214 linux_common_execve(struct thread *td, struct image_args *eargs) argument 223 p = td 264 struct thread *td; local 319 linux_thread_dtor(void *arg __unused, struct thread *td) argument 334 linux_schedtail(struct thread *td) argument [all...] |
H A D | linux_fork.c | 68 linux_fork(struct thread *td, struct linux_fork_args *args) argument 83 if ((error = fork1(td, &fr)) != 0) 88 linux_proc_init(td, td2, 0); 90 td->td_retval[0] = p2->p_pid; 104 linux_vfork(struct thread *td, struct linux_vfork_args *args) argument 119 if ((error = fork1(td, &fr)) != 0) 124 linux_proc_init(td, td2, 0); 126 td->td_retval[0] = p2->p_pid; 141 linux_clone_proc(struct thread *td, struct linux_clone_args *args) argument 187 error = fork1(td, 262 linux_clone_thread(struct thread *td, struct linux_clone_args *args) argument 400 linux_clone(struct thread *td, struct linux_clone_args *args) argument 410 linux_exit(struct thread *td, struct linux_exit_args *args) argument 433 linux_set_tid_address(struct thread *td, struct linux_set_tid_address_args *args) argument 451 linux_thread_detach(struct thread *td) argument [all...] |
/freebsd-11-stable/sys/compat/freebsd32/ |
H A D | freebsd32_misc.c | 137 static int freebsd32_user_clock_nanosleep(struct thread *td, clockid_t clock_id, 163 freebsd32_wait4(struct thread *td, struct freebsd32_wait4_args *uap) argument 173 error = kern_wait(td, uap->pid, &status, uap->options, rup); 186 freebsd32_wait6(struct thread *td, struct freebsd32_wait6_args *uap) argument 203 error = kern_wait6(td, uap->idtype, PAIR32TO64(id_t, uap->id), 254 freebsd4_freebsd32_getfsstat(struct thread *td, argument 264 error = kern_getfsstat(td, &buf, size, &count, UIO_SYSSPACE, uap->mode); 278 td->td_retval[0] = count; 285 freebsd10_freebsd32_pipe(struct thread *td, argument 288 return (freebsd10_pipe(td, (struc 293 freebsd32_sigaltstack(struct thread *td, struct freebsd32_sigaltstack_args *uap) argument 419 freebsd32_execve(struct thread *td, struct freebsd32_execve_args *uap) argument 437 freebsd32_fexecve(struct thread *td, struct freebsd32_fexecve_args *uap) argument 457 freebsd32_mprotect(struct thread *td, struct freebsd32_mprotect_args *uap) argument 471 freebsd32_mmap(struct thread *td, struct freebsd32_mmap_args *uap) argument 487 freebsd6_freebsd32_mmap(struct thread *td, struct freebsd6_freebsd32_mmap_args *uap) argument 504 freebsd32_setitimer(struct thread *td, struct freebsd32_setitimer_args *uap) argument 528 freebsd32_getitimer(struct thread *td, struct freebsd32_getitimer_args *uap) argument 543 freebsd32_select(struct thread *td, struct freebsd32_select_args *uap) argument 566 freebsd32_pselect(struct thread *td, struct freebsd32_pselect_args *uap) argument 657 freebsd32_kevent(struct thread *td, struct freebsd32_kevent_args *uap) argument 697 freebsd32_gettimeofday(struct thread *td, struct freebsd32_gettimeofday_args *uap) argument 720 freebsd32_getrusage(struct thread *td, struct freebsd32_getrusage_args *uap) argument 776 freebsd32_readv(struct thread *td, struct freebsd32_readv_args *uap) argument 790 freebsd32_writev(struct thread *td, struct freebsd32_writev_args *uap) argument 804 freebsd32_preadv(struct thread *td, struct freebsd32_preadv_args *uap) argument 818 freebsd32_pwritev(struct thread *td, struct freebsd32_pwritev_args *uap) argument 1203 freebsd32_sendmsg(struct thread *td, struct freebsd32_sendmsg_args *uap) argument 1259 freebsd32_recvfrom(struct thread *td, struct freebsd32_recvfrom_args *uap) argument 1290 freebsd32_settimeofday(struct thread *td, struct freebsd32_settimeofday_args *uap) argument 1318 freebsd32_utimes(struct thread *td, struct freebsd32_utimes_args *uap) argument 1340 freebsd32_lutimes(struct thread *td, struct freebsd32_lutimes_args *uap) argument 1361 freebsd32_futimes(struct thread *td, struct freebsd32_futimes_args *uap) argument 1382 freebsd32_futimesat(struct thread *td, struct freebsd32_futimesat_args *uap) argument 1404 freebsd32_futimens(struct thread *td, struct freebsd32_futimens_args *uap) argument 1425 freebsd32_utimensat(struct thread *td, struct freebsd32_utimensat_args *uap) argument 1447 freebsd32_adjtime(struct thread *td, struct freebsd32_adjtime_args *uap) argument 1473 freebsd4_freebsd32_statfs(struct thread *td, struct freebsd4_freebsd32_statfs_args *uap) argument 1492 freebsd4_freebsd32_fstatfs(struct thread *td, struct freebsd4_freebsd32_fstatfs_args *uap) argument 1511 freebsd4_freebsd32_fhstatfs(struct thread *td, struct freebsd4_freebsd32_fhstatfs_args *uap) argument 1532 freebsd32_pread(struct thread *td, struct freebsd32_pread_args *uap) argument 1540 freebsd32_pwrite(struct thread *td, struct freebsd32_pwrite_args *uap) argument 1549 ofreebsd32_lseek(struct thread *td, struct ofreebsd32_lseek_args *uap) argument 1557 freebsd32_lseek(struct thread *td, struct freebsd32_lseek_args *uap) argument 1572 freebsd32_truncate(struct thread *td, struct freebsd32_truncate_args *uap) argument 1580 freebsd32_ftruncate(struct thread *td, struct freebsd32_ftruncate_args *uap) argument 1588 ofreebsd32_getdirentries(struct thread *td, struct ofreebsd32_getdirentries_args *uap) argument 1610 freebsd32_getdirentries(struct thread *td, struct freebsd32_getdirentries_args *uap) argument 1631 freebsd6_freebsd32_pread(struct thread *td, struct freebsd6_freebsd32_pread_args *uap) argument 1639 freebsd6_freebsd32_pwrite(struct thread *td, struct freebsd6_freebsd32_pwrite_args *uap) argument 1647 freebsd6_freebsd32_lseek(struct thread *td, struct freebsd6_freebsd32_lseek_args *uap) argument 1662 freebsd6_freebsd32_truncate(struct thread *td, struct freebsd6_freebsd32_truncate_args *uap) argument 1670 freebsd6_freebsd32_ftruncate(struct thread *td, struct freebsd6_freebsd32_ftruncate_args *uap) argument 1685 freebsd32_do_sendfile(struct thread *td, struct freebsd32_sendfile_args *uap, int compat) argument 1764 freebsd4_freebsd32_sendfile(struct thread *td, struct freebsd4_freebsd32_sendfile_args *uap) argument 1773 freebsd32_sendfile(struct thread *td, struct freebsd32_sendfile_args *uap) argument 1825 freebsd32_stat(struct thread *td, struct freebsd32_stat_args *uap) argument 1842 ofreebsd32_stat(struct thread *td, struct ofreebsd32_stat_args *uap) argument 1859 freebsd32_fstat(struct thread *td, struct freebsd32_fstat_args *uap) argument 1875 ofreebsd32_fstat(struct thread *td, struct ofreebsd32_fstat_args *uap) argument 1891 freebsd32_fstatat(struct thread *td, struct freebsd32_fstatat_args *uap) argument 1907 freebsd32_lstat(struct thread *td, struct freebsd32_lstat_args *uap) argument 1924 ofreebsd32_lstat(struct thread *td, struct ofreebsd32_lstat_args *uap) argument 1941 freebsd32_sysctl(struct thread *td, struct freebsd32_sysctl_args *uap) argument 1971 freebsd32_jail(struct thread *td, struct freebsd32_jail_args *uap) argument 2032 freebsd32_jail_set(struct thread *td, struct freebsd32_jail_set_args *uap) argument 2050 freebsd32_jail_get(struct thread *td, struct freebsd32_jail_get_args *uap) argument 2077 freebsd32_sigaction(struct thread *td, struct freebsd32_sigaction_args *uap) argument 2105 freebsd4_freebsd32_sigaction(struct thread *td, struct freebsd4_freebsd32_sigaction_args *uap) argument 2143 ofreebsd32_sigaction(struct thread *td, struct ofreebsd32_sigaction_args *uap) argument 2174 ofreebsd32_sigprocmask(struct thread *td, struct ofreebsd32_sigprocmask_args *uap) argument 2187 ofreebsd32_sigpending(struct thread *td, struct ofreebsd32_sigpending_args *uap) argument 2208 ofreebsd32_sigvec(struct thread *td, struct ofreebsd32_sigvec_args *uap) argument 2242 ofreebsd32_sigblock(struct thread *td, struct ofreebsd32_sigblock_args *uap) argument 2254 ofreebsd32_sigsetmask(struct thread *td, struct ofreebsd32_sigsetmask_args *uap) argument 2266 ofreebsd32_sigsuspend(struct thread *td, struct ofreebsd32_sigsuspend_args *uap) argument 2281 ofreebsd32_sigstack(struct thread *td, struct ofreebsd32_sigstack_args *uap) argument 2316 freebsd32_nanosleep(struct thread *td, struct freebsd32_nanosleep_args *uap) argument 2324 freebsd32_clock_nanosleep(struct thread *td, struct freebsd32_clock_nanosleep_args *uap) argument 2335 freebsd32_user_clock_nanosleep(struct thread *td, clockid_t clock_id, int flags, const struct timespec32 *ua_rqtp, struct timespec32 *ua_rmtp) argument 2362 freebsd32_clock_gettime(struct thread *td, struct freebsd32_clock_gettime_args *uap) argument 2379 freebsd32_clock_settime(struct thread *td, struct freebsd32_clock_settime_args *uap) argument 2396 freebsd32_clock_getres(struct thread *td, struct freebsd32_clock_getres_args *uap) argument 2414 freebsd32_ktimer_create(struct thread *td, struct freebsd32_ktimer_create_args *uap) argument 2442 freebsd32_ktimer_settime(struct thread *td, struct freebsd32_ktimer_settime_args *uap) argument 2463 freebsd32_ktimer_gettime(struct thread *td, struct freebsd32_ktimer_gettime_args *uap) argument 2479 freebsd32_clock_getcpuclockid2(struct thread *td, struct freebsd32_clock_getcpuclockid2_args *uap) argument 2493 freebsd32_thr_new(struct thread *td, struct freebsd32_thr_new_args *uap) argument 2526 freebsd32_thr_suspend(struct thread *td, struct freebsd32_thr_suspend_args *uap) argument 2570 freebsd32_sigqueue(struct thread *td, struct freebsd32_sigqueue_args *uap) argument 2589 freebsd32_sigtimedwait(struct thread *td, struct freebsd32_sigtimedwait_args *uap) argument 2631 freebsd32_sigwaitinfo(struct thread *td, struct freebsd32_sigwaitinfo_args *uap) argument 2656 freebsd32_cpuset_setid(struct thread *td, struct freebsd32_cpuset_setid_args *uap) argument 2665 freebsd32_cpuset_getid(struct thread *td, struct freebsd32_cpuset_getid_args *uap) argument 2674 freebsd32_cpuset_getaffinity(struct thread *td, struct freebsd32_cpuset_getaffinity_args *uap) argument 2683 freebsd32_cpuset_setaffinity(struct thread *td, struct freebsd32_cpuset_setaffinity_args *uap) argument 2692 freebsd32_nmount(struct thread *td, struct freebsd32_nmount_args *uap) argument 3021 freebsd32_kldstat(struct thread *td, struct freebsd32_kldstat_args *uap) argument 3054 freebsd32_posix_fallocate(struct thread *td, struct freebsd32_posix_fallocate_args *uap) argument 3065 freebsd32_posix_fadvise(struct thread *td, struct freebsd32_posix_fadvise_args *uap) argument 3102 freebsd32_procctl(struct thread *td, struct freebsd32_procctl_args *uap) argument 3192 freebsd32_fcntl(struct thread *td, struct freebsd32_fcntl_args *uap) argument 3220 freebsd32_ppoll(struct thread *td, struct freebsd32_ppoll_args *uap) argument 3248 freebsd32_sched_rr_get_interval(struct thread *td, struct freebsd32_sched_rr_get_interval_args *uap) argument [all...] |
/freebsd-11-stable/sys/compat/cloudabi/ |
H A D | cloudabi_proc.c | 46 cloudabi_sys_proc_exec(struct thread *td, argument 53 error = pre_execve(td, &oldvmspace); 56 error = exec_copyin_data_fds(td, &args, uap->data, uap->data_len, 60 error = kern_execve(td, &args, NULL, oldvmspace); 62 post_execve(td, error, oldvmspace); 67 cloudabi_sys_proc_exit(struct thread *td, argument 71 exit1(td, uap->rval, 0); 76 cloudabi_sys_proc_fork(struct thread *td, argument 88 error = fork1(td, &fr); 92 td 97 cloudabi_sys_proc_raise(struct thread *td, struct cloudabi_sys_proc_raise_args *uap) argument [all...] |
/freebsd-11-stable/sys/fs/udf/ |
H A D | udf_vfsops.c | 192 struct thread *td; local 199 td = curthread; 228 NDINIT(ndp, LOOKUP, FOLLOW | LOCKLEAF, UIO_SYSSPACE, fspec, td); 240 error = VOP_ACCESS(devvp, VREAD, td->td_ucred, td); 242 error = priv_check(td, PRIV_VFS_MOUNT_PERM); 587 struct thread *td; local 614 td = curthread; 619 if ((error = udf_allocv(mp, &vp, td))) { 636 error = vfs_hash_insert(vp, ino, flags, td, vp [all...] |
/freebsd-11-stable/sys/geom/part/ |
H A D | g_part.c | 2118 g_part_ioctl(struct g_provider *pp, u_long cmd, void *data, int fflag, struct thread *td) argument 2123 return G_PART_IOCTL(table, pp, cmd, data, fflag, td);
|
/freebsd-11-stable/contrib/llvm-project/openmp/runtime/src/ |
H A D | kmp.h | 2332 #define TASK_DEQUE_SIZE(td) ((td).td_deque_size) 2333 #define TASK_DEQUE_MASK(td) ((td).td_deque_size - 1) 2336 kmp_base_thread_data_t td; member in union:kmp_thread_data
|
/freebsd-11-stable/sys/cddl/contrib/opensolaris/uts/common/fs/zfs/ |
H A D | zfs_vfsops.c | 179 struct thread *td; local 186 td = curthread; 194 id = td->td_ucred->cr_ruid; 197 id = td->td_ucred->cr_rgid; 1782 kthread_t *td = curthread; local 1784 cred_t *cr = td->td_ucred; 1819 if (!prison_allow(td->td_ucred, PR_ALLOW_MOUNT_ZFS)) 1863 VOP_ACCESS(mvp, VWRITE, cr, td) != 0) { 2126 kthread_t *td = curthread; local 2129 cred_t *cr = td [all...] |
/freebsd-11-stable/sys/dev/netmap/ |
H A D | netmap_legacy.c | 355 struct thread *td) 376 error = netmap_ioctl(priv, NIOCCTRL, (caddr_t)hdr, td, 419 error = ifioctl(&so, cmd, data, td); 354 netmap_ioctl_legacy(struct netmap_priv_d *priv, u_long cmd, caddr_t data, struct thread *td) argument
|
/freebsd-11-stable/sys/dev/usb/ |
H A D | usb_freebsd_loader.h | 58 #define USB_TD_GET_PROC(td) (td)->td_proc 59 #define USB_PROC_GET_GID(td) (td)->p_pgid
|
H A D | usb_freebsd.h | 59 #define USB_TD_GET_PROC(td) (td)->td_proc 60 #define USB_PROC_GET_GID(td) (td)->p_pgid
|
H A D | usb_dev.c | 872 usb_open(struct cdev *dev, int fflags, int devtype, struct thread *td) argument 1010 struct thread *td) 1029 f->async_p = USB_TD_GET_PROC(td); 1057 usb_ioctl(struct cdev *dev, u_long cmd, caddr_t addr, int fflag, struct thread* td) argument 1087 err = usb_ioctl_f_sub(f, cmd, addr, td); 1091 err = usb_ioctl_f_sub(f, cmd, addr, td); 1300 usb_poll(struct cdev* dev, int events, struct thread* td) argument 1351 selrecord(td, &f->selinfo); 1390 selrecord(td, &f->selinfo); 1670 struct thread *td) 1009 usb_ioctl_f_sub(struct usb_fifo *f, u_long cmd, void *addr, struct thread *td) argument 1669 usb_static_ioctl(struct cdev *dev, u_long cmd, caddr_t data, int fflag, struct thread *td) argument [all...] |
/freebsd-11-stable/usr.bin/clang/llvm-objcopy/ |
H A D | Makefile | 30 ${hdr}.inc: ${LLVM_BASE}/${SRCDIR}/${hdr}.td 33 -d ${.TARGET}.d -o ${.TARGET} ${LLVM_BASE}/${SRCDIR}/${hdr}.td
|
/freebsd-11-stable/lib/clang/libllvm/ |
H A D | Makefile | 1630 llvm/IR/Attributes.inc: ${LLVM_SRCS}/include/llvm/IR/Attributes.td 1633 ${LLVM_SRCS}/include/llvm/IR/Attributes.td 1636 llvm/IR/IntrinsicEnums.inc: ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td 1639 ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td 1642 llvm/IR/IntrinsicImpl.inc: ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td 1645 ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td 1652 llvm/IR/Intrinsics${arch:H}.h: ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td 1655 ${LLVM_SRCS}/include/llvm/IR/Intrinsics.td 1659 AttributesCompatFunc.inc: ${LLVM_SRCS}/lib/IR/AttributesCompatFunc.td 1662 ${LLVM_SRCS}/lib/IR/AttributesCompatFunc.td [all...] |
/freebsd-11-stable/lib/clang/libclang/ |
H A D | Makefile | 701 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td 704 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td 708 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td 711 ${CLANG_SRCS}/include/clang/AST/PropertiesBase.td 715 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td 718 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td 722 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td 725 ${CLANG_SRCS}/include/clang/AST/TypeProperties.td 728 clang/AST/AttrImpl.inc: ${CLANG_SRCS}/include/clang/Basic/Attr.td 731 ${CLANG_SRCS}/include/clang/Basic/Attr.td [all...] |
/freebsd-11-stable/lib/clang/headers/ |
H A D | Makefile | 162 arm_fp16.h: ${CLANG_SRCS}/include/clang/Basic/arm_fp16.td 165 -o ${.TARGET} ${CLANG_SRCS}/include/clang/Basic/arm_fp16.td 167 arm_mve.h: ${CLANG_SRCS}/include/clang/Basic/arm_mve.td 170 -o ${.TARGET} ${CLANG_SRCS}/include/clang/Basic/arm_mve.td 172 arm_neon.h: ${CLANG_SRCS}/include/clang/Basic/arm_neon.td 175 -o ${.TARGET} ${CLANG_SRCS}/include/clang/Basic/arm_neon.td
|