From owner-svn-src-user@freebsd.org Fri Dec 15 23:35:21 2017 Return-Path: Delivered-To: svn-src-user@mailman.ysv.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by mailman.ysv.freebsd.org (Postfix) with ESMTP id BEE4DE8F58B for ; Fri, 15 Dec 2017 23:35:21 +0000 (UTC) (envelope-from jeff@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 86EED69D0F; Fri, 15 Dec 2017 23:35:21 +0000 (UTC) (envelope-from jeff@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id vBFNZKpB049613; Fri, 15 Dec 2017 23:35:20 GMT (envelope-from jeff@FreeBSD.org) Received: (from jeff@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id vBFNZKxj049606; Fri, 15 Dec 2017 23:35:20 GMT (envelope-from jeff@FreeBSD.org) Message-Id: <201712152335.vBFNZKxj049606@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: jeff set sender to jeff@FreeBSD.org using -f From: Jeff Roberson Date: Fri, 15 Dec 2017 23:35:20 +0000 (UTC) To: src-committers@freebsd.org, svn-src-user@freebsd.org Subject: svn commit: r326889 - in user/jeff/numa: lib/libc/sys sys/compat/freebsd32 sys/conf sys/kern sys/sys sys/vm usr.bin/cpuset X-SVN-Group: user X-SVN-Commit-Author: jeff X-SVN-Commit-Paths: in user/jeff/numa: lib/libc/sys sys/compat/freebsd32 sys/conf sys/kern sys/sys sys/vm usr.bin/cpuset X-SVN-Commit-Revision: 326889 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-user@freebsd.org X-Mailman-Version: 2.1.25 Precedence: list List-Id: "SVN commit messages for the experimental " user" src tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 Dec 2017 23:35:21 -0000 Author: jeff Date: Fri Dec 15 23:35:20 2017 New Revision: 326889 URL: https://svnweb.freebsd.org/changeset/base/326889 Log: First cut of NUMA domain integration into cpuset. Added: user/jeff/numa/sys/sys/_domainset.h (contents, props changed) user/jeff/numa/sys/sys/domainset.h (contents, props changed) user/jeff/numa/sys/vm/vm_domainset.c (contents, props changed) user/jeff/numa/sys/vm/vm_domainset.h (contents, props changed) Modified: user/jeff/numa/lib/libc/sys/Symbol.map user/jeff/numa/sys/compat/freebsd32/syscalls.master user/jeff/numa/sys/conf/files user/jeff/numa/sys/kern/init_main.c user/jeff/numa/sys/kern/init_sysent.c user/jeff/numa/sys/kern/kern_cpuset.c user/jeff/numa/sys/kern/kern_exit.c user/jeff/numa/sys/kern/kern_fork.c user/jeff/numa/sys/kern/kern_numa.c user/jeff/numa/sys/kern/kern_thr.c user/jeff/numa/sys/kern/kern_thread.c user/jeff/numa/sys/kern/makesyscalls.sh user/jeff/numa/sys/kern/sched_4bsd.c user/jeff/numa/sys/kern/sched_ule.c user/jeff/numa/sys/kern/syscalls.c user/jeff/numa/sys/kern/syscalls.master user/jeff/numa/sys/kern/systrace_args.c user/jeff/numa/sys/sys/cpuset.h user/jeff/numa/sys/sys/param.h user/jeff/numa/sys/sys/proc.h user/jeff/numa/sys/sys/syscall.h user/jeff/numa/sys/sys/syscall.mk user/jeff/numa/sys/sys/syscallsubr.h user/jeff/numa/sys/sys/sysproto.h user/jeff/numa/sys/vm/uma_core.c user/jeff/numa/sys/vm/vm_fault.c user/jeff/numa/sys/vm/vm_kern.c user/jeff/numa/sys/vm/vm_object.c user/jeff/numa/sys/vm/vm_object.h user/jeff/numa/sys/vm/vm_page.c user/jeff/numa/sys/vm/vm_phys.c user/jeff/numa/usr.bin/cpuset/cpuset.c Modified: user/jeff/numa/lib/libc/sys/Symbol.map ============================================================================== --- user/jeff/numa/lib/libc/sys/Symbol.map Fri Dec 15 23:19:49 2017 (r326888) +++ user/jeff/numa/lib/libc/sys/Symbol.map Fri Dec 15 23:35:20 2017 (r326889) @@ -398,6 +398,8 @@ FBSD_1.5 { mknodat; stat; statfs; + cpuset_getdomain; + cpuset_setdomain; }; FBSDprivate_1.0 { @@ -1022,4 +1024,8 @@ FBSDprivate_1.0 { gssd_syscall; __libc_interposing_slot; __libc_sigwait; + _cpuset_getdomain; + __sys_cpuset_getdomain; + _cpuset_setdomain; + __sys_cpuset_setdomain; }; Modified: user/jeff/numa/sys/compat/freebsd32/syscalls.master ============================================================================== --- user/jeff/numa/sys/compat/freebsd32/syscalls.master Fri Dec 15 23:19:49 2017 (r326888) +++ user/jeff/numa/sys/compat/freebsd32/syscalls.master Fri Dec 15 23:35:20 2017 (r326889) @@ -1119,4 +1119,13 @@ struct kevent32 *eventlist, \ int nevents, \ const struct timespec32 *timeout); } +561 AUE_NULL STD { int cpuset_getdomain(cpulevel_t level, \ + cpuwhich_t which, id_t id, \ + size_t domainsetsize, domainset_t *mask, \ + int *policy); } +562 AUE_NULL STD { int cpuset_setdomain(cpulevel_t level, \ + cpuwhich_t which, id_t id, \ + size_t domainsetsize, domainset_t *mask, \ + int policy); } + ; vim: syntax=off Modified: user/jeff/numa/sys/conf/files ============================================================================== --- user/jeff/numa/sys/conf/files Fri Dec 15 23:19:49 2017 (r326888) +++ user/jeff/numa/sys/conf/files Fri Dec 15 23:35:20 2017 (r326889) @@ -4816,7 +4816,7 @@ vm/swap_pager.c standard vm/uma_core.c standard vm/uma_dbg.c standard vm/memguard.c optional DEBUG_MEMGUARD -vm/vm_domain.c standard +vm/vm_domainset.c standard vm/vm_fault.c standard vm/vm_glue.c standard vm/vm_init.c standard Modified: user/jeff/numa/sys/kern/init_main.c ============================================================================== --- user/jeff/numa/sys/kern/init_main.c Fri Dec 15 23:19:49 2017 (r326888) +++ user/jeff/numa/sys/kern/init_main.c Fri Dec 15 23:35:20 2017 (r326889) @@ -493,10 +493,7 @@ proc0_init(void *dummy __unused) td->td_flags = TDF_INMEM; td->td_pflags = TDP_KTHREAD; td->td_cpuset = cpuset_thread0(); - vm_domain_policy_init(&td->td_vm_dom_policy); - vm_domain_policy_set(&td->td_vm_dom_policy, VM_POLICY_NONE, -1); - vm_domain_policy_init(&p->p_vm_dom_policy); - vm_domain_policy_set(&p->p_vm_dom_policy, VM_POLICY_NONE, -1); + td->td_domain.dr_policy = td->td_cpuset->cs_domain; prison0_init(); p->p_peers = 0; p->p_leader = p; Modified: user/jeff/numa/sys/kern/init_sysent.c ============================================================================== --- user/jeff/numa/sys/kern/init_sysent.c Fri Dec 15 23:19:49 2017 (r326888) +++ user/jeff/numa/sys/kern/init_sysent.c Fri Dec 15 23:35:20 2017 (r326889) @@ -612,4 +612,6 @@ struct sysent sysent[] = { { AS(fhstatfs_args), (sy_call_t *)sys_fhstatfs, AUE_FHSTATFS, NULL, 0, 0, 0, SY_THR_STATIC }, /* 558 = fhstatfs */ { AS(mknodat_args), (sy_call_t *)sys_mknodat, AUE_MKNODAT, NULL, 0, 0, SYF_CAPENABLED, SY_THR_STATIC }, /* 559 = mknodat */ { AS(kevent_args), (sy_call_t *)sys_kevent, AUE_KEVENT, NULL, 0, 0, SYF_CAPENABLED, SY_THR_STATIC }, /* 560 = kevent */ + { AS(cpuset_getdomain_args), (sy_call_t *)sys_cpuset_getdomain, AUE_NULL, NULL, 0, 0, 0, SY_THR_STATIC }, /* 561 = cpuset_getdomain */ + { AS(cpuset_setdomain_args), (sy_call_t *)sys_cpuset_setdomain, AUE_NULL, NULL, 0, 0, 0, SY_THR_STATIC }, /* 562 = cpuset_setdomain */ }; Modified: user/jeff/numa/sys/kern/kern_cpuset.c ============================================================================== --- user/jeff/numa/sys/kern/kern_cpuset.c Fri Dec 15 23:19:49 2017 (r326888) +++ user/jeff/numa/sys/kern/kern_cpuset.c Fri Dec 15 23:35:20 2017 (r326889) @@ -51,17 +51,21 @@ __FBSDID("$FreeBSD$"); #include #include #include +#include #include #include #include #include #include #include +#include #include #include +#include #include #include +#include #ifdef DDB #include @@ -109,8 +113,10 @@ __FBSDID("$FreeBSD$"); * getaffinity call using (CPU_LEVEL_CPUSET, CPU_WHICH_PID, -1, ...). */ static uma_zone_t cpuset_zone; +static uma_zone_t domainset_zone; static struct mtx cpuset_lock; static struct setlist cpuset_ids; +static struct domainlist cpuset_domains; static struct unrhdr *cpuset_unr; static struct cpuset *cpuset_zero, *cpuset_default; @@ -122,6 +128,30 @@ cpuset_t *cpuset_root; cpuset_t cpuset_domain[MAXMEMDOM]; /* + * Find the first non-anonymous set starting from 'set'. + */ +static struct cpuset * +cpuset_getbase(struct cpuset *set) +{ + + if (set->cs_id == CPUSET_INVALID) + set = set->cs_parent; + return (set); +} + +/* + * Walks up the tree from 'set' to find the root. + */ +static struct cpuset * +cpuset_getroot(struct cpuset *set) +{ + + while ((set->cs_flags & CPU_SET_ROOT) == 0 && set->cs_parent != NULL) + set = set->cs_parent; + return (set); +} + +/* * Acquire a reference to a cpuset, all pointers must be tracked with refs. */ struct cpuset * @@ -140,12 +170,7 @@ static struct cpuset * cpuset_refroot(struct cpuset *set) { - for (; set->cs_parent != NULL; set = set->cs_parent) - if (set->cs_flags & CPU_SET_ROOT) - break; - cpuset_ref(set); - - return (set); + return cpuset_ref(cpuset_getroot(set)); } /* @@ -157,11 +182,7 @@ static struct cpuset * cpuset_refbase(struct cpuset *set) { - if (set->cs_id == CPUSET_INVALID) - set = set->cs_parent; - cpuset_ref(set); - - return (set); + return cpuset_ref(cpuset_getbase(set)); } /* @@ -257,17 +278,25 @@ cpuset_lookup(cpusetid_t setid, struct thread *td) * will have no valid cpu based on restrictions from the parent. */ static int -_cpuset_create(struct cpuset *set, struct cpuset *parent, const cpuset_t *mask, - cpusetid_t id) +_cpuset_create(struct cpuset *set, struct cpuset *parent, + const cpuset_t *mask, struct domainset *domain, cpusetid_t id) { + if (domain == NULL) + domain = parent->cs_domain; + if (mask == NULL) + mask = &parent->cs_mask; if (!CPU_OVERLAP(&parent->cs_mask, mask)) return (EDEADLK); + /* The domain must be prepared ahead of time. */ + if (!DOMAINSET_SUBSET(&parent->cs_domain->ds_mask, &domain->ds_mask)) + return (EDEADLK); CPU_COPY(mask, &set->cs_mask); LIST_INIT(&set->cs_children); refcount_init(&set->cs_ref, 1); set->cs_flags = 0; mtx_lock_spin(&cpuset_lock); + set->cs_domain = domain; CPU_AND(&set->cs_mask, &parent->cs_mask); set->cs_id = id; set->cs_parent = cpuset_ref(parent); @@ -294,8 +323,8 @@ cpuset_create(struct cpuset **setp, struct cpuset *par id = alloc_unr(cpuset_unr); if (id == -1) return (ENFILE); - *setp = set = uma_zalloc(cpuset_zone, M_WAITOK); - error = _cpuset_create(set, parent, mask, id); + *setp = set = uma_zalloc(cpuset_zone, M_WAITOK | M_ZERO); + error = _cpuset_create(set, parent, mask, NULL, id); if (error == 0) return (0); free_unr(cpuset_unr, id); @@ -304,7 +333,187 @@ cpuset_create(struct cpuset **setp, struct cpuset *par return (error); } +static void +cpuset_freelist_add(struct setlist *list, int count) +{ + struct cpuset *set; + int i; + + for (i = 0; i < count; i++) { + set = uma_zalloc(cpuset_zone, M_ZERO | M_WAITOK); + LIST_INSERT_HEAD(list, set, cs_link); + } +} + +static void +cpuset_freelist_init(struct setlist *list, int count) +{ + + LIST_INIT(list); + cpuset_freelist_add(list, count); +} + +static void +cpuset_freelist_free(struct setlist *list) +{ + struct cpuset *set; + + while ((set = LIST_FIRST(list)) != NULL) { + LIST_REMOVE(set, cs_link); + uma_zfree(cpuset_zone, set); + } +} + +static void +domainset_freelist_add(struct domainlist *list, int count) +{ + struct domainset *set; + int i; + + for (i = 0; i < count; i++) { + set = uma_zalloc(domainset_zone, M_ZERO | M_WAITOK); + LIST_INSERT_HEAD(list, set, ds_link); + } +} + +static void +domainset_freelist_init(struct domainlist *list, int count) +{ + + LIST_INIT(list); + domainset_freelist_add(list, count); +} + +static void +domainset_freelist_free(struct domainlist *list) +{ + struct domainset *set; + + while ((set = LIST_FIRST(list)) != NULL) { + LIST_REMOVE(set, ds_link); + uma_zfree(domainset_zone, set); + } +} + +/* Copy a domainset preserving mask and policy. */ +static void +domainset_copy(const struct domainset *from, struct domainset *to) +{ + + DOMAINSET_COPY(&from->ds_mask, &to->ds_mask); + to->ds_policy = from->ds_policy; +} + +/* Return 1 if mask and policy are equal, otherwise 0. */ +static int +domainset_equal(const struct domainset *one, const struct domainset *two) +{ + + return (DOMAINSET_CMP(&one->ds_mask, &two->ds_mask) == 0 && + one->ds_policy == two->ds_policy); +} + /* + * Lookup or create a domainset. The key is provided in ds_mask and + * ds_policy. If the domainset does not yet exist the storage in + * 'domain' is used to insert. Otherwise this storage is freed to the + * domainset_zone and the existing domainset is returned. + */ +static struct domainset * +_domainset_create(struct domainset *domain, struct domainlist *freelist) +{ + struct domainset *ndomain; + + mtx_lock_spin(&cpuset_lock); + LIST_FOREACH(ndomain, &cpuset_domains, ds_link) + if (domainset_equal(ndomain, domain)) + break; + /* + * If the domain does not yet exist we insert it and initialize + * various iteration helpers which are not part of the key. + */ + if (ndomain == NULL) { + LIST_INSERT_HEAD(&cpuset_domains, domain, ds_link); + domain->ds_cnt = DOMAINSET_COUNT(&domain->ds_mask); + domain->ds_max = DOMAINSET_FLS(&domain->ds_mask) + 1; + } + mtx_unlock_spin(&cpuset_lock); + if (ndomain == NULL) + return (domain); + if (freelist != NULL) + LIST_INSERT_HEAD(freelist, domain, ds_link); + else + uma_zfree(domainset_zone, domain); + return (ndomain); + +} + +/* + * Create or lookup a domainset based on the key held in 'domain'. + */ +static struct domainset * +domainset_create(const struct domainset *domain) +{ + struct domainset *ndomain; + + ndomain = uma_zalloc(domainset_zone, M_WAITOK | M_ZERO); + domainset_copy(domain, ndomain); + return _domainset_create(ndomain, NULL); +} + +/* + * Update thread domainset pointers. + */ +static void +domainset_notify(void) +{ + struct thread *td; + struct proc *p; + + sx_slock(&allproc_lock); + FOREACH_PROC_IN_SYSTEM(p) { + PROC_LOCK(p); + if (p->p_state == PRS_NEW) { + PROC_UNLOCK(p); + continue; + } + FOREACH_THREAD_IN_PROC(p, td) { + thread_lock(td); + td->td_domain.dr_policy = td->td_cpuset->cs_domain; + thread_unlock(td); + } + PROC_UNLOCK(p); + } + sx_sunlock(&allproc_lock); + kernel_object->domain.dr_policy = cpuset_default->cs_domain; +} + +/* + * Create a new set that is a subset of a parent. + */ +static struct domainset * +domainset_shadow(const struct domainset *pdomain, + const struct domainset *domain, struct domainlist *freelist) +{ + struct domainset *ndomain; + + ndomain = LIST_FIRST(freelist); + LIST_REMOVE(ndomain, ds_link); + + /* + * Initialize the key from the request. + */ + domainset_copy(domain, ndomain); + + /* + * Restrict the key by the parent. + */ + DOMAINSET_AND(&ndomain->ds_mask, &pdomain->ds_mask); + + return _domainset_create(ndomain, freelist); +} + +/* * Recursively check for errors that would occur from applying mask to * the tree of sets starting at 'set'. Checks for sets that would become * empty as well as RDONLY flags. @@ -376,10 +585,12 @@ cpuset_modify(struct cpuset *set, cpuset_t *mask) * Verify that we have access to this set of * cpus. */ - root = set->cs_parent; - if (root && !CPU_SUBSET(&root->cs_mask, mask)) - return (EINVAL); + root = cpuset_getroot(set); mtx_lock_spin(&cpuset_lock); + if (root && !CPU_SUBSET(&root->cs_mask, mask)) { + error = EINVAL; + goto out; + } error = cpuset_testupdate(set, mask, 0); if (error) goto out; @@ -392,6 +603,136 @@ out: } /* + * Recursively check for errors that would occur from applying mask to + * the tree of sets starting at 'set'. Checks for sets that would become + * empty as well as RDONLY flags. + */ +static int +cpuset_testupdate_domain(struct cpuset *set, struct domainset *dset, + struct domainset *orig, int *count, int check_mask) +{ + struct cpuset *nset; + struct domainset *domain; + struct domainset newset; + int error; + + mtx_assert(&cpuset_lock, MA_OWNED); + if (set->cs_flags & CPU_SET_RDONLY) + return (EPERM); + domain = set->cs_domain; + domainset_copy(domain, &newset); + if (!domainset_equal(domain, orig)) { + if (!DOMAINSET_OVERLAP(&domain->ds_mask, &dset->ds_mask)) + return (EDEADLK); + DOMAINSET_AND(&newset.ds_mask, &dset->ds_mask); + /* Count the number of domains that are changing. */ + (*count)++; + } + error = 0; + LIST_FOREACH(nset, &set->cs_children, cs_siblings) + if ((error = cpuset_testupdate_domain(nset, &newset, domain, + count, 1)) != 0) + break; + return (error); +} + +/* + * Applies the mask 'mask' without checking for empty sets or permissions. + */ +static void +cpuset_update_domain(struct cpuset *set, struct domainset *domain, + struct domainset *orig, struct domainlist *domains) +{ + struct cpuset *nset; + + mtx_assert(&cpuset_lock, MA_OWNED); + /* + * If this domainset has changed from the parent we must calculate + * a new set. Otherwise it simply inherits from the parent. When + * we inherit from the parent we get a new mask and policy. If the + * set is modified from the parent we keep the policy and only + * update the mask. + */ + if (set->cs_domain != orig) { + orig = set->cs_domain; + set->cs_domain = domainset_shadow(domain, orig, domains); + } else + set->cs_domain = domain; + LIST_FOREACH(nset, &set->cs_children, cs_siblings) + cpuset_update_domain(nset, set->cs_domain, orig, domains); + + return; +} + +/* + * Modify the set 'set' to use a copy the domainset provided. Apply this new + * mask to restrict all children in the tree. Checks for validity before + * applying the changes. + */ +static int +cpuset_modify_domain(struct cpuset *set, struct domainset *domain) +{ + struct domainlist domains; + struct domainset temp; + struct domainset *dset; + struct cpuset *root; + int ndomains, needed; + int error; + + error = priv_check(curthread, PRIV_SCHED_CPUSET); + if (error) + return (error); + /* + * In case we are called from within the jail + * we do not allow modifying the dedicated root + * cpuset of the jail but may still allow to + * change child sets. + */ + if (jailed(curthread->td_ucred) && + set->cs_flags & CPU_SET_ROOT) + return (EPERM); + domainset_freelist_init(&domains, 0); + domain = domainset_create(domain); + ndomains = needed = 0; + do { + if (ndomains < needed) { + domainset_freelist_add(&domains, needed - ndomains); + ndomains = needed; + } + root = cpuset_getroot(set); + mtx_lock_spin(&cpuset_lock); + dset = root->cs_domain; + /* + * Verify that we have access to this set of domains. + */ + if (root && + !DOMAINSET_SUBSET(&dset->ds_mask, &domain->ds_mask)) { + error = EINVAL; + goto out; + } + /* + * Determine whether we can apply this set of domains and + * how many new domain structures it will require. + */ + domainset_copy(domain, &temp); + needed = 0; + error = cpuset_testupdate_domain(set, &temp, set->cs_domain, + &needed, 0); + if (error) + goto out; + } while (ndomains < needed); + dset = set->cs_domain; + cpuset_update_domain(set, domain, dset, &domains); +out: + mtx_unlock_spin(&cpuset_lock); + domainset_freelist_free(&domains); + if (error == 0) + domainset_notify(); + + return (error); +} + +/* * Resolve the 'which' parameter of several cpuset apis. * * For WHICH_PID and WHICH_TID return a locked proc and valid proc/tid. Also @@ -481,44 +822,204 @@ cpuset_which(cpuwhich_t which, id_t id, struct proc ** return (0); } +static int +cpuset_testshadow(struct cpuset *set, const cpuset_t *mask, + const struct domainset *domain) +{ + struct cpuset *parent; + struct domainset *dset; + + parent = cpuset_getbase(set); + /* + * If we are restricting a cpu mask it must be a subset of the + * parent or invalid CPUs have been specified. + */ + if (mask != NULL && !CPU_SUBSET(&parent->cs_mask, mask)) + return (EINVAL); + + /* + * If we are restricting a domain mask it must be a subset of the + * parent or invalid domains have been specified. + */ + dset = parent->cs_domain; + if (domain != NULL && + !DOMAINSET_SUBSET(&dset->ds_mask, &domain->ds_mask)) + return (EINVAL); + + return (0); +} + /* * Create an anonymous set with the provided mask in the space provided by - * 'fset'. If the passed in set is anonymous we use its parent otherwise + * 'nset'. If the passed in set is anonymous we use its parent otherwise * the new set is a child of 'set'. */ static int -cpuset_shadow(struct cpuset *set, struct cpuset *fset, const cpuset_t *mask) +cpuset_shadow(struct cpuset *set, struct cpuset **nsetp, + const cpuset_t *mask, const struct domainset *domain, + struct setlist *cpusets, struct domainlist *domains) { struct cpuset *parent; + struct cpuset *nset; + struct domainset *dset; + struct domainset *d; + int error; - if (set->cs_id == CPUSET_INVALID) - parent = set->cs_parent; + error = cpuset_testshadow(set, mask, domain); + if (error) + return (error); + + parent = cpuset_getbase(set); + dset = parent->cs_domain; + if (mask == NULL) + mask = &set->cs_mask; + if (domain != NULL) + d = domainset_shadow(dset, domain, domains); else - parent = set; - if (!CPU_SUBSET(&parent->cs_mask, mask)) + d = set->cs_domain; + nset = LIST_FIRST(cpusets); + error = _cpuset_create(nset, parent, mask, d, CPUSET_INVALID); + if (error == 0) { + LIST_REMOVE(nset, cs_link); + *nsetp = nset; + } + return (error); +} + +static struct cpuset * +cpuset_update_thread(struct thread *td, struct cpuset *nset) +{ + struct cpuset *tdset; + + tdset = td->td_cpuset; + td->td_cpuset = nset; + td->td_domain.dr_policy = nset->cs_domain; + sched_affinity(td); + + return (tdset); +} + +static int +cpuset_setproc_test_maskthread(struct cpuset *tdset, cpuset_t *mask, + struct domainset *domain) +{ + struct cpuset *parent; + + parent = cpuset_getbase(tdset); + if (mask == NULL) + mask = &tdset->cs_mask; + if (domain == NULL) + domain = tdset->cs_domain; + return cpuset_testshadow(parent, mask, domain); +} + +static int +cpuset_setproc_maskthread(struct cpuset *tdset, cpuset_t *mask, + struct domainset *domain, struct cpuset **nsetp, + struct setlist *freelist, struct domainlist *domainlist) +{ + struct cpuset *parent; + + parent = cpuset_getbase(tdset); + if (mask == NULL) + mask = &tdset->cs_mask; + if (domain == NULL) + domain = tdset->cs_domain; + return cpuset_shadow(parent, nsetp, mask, domain, freelist, + domainlist); +} + +static int +cpuset_setproc_setthread_mask(struct cpuset *tdset, struct cpuset *set, + cpuset_t *mask, struct domainset *domain) +{ + struct cpuset *parent; + + parent = cpuset_getbase(tdset); + + /* + * If the thread restricted its mask then apply that same + * restriction to the new set, otherwise take it wholesale. + */ + if (CPU_CMP(&tdset->cs_mask, &parent->cs_mask) != 0) { + CPU_COPY(&tdset->cs_mask, mask); + CPU_AND(mask, &set->cs_mask); + } else + CPU_COPY(&set->cs_mask, mask); + + /* + * If the thread restricted the domain then we apply the + * restriction to the new set but retain the policy. + */ + if (tdset->cs_domain != parent->cs_domain) { + domainset_copy(tdset->cs_domain, domain); + DOMAINSET_AND(&domain->ds_mask, &set->cs_domain->ds_mask); + } else + domainset_copy(set->cs_domain, domain); + + if (CPU_EMPTY(mask) || DOMAINSET_EMPTY(&domain->ds_mask)) return (EDEADLK); - return (_cpuset_create(fset, parent, mask, CPUSET_INVALID)); + + return (0); } +static int +cpuset_setproc_test_setthread(struct cpuset *tdset, struct cpuset *set) +{ + struct domainset domain; + cpuset_t mask; + + if (tdset->cs_id != CPUSET_INVALID) + return (0); + return cpuset_setproc_setthread_mask(tdset, set, &mask, &domain); +} + +static int +cpuset_setproc_setthread(struct cpuset *tdset, struct cpuset *set, + struct cpuset **nsetp, struct setlist *freelist, + struct domainlist *domainlist) +{ + struct domainset domain; + cpuset_t mask; + int error; + + /* + * If we're replacing on a thread that has not constrained the + * original set we can simply accept the new set. + */ + if (tdset->cs_id != CPUSET_INVALID) { + *nsetp = cpuset_ref(set); + return (0); + } + error = cpuset_setproc_setthread_mask(tdset, set, &mask, &domain); + if (error) + return (error); + + return cpuset_shadow(tdset, nsetp, &mask, &domain, freelist, + domainlist); +} + /* - * Handle two cases for replacing the base set or mask of an entire process. + * Handle three cases for updating an entire process. * - * 1) Set is non-null and mask is null. This reparents all anonymous sets - * to the provided set and replaces all non-anonymous td_cpusets with the - * provided set. - * 2) Mask is non-null and set is null. This replaces or creates anonymous - * sets for every thread with the existing base as a parent. + * 1) Set is non-null. This reparents all anonymous sets to the provided + * set and replaces all non-anonymous td_cpusets with the provided set. + * 2) Mask is non-null. This replaces or creates anonymous sets for every + * thread with the existing base as a parent. + * 3) domain is non-null. This creates anonymous sets for every thread + * and replaces the domain set. * * This is overly complicated because we can't allocate while holding a * spinlock and spinlocks must be held while changing and examining thread * state. */ static int -cpuset_setproc(pid_t pid, struct cpuset *set, cpuset_t *mask) +cpuset_setproc(pid_t pid, struct cpuset *set, cpuset_t *mask, + struct domainset *domain) { struct setlist freelist; struct setlist droplist; - struct cpuset *tdset; + struct domainlist domainlist; struct cpuset *nset; struct thread *td; struct proc *p; @@ -533,7 +1034,9 @@ cpuset_setproc(pid_t pid, struct cpuset *set, cpuset_t * 2) If enough cpusets have not been allocated release the locks and * allocate them. Loop. */ - LIST_INIT(&freelist); + cpuset_freelist_init(&freelist, 1); + domainset_freelist_init(&domainlist, 1); + nfree = 1; LIST_INIT(&droplist); nfree = 0; for (;;) { @@ -544,39 +1047,27 @@ cpuset_setproc(pid_t pid, struct cpuset *set, cpuset_t break; threads = p->p_numthreads; PROC_UNLOCK(p); - for (; nfree < threads; nfree++) { - nset = uma_zalloc(cpuset_zone, M_WAITOK); - LIST_INSERT_HEAD(&freelist, nset, cs_link); + if (nfree < threads) { + cpuset_freelist_add(&freelist, threads - nfree); + domainset_freelist_add(&domainlist, threads - nfree); + nfree = threads; } } PROC_LOCK_ASSERT(p, MA_OWNED); /* * Now that the appropriate locks are held and we have enough cpusets, - * make sure the operation will succeed before applying changes. The + * make sure the operation will succeed before applying changes. The * proc lock prevents td_cpuset from changing between calls. */ error = 0; FOREACH_THREAD_IN_PROC(p, td) { thread_lock(td); - tdset = td->td_cpuset; - /* - * Verify that a new mask doesn't specify cpus outside of - * the set the thread is a member of. - */ - if (mask) { - if (tdset->cs_id == CPUSET_INVALID) - tdset = tdset->cs_parent; - if (!CPU_SUBSET(&tdset->cs_mask, mask)) - error = EDEADLK; - /* - * Verify that a new set won't leave an existing thread - * mask without a cpu to run on. It can, however, restrict - * the set. - */ - } else if (tdset->cs_id == CPUSET_INVALID) { - if (!CPU_OVERLAP(&set->cs_mask, &tdset->cs_mask)) - error = EDEADLK; - } + if (set != NULL) + error = cpuset_setproc_test_setthread(td->td_cpuset, + set); + else + error = cpuset_setproc_test_maskthread(td->td_cpuset, + mask, domain); thread_unlock(td); if (error) goto unlock_out; @@ -588,33 +1079,17 @@ cpuset_setproc(pid_t pid, struct cpuset *set, cpuset_t */ FOREACH_THREAD_IN_PROC(p, td) { thread_lock(td); - /* - * If we presently have an anonymous set or are applying a - * mask we must create an anonymous shadow set. That is - * either parented to our existing base or the supplied set. - * - * If we have a base set with no anonymous shadow we simply - * replace it outright. - */ - tdset = td->td_cpuset; - if (tdset->cs_id == CPUSET_INVALID || mask) { - nset = LIST_FIRST(&freelist); - LIST_REMOVE(nset, cs_link); - if (mask) - error = cpuset_shadow(tdset, nset, mask); - else - error = _cpuset_create(nset, set, - &tdset->cs_mask, CPUSET_INVALID); - if (error) { - LIST_INSERT_HEAD(&freelist, nset, cs_link); - thread_unlock(td); - break; - } - } else - nset = cpuset_ref(set); - cpuset_rel_defer(&droplist, tdset); - td->td_cpuset = nset; - sched_affinity(td); + if (set != NULL) + error = cpuset_setproc_setthread(td->td_cpuset, set, + &nset, &freelist, &domainlist); + else + error = cpuset_setproc_maskthread(td->td_cpuset, mask, + domain, &nset, &freelist, &domainlist); + if (error) { + thread_unlock(td); + break; + } + cpuset_rel_defer(&droplist, cpuset_update_thread(td, nset)); thread_unlock(td); } unlock_out: @@ -622,10 +1097,8 @@ unlock_out: out: while ((nset = LIST_FIRST(&droplist)) != NULL) cpuset_rel_complete(nset); - while ((nset = LIST_FIRST(&freelist)) != NULL) { - LIST_REMOVE(nset, cs_link); - uma_zfree(cpuset_zone, nset); - } + cpuset_freelist_free(&freelist); + domainset_freelist_free(&domainlist); return (error); } @@ -690,46 +1163,57 @@ cpusetobj_strscan(cpuset_t *set, const char *buf) } /* - * Apply an anonymous mask to a single thread. + * Apply an anonymous mask or a domain to a single thread. */ -int -cpuset_setthread(lwpid_t id, cpuset_t *mask) +static int +_cpuset_setthread(lwpid_t id, cpuset_t *mask, struct domainset *domain) { + struct setlist cpusets; + struct domainlist domainlist; struct cpuset *nset; struct cpuset *set; struct thread *td; struct proc *p; int error; - nset = uma_zalloc(cpuset_zone, M_WAITOK); + cpuset_freelist_init(&cpusets, 1); + domainset_freelist_init(&domainlist, domain != NULL); error = cpuset_which(CPU_WHICH_TID, id, &p, &td, &set); if (error) goto out; set = NULL; thread_lock(td); - error = cpuset_shadow(td->td_cpuset, nset, mask); - if (error == 0) { - set = td->td_cpuset; - td->td_cpuset = nset; - sched_affinity(td); - nset = NULL; - } + error = cpuset_shadow(td->td_cpuset, &nset, mask, domain, + &cpusets, &domainlist); + if (error == 0) + set = cpuset_update_thread(td, nset); thread_unlock(td); PROC_UNLOCK(p); if (set) cpuset_rel(set); out: - if (nset) - uma_zfree(cpuset_zone, nset); + cpuset_freelist_free(&cpusets); + domainset_freelist_free(&domainlist); return (error); } /* + * Apply an anonymous mask to a single thread. + */ +int +cpuset_setthread(lwpid_t id, cpuset_t *mask) +{ + + return _cpuset_setthread(id, mask, NULL); +} + +/* * Apply new cpumask to the ithread. */ int cpuset_setithread(lwpid_t id, int cpu) { + struct setlist cpusets; struct cpuset *nset, *rset; struct cpuset *parent, *old_set; struct thread *td; @@ -738,8 +1222,8 @@ cpuset_setithread(lwpid_t id, int cpu) cpuset_t mask; int error; - nset = uma_zalloc(cpuset_zone, M_WAITOK); - rset = uma_zalloc(cpuset_zone, M_WAITOK); + cpuset_freelist_init(&cpusets, 1); + rset = uma_zalloc(cpuset_zone, M_WAITOK | M_ZERO); cs_id = CPUSET_INVALID; CPU_ZERO(&mask); @@ -756,13 +1240,15 @@ cpuset_setithread(lwpid_t id, int cpu) old_set = td->td_cpuset; if (cpu == NOCPU) { + nset = LIST_FIRST(&cpusets); + LIST_REMOVE(nset, cs_link); /* * roll back to default set. We're not using cpuset_shadow() * here because we can fail CPU_SUBSET() check. This can happen * if default set does not contain all CPUs. */ - error = _cpuset_create(nset, cpuset_default, &mask, + error = _cpuset_create(nset, cpuset_default, &mask, NULL, CPUSET_INVALID); goto applyset; @@ -779,7 +1265,7 @@ cpuset_setithread(lwpid_t id, int cpu) * with any mask. */ error = _cpuset_create(rset, cpuset_zero, - &cpuset_zero->cs_mask, cs_id); + &cpuset_zero->cs_mask, NULL, cs_id); if (error != 0) { PROC_UNLOCK(p); goto out; @@ -794,22 +1280,19 @@ cpuset_setithread(lwpid_t id, int cpu) old_set = NULL; } - error = cpuset_shadow(parent, nset, &mask); + error = cpuset_shadow(parent, &nset, &mask, NULL, &cpusets, NULL); applyset: if (error == 0) { thread_lock(td); *** DIFF OUTPUT TRUNCATED AT 1000 LINES *** From owner-svn-src-user@freebsd.org Fri Dec 15 23:50:32 2017 Return-Path: Delivered-To: svn-src-user@mailman.ysv.freebsd.org Received: from mx1.freebsd.org (mx1.freebsd.org [IPv6:2001:1900:2254:206a::19:1]) by mailman.ysv.freebsd.org (Postfix) with ESMTP id D03B2E8FA6B for ; Fri, 15 Dec 2017 23:50:32 +0000 (UTC) (envelope-from jeff@FreeBSD.org) Received: from repo.freebsd.org (repo.freebsd.org [IPv6:2610:1c1:1:6068::e6a:0]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (Client did not present a certificate) by mx1.freebsd.org (Postfix) with ESMTPS id 0750A6A448; Fri, 15 Dec 2017 23:50:31 +0000 (UTC) (envelope-from jeff@FreeBSD.org) Received: from repo.freebsd.org ([127.0.1.37]) by repo.freebsd.org (8.15.2/8.15.2) with ESMTP id vBFNoVjd054049; Fri, 15 Dec 2017 23:50:31 GMT (envelope-from jeff@FreeBSD.org) Received: (from jeff@localhost) by repo.freebsd.org (8.15.2/8.15.2/Submit) id vBFNoRwp054015; Fri, 15 Dec 2017 23:50:27 GMT (envelope-from jeff@FreeBSD.org) Message-Id: <201712152350.vBFNoRwp054015@repo.freebsd.org> X-Authentication-Warning: repo.freebsd.org: jeff set sender to jeff@FreeBSD.org using -f From: Jeff Roberson Date: Fri, 15 Dec 2017 23:50:27 +0000 (UTC) To: src-committers@freebsd.org, svn-src-user@freebsd.org Subject: svn commit: r326890 - in user/jeff/numa: . bin/cat bin/date bin/kenv bin/ps bin/setfacl bin/sh cddl/contrib/opensolaris/cmd/dtrace/test/tst/common/env cddl/contrib/opensolaris/lib/libdtrace/common ... X-SVN-Group: user X-SVN-Commit-Author: jeff X-SVN-Commit-Paths: in user/jeff/numa: . bin/cat bin/date bin/kenv bin/ps bin/setfacl bin/sh cddl/contrib/opensolaris/cmd/dtrace/test/tst/common/env cddl/contrib/opensolaris/lib/libdtrace/common cddl/usr.sbin/dtrace/test... X-SVN-Commit-Revision: 326890 X-SVN-Commit-Repository: base MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit X-BeenThere: svn-src-user@freebsd.org X-Mailman-Version: 2.1.25 Precedence: list List-Id: "SVN commit messages for the experimental " user" src tree" List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , X-List-Received-Date: Fri, 15 Dec 2017 23:50:32 -0000 Author: jeff Date: Fri Dec 15 23:50:26 2017 New Revision: 326890 URL: https://svnweb.freebsd.org/changeset/base/326890 Log: Merge to head Added: user/jeff/numa/cddl/contrib/opensolaris/cmd/dtrace/test/tst/common/env/ - copied from r326889, head/cddl/contrib/opensolaris/cmd/dtrace/test/tst/common/env/ user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/env/ - copied from r326889, head/cddl/usr.sbin/dtrace/tests/common/env/ user/jeff/numa/contrib/tcpdump/funcattrs.h - copied unchanged from r326889, head/contrib/tcpdump/funcattrs.h user/jeff/numa/crypto/openssl/ssl/fatalerrtest.c - copied unchanged from r326889, head/crypto/openssl/ssl/fatalerrtest.c user/jeff/numa/lib/libc/tests/gen/dir2_test.c - copied unchanged from r326889, head/lib/libc/tests/gen/dir2_test.c user/jeff/numa/lib/libefivar/efivar-dp-xlate.c - copied unchanged from r326889, head/lib/libefivar/efivar-dp-xlate.c user/jeff/numa/sys/arm64/cloudabi32/ - copied from r326889, head/sys/arm64/cloudabi32/ user/jeff/numa/sys/dev/bwn/if_bwn_bhnd.c - copied unchanged from r326889, head/sys/dev/bwn/if_bwn_bhnd.c user/jeff/numa/sys/dev/bwn/if_bwn_siba.c - copied unchanged from r326889, head/sys/dev/bwn/if_bwn_siba.c user/jeff/numa/sys/dev/bwn/if_bwn_siba.h - copied unchanged from r326889, head/sys/dev/bwn/if_bwn_siba.h user/jeff/numa/sys/dev/bwn/if_bwn_siba_compat.c - copied unchanged from r326889, head/sys/dev/bwn/if_bwn_siba_compat.c user/jeff/numa/sys/dev/bwn/if_bwn_siba_compat.h - copied unchanged from r326889, head/sys/dev/bwn/if_bwn_siba_compat.h user/jeff/numa/sys/dev/syscon/ - copied from r326889, head/sys/dev/syscon/ user/jeff/numa/tests/sys/geom/class/mirror/10_test.sh - copied unchanged from r326889, head/tests/sys/geom/class/mirror/10_test.sh user/jeff/numa/tests/sys/geom/class/mirror/11_test.sh - copied unchanged from r326889, head/tests/sys/geom/class/mirror/11_test.sh user/jeff/numa/tests/sys/geom/class/mirror/12_test.sh - copied unchanged from r326889, head/tests/sys/geom/class/mirror/12_test.sh user/jeff/numa/tests/sys/geom/class/mirror/13_test.sh - copied unchanged from r326889, head/tests/sys/geom/class/mirror/13_test.sh user/jeff/numa/tests/sys/netipsec/ - copied from r326889, head/tests/sys/netipsec/ user/jeff/numa/tools/boot/install-boot.sh - copied unchanged from r326889, head/tools/boot/install-boot.sh user/jeff/numa/tools/boot/rootgen.sh - copied unchanged from r326889, head/tools/boot/rootgen.sh user/jeff/numa/usr.bin/dc/tests/ - copied from r326889, head/usr.bin/dc/tests/ user/jeff/numa/usr.sbin/efibootmgr/ - copied from r326889, head/usr.sbin/efibootmgr/ user/jeff/numa/usr.sbin/fdformat/fdformat.8 - copied unchanged from r326889, head/usr.sbin/fdformat/fdformat.8 Deleted: user/jeff/numa/stand/libsa/util.c user/jeff/numa/stand/libsa/util.h user/jeff/numa/sys/dev/bwn/bwn_mac.c user/jeff/numa/sys/dts/arm/apalis-imx6.dts user/jeff/numa/sys/dts/arm/imx6.dtsi user/jeff/numa/sys/dts/arm/wandboard-dual.dts user/jeff/numa/sys/dts/arm/wandboard-quad.dts user/jeff/numa/sys/dts/arm/wandboard-solo.dts user/jeff/numa/tools/diag/httpd-error/ user/jeff/numa/usr.sbin/fdformat/fdformat.1 Modified: user/jeff/numa/.arclint user/jeff/numa/Makefile user/jeff/numa/Makefile.inc1 user/jeff/numa/Makefile.sys.inc user/jeff/numa/ObsoleteFiles.inc user/jeff/numa/README user/jeff/numa/README.md user/jeff/numa/UPDATING user/jeff/numa/bin/cat/cat.1 user/jeff/numa/bin/date/date.1 user/jeff/numa/bin/kenv/kenv.1 user/jeff/numa/bin/ps/keyword.c user/jeff/numa/bin/ps/ps.1 user/jeff/numa/bin/setfacl/setfacl.1 user/jeff/numa/bin/sh/sh.1 user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_open.c user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.c user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.h user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/Makefile user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/probes/Makefile user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/speculation/Makefile user/jeff/numa/cddl/usr.sbin/dtrace/tests/tools/exclude.sh user/jeff/numa/contrib/binutils/libiberty/make-relative-prefix.c user/jeff/numa/contrib/bsnmp/snmpd/config.c user/jeff/numa/contrib/compiler-rt/lib/builtins/int_lib.h user/jeff/numa/contrib/dma/mail.c user/jeff/numa/contrib/jemalloc/include/jemalloc/internal/jemalloc_internal_inlines_c.h user/jeff/numa/contrib/less/main.c user/jeff/numa/contrib/libc++/include/algorithm user/jeff/numa/contrib/libc++/include/deque user/jeff/numa/contrib/libc++/include/functional user/jeff/numa/contrib/libc++/include/list user/jeff/numa/contrib/libc++/include/string user/jeff/numa/contrib/libc++/include/type_traits user/jeff/numa/contrib/libc++/include/vector user/jeff/numa/contrib/llvm/include/llvm/Analysis/TargetTransformInfoImpl.h user/jeff/numa/contrib/llvm/include/llvm/CodeGen/MachineRegisterInfo.h user/jeff/numa/contrib/llvm/include/llvm/IR/AutoUpgrade.h user/jeff/numa/contrib/llvm/include/llvm/Support/FormatVariadic.h user/jeff/numa/contrib/llvm/lib/AsmParser/LLParser.cpp user/jeff/numa/contrib/llvm/lib/Bitcode/Reader/BitcodeReader.cpp user/jeff/numa/contrib/llvm/lib/CodeGen/AsmPrinter/DwarfCompileUnit.cpp user/jeff/numa/contrib/llvm/lib/CodeGen/AsmPrinter/DwarfDebug.h user/jeff/numa/contrib/llvm/lib/CodeGen/AsmPrinter/DwarfExpression.cpp user/jeff/numa/contrib/llvm/lib/CodeGen/LiveIntervalAnalysis.cpp user/jeff/numa/contrib/llvm/lib/CodeGen/MachineRegisterInfo.cpp user/jeff/numa/contrib/llvm/lib/CodeGen/MachineVerifier.cpp user/jeff/numa/contrib/llvm/lib/IR/AutoUpgrade.cpp user/jeff/numa/contrib/llvm/lib/IR/ConstantFold.cpp user/jeff/numa/contrib/llvm/lib/Linker/IRMover.cpp user/jeff/numa/contrib/llvm/lib/Linker/LinkModules.cpp user/jeff/numa/contrib/llvm/lib/Support/Host.cpp user/jeff/numa/contrib/llvm/lib/Target/AArch64/AArch64FalkorHWPFFix.cpp user/jeff/numa/contrib/llvm/lib/Target/AArch64/AArch64ISelLowering.cpp user/jeff/numa/contrib/llvm/lib/Target/AArch64/AArch64InstrInfo.td user/jeff/numa/contrib/llvm/lib/Target/AMDGPU/GCNHazardRecognizer.cpp user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMAsmPrinter.cpp user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMCallLowering.cpp user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMExpandPseudoInsts.cpp user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMFastISel.cpp user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMFrameLowering.cpp user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMInstrInfo.td user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMLoadStoreOptimizer.cpp user/jeff/numa/contrib/llvm/lib/Target/ARM/ARMSubtarget.h user/jeff/numa/contrib/llvm/lib/Target/ARM/MCTargetDesc/ARMMCTargetDesc.cpp user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRExpandPseudoInsts.cpp user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRISelLowering.cpp user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRISelLowering.h user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRInstrInfo.cpp user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRInstrInfo.h user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRInstrInfo.td user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRRegisterInfo.cpp user/jeff/numa/contrib/llvm/lib/Target/AVR/AVRTargetMachine.cpp user/jeff/numa/contrib/llvm/lib/Target/AVR/MCTargetDesc/AVRTargetStreamer.cpp user/jeff/numa/contrib/llvm/lib/Target/AVR/MCTargetDesc/AVRTargetStreamer.h user/jeff/numa/contrib/llvm/lib/Target/Mips/AsmParser/MipsAsmParser.cpp user/jeff/numa/contrib/llvm/lib/Target/Mips/MCTargetDesc/MipsMCExpr.cpp user/jeff/numa/contrib/llvm/lib/Target/Mips/MCTargetDesc/MipsTargetStreamer.cpp user/jeff/numa/contrib/llvm/lib/Target/Mips/MicroMipsDSPInstrInfo.td user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsDSPInstrInfo.td user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsFrameLowering.cpp user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsMTInstrFormats.td user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsMTInstrInfo.td user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsSEFrameLowering.cpp user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsSEInstrInfo.cpp user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsSchedule.td user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsScheduleGeneric.td user/jeff/numa/contrib/llvm/lib/Target/Mips/MipsTargetStreamer.h user/jeff/numa/contrib/llvm/lib/Target/X86/X86ISelLowering.cpp user/jeff/numa/contrib/llvm/tools/clang/include/clang/Basic/Attr.td user/jeff/numa/contrib/llvm/tools/clang/include/clang/Basic/AttrDocs.td user/jeff/numa/contrib/llvm/tools/clang/include/clang/Basic/BuiltinsX86.def user/jeff/numa/contrib/llvm/tools/clang/include/clang/Basic/DiagnosticSemaKinds.td user/jeff/numa/contrib/llvm/tools/clang/include/clang/Sema/ScopeInfo.h user/jeff/numa/contrib/llvm/tools/clang/lib/AST/ExprConstant.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Basic/Targets.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Basic/Version.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/CodeGen/CGExpr.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/CodeGen/CGOpenMPRuntime.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/CodeGen/CGOpenMPRuntime.h user/jeff/numa/contrib/llvm/tools/clang/lib/CodeGen/CGStmtOpenMP.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/CodeGen/CodeGenFunction.h user/jeff/numa/contrib/llvm/tools/clang/lib/Driver/ToolChain.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Driver/ToolChains/BareMetal.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Driver/ToolChains/BareMetal.h user/jeff/numa/contrib/llvm/tools/clang/lib/Driver/ToolChains/Clang.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Format/Format.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Headers/avx512fintrin.h user/jeff/numa/contrib/llvm/tools/clang/lib/Sema/SemaDeclCXX.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Sema/SemaLambda.cpp user/jeff/numa/contrib/llvm/tools/clang/lib/Sema/SemaOpenMP.cpp user/jeff/numa/contrib/llvm/tools/lld/ELF/Driver.cpp user/jeff/numa/contrib/llvm/tools/lld/ELF/MarkLive.cpp user/jeff/numa/contrib/llvm/tools/lld/ELF/Relocations.cpp user/jeff/numa/contrib/llvm/tools/lld/ELF/SyntheticSections.cpp user/jeff/numa/contrib/llvm/tools/lld/ELF/SyntheticSections.h user/jeff/numa/contrib/llvm/tools/lld/ELF/Writer.cpp user/jeff/numa/contrib/llvm/tools/lld/ELF/Writer.h user/jeff/numa/contrib/llvm/tools/lldb/source/Expression/IRExecutionUnit.cpp user/jeff/numa/contrib/mdocml/mdoc.7 user/jeff/numa/contrib/mdocml/st.in user/jeff/numa/contrib/ofed/include/udma_barrier.h user/jeff/numa/contrib/ofed/infiniband-diags/build/Makefile.inc user/jeff/numa/contrib/ofed/libibnetdisc/Makefile user/jeff/numa/contrib/ofed/libibnetdisc/g_hash_table.cpp user/jeff/numa/contrib/ofed/librdmacm/librdmacm.map user/jeff/numa/contrib/ofed/opensm/complib/Makefile user/jeff/numa/contrib/ofed/opensm/libopensm/Makefile user/jeff/numa/contrib/ofed/opensm/libvendor/Makefile user/jeff/numa/contrib/ofed/opensm/opensm/Makefile user/jeff/numa/contrib/tcpdump/CHANGES user/jeff/numa/contrib/tcpdump/CONTRIBUTING user/jeff/numa/contrib/tcpdump/CREDITS user/jeff/numa/contrib/tcpdump/INSTALL.txt user/jeff/numa/contrib/tcpdump/Makefile.in user/jeff/numa/contrib/tcpdump/PLATFORMS user/jeff/numa/contrib/tcpdump/README.md user/jeff/numa/contrib/tcpdump/VERSION user/jeff/numa/contrib/tcpdump/addrtoname.c user/jeff/numa/contrib/tcpdump/addrtoname.h user/jeff/numa/contrib/tcpdump/addrtostr.c user/jeff/numa/contrib/tcpdump/af.c user/jeff/numa/contrib/tcpdump/af.h user/jeff/numa/contrib/tcpdump/checksum.c user/jeff/numa/contrib/tcpdump/config.h.in user/jeff/numa/contrib/tcpdump/configure user/jeff/numa/contrib/tcpdump/configure.in user/jeff/numa/contrib/tcpdump/extract.h user/jeff/numa/contrib/tcpdump/gmpls.c user/jeff/numa/contrib/tcpdump/gmpls.h user/jeff/numa/contrib/tcpdump/ip6.h user/jeff/numa/contrib/tcpdump/ipproto.c user/jeff/numa/contrib/tcpdump/ipproto.h user/jeff/numa/contrib/tcpdump/l2vpn.c user/jeff/numa/contrib/tcpdump/l2vpn.h user/jeff/numa/contrib/tcpdump/netdissect-stdinc.h user/jeff/numa/contrib/tcpdump/netdissect.h user/jeff/numa/contrib/tcpdump/nlpid.c user/jeff/numa/contrib/tcpdump/nlpid.h user/jeff/numa/contrib/tcpdump/oui.c user/jeff/numa/contrib/tcpdump/oui.h user/jeff/numa/contrib/tcpdump/print-802_11.c user/jeff/numa/contrib/tcpdump/print-802_15_4.c user/jeff/numa/contrib/tcpdump/print-aodv.c user/jeff/numa/contrib/tcpdump/print-arp.c user/jeff/numa/contrib/tcpdump/print-atm.c user/jeff/numa/contrib/tcpdump/print-beep.c user/jeff/numa/contrib/tcpdump/print-bfd.c user/jeff/numa/contrib/tcpdump/print-bgp.c user/jeff/numa/contrib/tcpdump/print-bootp.c user/jeff/numa/contrib/tcpdump/print-cfm.c user/jeff/numa/contrib/tcpdump/print-chdlc.c user/jeff/numa/contrib/tcpdump/print-cnfp.c user/jeff/numa/contrib/tcpdump/print-decnet.c user/jeff/numa/contrib/tcpdump/print-dhcp6.c user/jeff/numa/contrib/tcpdump/print-domain.c user/jeff/numa/contrib/tcpdump/print-eap.c user/jeff/numa/contrib/tcpdump/print-eigrp.c user/jeff/numa/contrib/tcpdump/print-esp.c user/jeff/numa/contrib/tcpdump/print-ether.c user/jeff/numa/contrib/tcpdump/print-fr.c user/jeff/numa/contrib/tcpdump/print-frag6.c user/jeff/numa/contrib/tcpdump/print-gre.c user/jeff/numa/contrib/tcpdump/print-hncp.c user/jeff/numa/contrib/tcpdump/print-icmp.c user/jeff/numa/contrib/tcpdump/print-icmp6.c user/jeff/numa/contrib/tcpdump/print-ip.c user/jeff/numa/contrib/tcpdump/print-ip6.c user/jeff/numa/contrib/tcpdump/print-ip6opts.c user/jeff/numa/contrib/tcpdump/print-isakmp.c user/jeff/numa/contrib/tcpdump/print-isoclns.c user/jeff/numa/contrib/tcpdump/print-juniper.c user/jeff/numa/contrib/tcpdump/print-l2tp.c user/jeff/numa/contrib/tcpdump/print-ldp.c user/jeff/numa/contrib/tcpdump/print-llc.c user/jeff/numa/contrib/tcpdump/print-lldp.c user/jeff/numa/contrib/tcpdump/print-lmp.c user/jeff/numa/contrib/tcpdump/print-lspping.c user/jeff/numa/contrib/tcpdump/print-m3ua.c user/jeff/numa/contrib/tcpdump/print-mobility.c user/jeff/numa/contrib/tcpdump/print-mpcp.c user/jeff/numa/contrib/tcpdump/print-mpls.c user/jeff/numa/contrib/tcpdump/print-mptcp.c user/jeff/numa/contrib/tcpdump/print-nfs.c user/jeff/numa/contrib/tcpdump/print-null.c user/jeff/numa/contrib/tcpdump/print-olsr.c user/jeff/numa/contrib/tcpdump/print-ospf6.c user/jeff/numa/contrib/tcpdump/print-pgm.c user/jeff/numa/contrib/tcpdump/print-pim.c user/jeff/numa/contrib/tcpdump/print-pktap.c user/jeff/numa/contrib/tcpdump/print-ppp.c user/jeff/numa/contrib/tcpdump/print-radius.c user/jeff/numa/contrib/tcpdump/print-resp.c user/jeff/numa/contrib/tcpdump/print-ripng.c user/jeff/numa/contrib/tcpdump/print-rpki-rtr.c user/jeff/numa/contrib/tcpdump/print-rsvp.c user/jeff/numa/contrib/tcpdump/print-rt6.c user/jeff/numa/contrib/tcpdump/print-rx.c user/jeff/numa/contrib/tcpdump/print-sip.c user/jeff/numa/contrib/tcpdump/print-sl.c user/jeff/numa/contrib/tcpdump/print-slow.c user/jeff/numa/contrib/tcpdump/print-stp.c user/jeff/numa/contrib/tcpdump/print-syslog.c user/jeff/numa/contrib/tcpdump/print-telnet.c user/jeff/numa/contrib/tcpdump/print-tftp.c user/jeff/numa/contrib/tcpdump/print-vqp.c user/jeff/numa/contrib/tcpdump/print-vtp.c user/jeff/numa/contrib/tcpdump/print-wb.c user/jeff/numa/contrib/tcpdump/print-zephyr.c user/jeff/numa/contrib/tcpdump/print.c user/jeff/numa/contrib/tcpdump/signature.c user/jeff/numa/contrib/tcpdump/signature.h user/jeff/numa/contrib/tcpdump/smbutil.c user/jeff/numa/contrib/tcpdump/tcpdump.1.in user/jeff/numa/contrib/tcpdump/tcpdump.c user/jeff/numa/contrib/tcpdump/util-print.c user/jeff/numa/crypto/openssl/CHANGES user/jeff/numa/crypto/openssl/Configure user/jeff/numa/crypto/openssl/Makefile user/jeff/numa/crypto/openssl/NEWS user/jeff/numa/crypto/openssl/README user/jeff/numa/crypto/openssl/apps/apps.c user/jeff/numa/crypto/openssl/apps/dsa.c user/jeff/numa/crypto/openssl/apps/s_client.c user/jeff/numa/crypto/openssl/apps/speed.c user/jeff/numa/crypto/openssl/crypto/aes/asm/aes-armv4.pl user/jeff/numa/crypto/openssl/crypto/aes/asm/bsaes-armv7.pl user/jeff/numa/crypto/openssl/crypto/asn1/a_i2d_fp.c user/jeff/numa/crypto/openssl/crypto/bio/b_print.c user/jeff/numa/crypto/openssl/crypto/bn/asm/rsaz-avx2.pl user/jeff/numa/crypto/openssl/crypto/bn/bn_exp.c user/jeff/numa/crypto/openssl/crypto/dsa/dsa_ameth.c user/jeff/numa/crypto/openssl/crypto/engine/eng_fat.c user/jeff/numa/crypto/openssl/crypto/lhash/lhash.c user/jeff/numa/crypto/openssl/crypto/opensslv.h user/jeff/numa/crypto/openssl/crypto/rsa/rsa_gen.c user/jeff/numa/crypto/openssl/crypto/sha/asm/sha256-armv4.pl user/jeff/numa/crypto/openssl/crypto/symhacks.h user/jeff/numa/crypto/openssl/crypto/x509v3/v3_lib.c user/jeff/numa/crypto/openssl/crypto/x509v3/v3_scts.c user/jeff/numa/crypto/openssl/doc/crypto/EVP_EncryptInit.pod user/jeff/numa/crypto/openssl/ssl/Makefile user/jeff/numa/crypto/openssl/ssl/bad_dtls_test.c user/jeff/numa/crypto/openssl/ssl/s23_clnt.c user/jeff/numa/crypto/openssl/ssl/s3_pkt.c user/jeff/numa/crypto/openssl/ssl/ssl.h user/jeff/numa/crypto/openssl/ssl/ssltest.c user/jeff/numa/crypto/openssl/ssl/t1_lib.c user/jeff/numa/crypto/openssl/util/copy-if-different.pl user/jeff/numa/crypto/openssl/util/copy.pl user/jeff/numa/crypto/openssl/util/libeay.num user/jeff/numa/crypto/openssl/util/mk1mf.pl user/jeff/numa/etc/mtree/BSD.debug.dist user/jeff/numa/etc/mtree/BSD.root.dist user/jeff/numa/etc/mtree/BSD.tests.dist user/jeff/numa/etc/mtree/BSD.usr.dist user/jeff/numa/etc/pf.os user/jeff/numa/include/arpa/inet.h user/jeff/numa/include/arpa/nameser.h user/jeff/numa/include/ftw.h user/jeff/numa/include/hesiod.h user/jeff/numa/include/ifaddrs.h user/jeff/numa/include/libgen.h user/jeff/numa/include/netdb.h user/jeff/numa/include/readpassphrase.h user/jeff/numa/include/res_update.h user/jeff/numa/include/resolv.h user/jeff/numa/include/unwind.h user/jeff/numa/include/wchar.h user/jeff/numa/lib/clang/headers/Makefile user/jeff/numa/lib/clang/include/clang/Basic/Version.inc user/jeff/numa/lib/clang/include/clang/Config/config.h user/jeff/numa/lib/clang/include/lld/Config/Version.inc user/jeff/numa/lib/clang/include/llvm/Config/config.h user/jeff/numa/lib/clang/include/llvm/Config/llvm-config.h user/jeff/numa/lib/clang/include/llvm/Support/VCSRevision.h user/jeff/numa/lib/libc/gen/Makefile.inc user/jeff/numa/lib/libc/gen/Symbol.map user/jeff/numa/lib/libc/gen/basename_compat.c user/jeff/numa/lib/libc/gen/signal.3 user/jeff/numa/lib/libc/gen/telldir.c user/jeff/numa/lib/libc/gen/telldir.h user/jeff/numa/lib/libc/gen/tls.c user/jeff/numa/lib/libc/include/fpmath.h user/jeff/numa/lib/libc/include/isc/eventlib.h user/jeff/numa/lib/libc/include/isc/list.h user/jeff/numa/lib/libc/include/isc/platform.h user/jeff/numa/lib/libc/inet/inet_addr.c user/jeff/numa/lib/libc/inet/inet_cidr_ntop.c user/jeff/numa/lib/libc/inet/inet_cidr_pton.c user/jeff/numa/lib/libc/inet/inet_net_ntop.c user/jeff/numa/lib/libc/inet/inet_net_pton.c user/jeff/numa/lib/libc/inet/inet_neta.c user/jeff/numa/lib/libc/inet/inet_ntop.c user/jeff/numa/lib/libc/inet/inet_pton.c user/jeff/numa/lib/libc/inet/nsap_addr.c user/jeff/numa/lib/libc/isc/ev_streams.c user/jeff/numa/lib/libc/isc/ev_timers.c user/jeff/numa/lib/libc/isc/eventlib_p.h user/jeff/numa/lib/libc/nameser/ns_name.c user/jeff/numa/lib/libc/nameser/ns_netint.c user/jeff/numa/lib/libc/nameser/ns_parse.c user/jeff/numa/lib/libc/nameser/ns_print.c user/jeff/numa/lib/libc/nameser/ns_samedomain.c user/jeff/numa/lib/libc/nameser/ns_ttl.c user/jeff/numa/lib/libc/net/getifaddrs.c user/jeff/numa/lib/libc/net/if_indextoname.c user/jeff/numa/lib/libc/net/if_nameindex.c user/jeff/numa/lib/libc/net/if_nametoindex.c user/jeff/numa/lib/libc/resolv/herror.c user/jeff/numa/lib/libc/resolv/res_comp.c user/jeff/numa/lib/libc/resolv/res_data.c user/jeff/numa/lib/libc/resolv/res_debug.c user/jeff/numa/lib/libc/resolv/res_debug.h user/jeff/numa/lib/libc/resolv/res_findzonecut.c user/jeff/numa/lib/libc/resolv/res_init.c user/jeff/numa/lib/libc/resolv/res_mkquery.c user/jeff/numa/lib/libc/resolv/res_mkupdate.c user/jeff/numa/lib/libc/resolv/res_query.c user/jeff/numa/lib/libc/resolv/res_send.c user/jeff/numa/lib/libc/resolv/res_update.c user/jeff/numa/lib/libc/stdio/vfwscanf.c user/jeff/numa/lib/libc/sys/chdir.2 user/jeff/numa/lib/libc/sys/chmod.2 user/jeff/numa/lib/libc/sys/chown.2 user/jeff/numa/lib/libc/sys/close.2 user/jeff/numa/lib/libc/sys/dup.2 user/jeff/numa/lib/libc/sys/fork.2 user/jeff/numa/lib/libc/sys/getuid.2 user/jeff/numa/lib/libc/sys/kill.2 user/jeff/numa/lib/libc/sys/kqueue.2 user/jeff/numa/lib/libc/sys/link.2 user/jeff/numa/lib/libc/sys/mkdir.2 user/jeff/numa/lib/libc/sys/mknod.2 user/jeff/numa/lib/libc/sys/mount.2 user/jeff/numa/lib/libc/sys/open.2 user/jeff/numa/lib/libc/sys/openat.c user/jeff/numa/lib/libc/sys/pipe.2 user/jeff/numa/lib/libc/sys/profil.2 user/jeff/numa/lib/libc/sys/ptrace.2 user/jeff/numa/lib/libc/sys/read.2 user/jeff/numa/lib/libc/sys/setcontext.c user/jeff/numa/lib/libc/sys/setuid.2 user/jeff/numa/lib/libc/sys/stat.2 user/jeff/numa/lib/libc/sys/swapcontext.c user/jeff/numa/lib/libc/sys/sync.2 user/jeff/numa/lib/libc/sys/unlink.2 user/jeff/numa/lib/libc/sys/wait.2 user/jeff/numa/lib/libc/sys/write.2 user/jeff/numa/lib/libc/tests/gen/Makefile user/jeff/numa/lib/libcam/camlib.c user/jeff/numa/lib/libclang_rt/Makefile.inc user/jeff/numa/lib/libefivar/Makefile user/jeff/numa/lib/libefivar/efivar-dp-format.c user/jeff/numa/lib/libefivar/efivar-dp.h user/jeff/numa/lib/libfetch/ftp.c user/jeff/numa/lib/libmd/md4.h user/jeff/numa/lib/libmd/md4c.c user/jeff/numa/lib/libmd/md5c.c user/jeff/numa/lib/libmd/mdXhl.c user/jeff/numa/lib/libmd/shadriver.c user/jeff/numa/lib/libmd/skeindriver.c user/jeff/numa/lib/libproc/Makefile user/jeff/numa/lib/libproc/libproc.h user/jeff/numa/lib/libproc/proc_create.c user/jeff/numa/lib/libproc/tests/proc_test.c user/jeff/numa/lib/msun/bsdsrc/b_log.c user/jeff/numa/lib/msun/man/exp.3 user/jeff/numa/lib/msun/man/lgamma.3 user/jeff/numa/lib/msun/man/math.3 user/jeff/numa/lib/msun/src/e_pow.c user/jeff/numa/libexec/ftpd/ftpd.c user/jeff/numa/release/Makefile user/jeff/numa/release/release.sh user/jeff/numa/release/tools/ec2.conf user/jeff/numa/release/tools/vmimage.subr user/jeff/numa/sbin/dhclient/Makefile user/jeff/numa/sbin/dhclient/clparse.c user/jeff/numa/sbin/dhclient/conflex.c user/jeff/numa/sbin/dhclient/dhclient.c user/jeff/numa/sbin/dhclient/dhcpd.h user/jeff/numa/sbin/dhclient/inet.c user/jeff/numa/sbin/dhclient/options.c user/jeff/numa/sbin/dhclient/packet.c user/jeff/numa/sbin/dhclient/parse.c user/jeff/numa/sbin/dhclient/privsep.c user/jeff/numa/sbin/dhclient/tree.c user/jeff/numa/sbin/fsck_msdosfs/dir.c user/jeff/numa/sbin/geom/class/mirror/gmirror.8 user/jeff/numa/sbin/growfs/growfs.8 user/jeff/numa/sbin/ifconfig/ifvxlan.c user/jeff/numa/sbin/ifconfig/sfp.c user/jeff/numa/sbin/recoverdisk/recoverdisk.c user/jeff/numa/secure/lib/libcrypto/Makefile.inc user/jeff/numa/secure/lib/libcrypto/amd64/rsaz-avx2.S user/jeff/numa/secure/lib/libcrypto/arm/aes-armv4.S user/jeff/numa/secure/lib/libcrypto/arm/bsaes-armv7.S user/jeff/numa/secure/lib/libcrypto/arm/sha256-armv4.S user/jeff/numa/secure/lib/libcrypto/man/ASN1_OBJECT_new.3 user/jeff/numa/secure/lib/libcrypto/man/ASN1_STRING_length.3 user/jeff/numa/secure/lib/libcrypto/man/ASN1_STRING_new.3 user/jeff/numa/secure/lib/libcrypto/man/ASN1_STRING_print_ex.3 user/jeff/numa/secure/lib/libcrypto/man/ASN1_TIME_set.3 user/jeff/numa/secure/lib/libcrypto/man/ASN1_generate_nconf.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_ctrl.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_f_base64.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_f_buffer.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_f_cipher.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_f_md.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_f_null.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_f_ssl.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_find_type.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_new.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_new_CMS.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_push.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_read.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_accept.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_bio.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_connect.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_fd.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_file.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_mem.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_null.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_s_socket.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_set_callback.3 user/jeff/numa/secure/lib/libcrypto/man/BIO_should_retry.3 user/jeff/numa/secure/lib/libcrypto/man/BN_BLINDING_new.3 user/jeff/numa/secure/lib/libcrypto/man/BN_CTX_new.3 user/jeff/numa/secure/lib/libcrypto/man/BN_CTX_start.3 user/jeff/numa/secure/lib/libcrypto/man/BN_add.3 user/jeff/numa/secure/lib/libcrypto/man/BN_add_word.3 user/jeff/numa/secure/lib/libcrypto/man/BN_bn2bin.3 user/jeff/numa/secure/lib/libcrypto/man/BN_cmp.3 user/jeff/numa/secure/lib/libcrypto/man/BN_copy.3 user/jeff/numa/secure/lib/libcrypto/man/BN_generate_prime.3 user/jeff/numa/secure/lib/libcrypto/man/BN_mod_inverse.3 user/jeff/numa/secure/lib/libcrypto/man/BN_mod_mul_montgomery.3 user/jeff/numa/secure/lib/libcrypto/man/BN_mod_mul_reciprocal.3 user/jeff/numa/secure/lib/libcrypto/man/BN_new.3 user/jeff/numa/secure/lib/libcrypto/man/BN_num_bytes.3 user/jeff/numa/secure/lib/libcrypto/man/BN_rand.3 user/jeff/numa/secure/lib/libcrypto/man/BN_set_bit.3 user/jeff/numa/secure/lib/libcrypto/man/BN_swap.3 user/jeff/numa/secure/lib/libcrypto/man/BN_zero.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_add0_cert.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_add1_recipient_cert.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_add1_signer.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_compress.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_decrypt.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_encrypt.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_final.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_get0_RecipientInfos.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_get0_SignerInfos.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_get0_type.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_get1_ReceiptRequest.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_sign.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_sign_receipt.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_uncompress.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_verify.3 user/jeff/numa/secure/lib/libcrypto/man/CMS_verify_receipt.3 user/jeff/numa/secure/lib/libcrypto/man/CONF_modules_free.3 user/jeff/numa/secure/lib/libcrypto/man/CONF_modules_load_file.3 user/jeff/numa/secure/lib/libcrypto/man/CRYPTO_set_ex_data.3 user/jeff/numa/secure/lib/libcrypto/man/DH_generate_key.3 user/jeff/numa/secure/lib/libcrypto/man/DH_generate_parameters.3 user/jeff/numa/secure/lib/libcrypto/man/DH_get_ex_new_index.3 user/jeff/numa/secure/lib/libcrypto/man/DH_new.3 user/jeff/numa/secure/lib/libcrypto/man/DH_set_method.3 user/jeff/numa/secure/lib/libcrypto/man/DH_size.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_SIG_new.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_do_sign.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_dup_DH.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_generate_key.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_generate_parameters.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_get_ex_new_index.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_new.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_set_method.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_sign.3 user/jeff/numa/secure/lib/libcrypto/man/DSA_size.3 user/jeff/numa/secure/lib/libcrypto/man/EC_GFp_simple_method.3 user/jeff/numa/secure/lib/libcrypto/man/EC_GROUP_copy.3 user/jeff/numa/secure/lib/libcrypto/man/EC_GROUP_new.3 user/jeff/numa/secure/lib/libcrypto/man/EC_KEY_new.3 user/jeff/numa/secure/lib/libcrypto/man/EC_POINT_add.3 user/jeff/numa/secure/lib/libcrypto/man/EC_POINT_new.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_GET_LIB.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_clear_error.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_error_string.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_get_error.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_load_crypto_strings.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_load_strings.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_print_errors.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_put_error.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_remove_state.3 user/jeff/numa/secure/lib/libcrypto/man/ERR_set_mark.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_BytesToKey.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_DigestInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_DigestSignInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_DigestVerifyInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_EncodeInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_EncryptInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_OpenInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_CTX_ctrl.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_CTX_new.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_cmp.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_decrypt.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_derive.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_encrypt.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_get_default_digest.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_keygen.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_meth_new.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_new.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_print_private.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_set1_RSA.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_sign.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_verify.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_PKEY_verify_recover.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_SealInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_SignInit.3 user/jeff/numa/secure/lib/libcrypto/man/EVP_VerifyInit.3 user/jeff/numa/secure/lib/libcrypto/man/OBJ_nid2obj.3 user/jeff/numa/secure/lib/libcrypto/man/OPENSSL_Applink.3 user/jeff/numa/secure/lib/libcrypto/man/OPENSSL_VERSION_NUMBER.3 user/jeff/numa/secure/lib/libcrypto/man/OPENSSL_config.3 user/jeff/numa/secure/lib/libcrypto/man/OPENSSL_ia32cap.3 user/jeff/numa/secure/lib/libcrypto/man/OPENSSL_instrument_bus.3 user/jeff/numa/secure/lib/libcrypto/man/OPENSSL_load_builtin_modules.3 user/jeff/numa/secure/lib/libcrypto/man/OpenSSL_add_all_algorithms.3 user/jeff/numa/secure/lib/libcrypto/man/PEM_write_bio_CMS_stream.3 user/jeff/numa/secure/lib/libcrypto/man/PEM_write_bio_PKCS7_stream.3 user/jeff/numa/secure/lib/libcrypto/man/PKCS12_create.3 user/jeff/numa/secure/lib/libcrypto/man/PKCS12_parse.3 user/jeff/numa/secure/lib/libcrypto/man/PKCS7_decrypt.3 user/jeff/numa/secure/lib/libcrypto/man/PKCS7_encrypt.3 user/jeff/numa/secure/lib/libcrypto/man/PKCS7_sign.3 user/jeff/numa/secure/lib/libcrypto/man/PKCS7_sign_add_signer.3 user/jeff/numa/secure/lib/libcrypto/man/PKCS7_verify.3 user/jeff/numa/secure/lib/libcrypto/man/RAND_add.3 user/jeff/numa/secure/lib/libcrypto/man/RAND_bytes.3 user/jeff/numa/secure/lib/libcrypto/man/RAND_cleanup.3 user/jeff/numa/secure/lib/libcrypto/man/RAND_egd.3 user/jeff/numa/secure/lib/libcrypto/man/RAND_load_file.3 user/jeff/numa/secure/lib/libcrypto/man/RAND_set_rand_method.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_blinding_on.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_check_key.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_generate_key.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_get_ex_new_index.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_new.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_padding_add_PKCS1_type_1.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_print.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_private_encrypt.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_public_encrypt.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_set_method.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_sign.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_sign_ASN1_OCTET_STRING.3 user/jeff/numa/secure/lib/libcrypto/man/RSA_size.3 user/jeff/numa/secure/lib/libcrypto/man/SMIME_read_CMS.3 user/jeff/numa/secure/lib/libcrypto/man/SMIME_read_PKCS7.3 user/jeff/numa/secure/lib/libcrypto/man/SMIME_write_CMS.3 user/jeff/numa/secure/lib/libcrypto/man/SMIME_write_PKCS7.3 user/jeff/numa/secure/lib/libcrypto/man/X509_NAME_ENTRY_get_object.3 user/jeff/numa/secure/lib/libcrypto/man/X509_NAME_add_entry_by_txt.3 user/jeff/numa/secure/lib/libcrypto/man/X509_NAME_get_index_by_NID.3 user/jeff/numa/secure/lib/libcrypto/man/X509_NAME_print_ex.3 user/jeff/numa/secure/lib/libcrypto/man/X509_STORE_CTX_get_error.3 user/jeff/numa/secure/lib/libcrypto/man/X509_STORE_CTX_get_ex_new_index.3 user/jeff/numa/secure/lib/libcrypto/man/X509_STORE_CTX_new.3 user/jeff/numa/secure/lib/libcrypto/man/X509_STORE_CTX_set_verify_cb.3 user/jeff/numa/secure/lib/libcrypto/man/X509_STORE_set_verify_cb_func.3 user/jeff/numa/secure/lib/libcrypto/man/X509_VERIFY_PARAM_set_flags.3 user/jeff/numa/secure/lib/libcrypto/man/X509_check_host.3 user/jeff/numa/secure/lib/libcrypto/man/X509_check_private_key.3 user/jeff/numa/secure/lib/libcrypto/man/X509_new.3 user/jeff/numa/secure/lib/libcrypto/man/X509_verify_cert.3 user/jeff/numa/secure/lib/libcrypto/man/bio.3 user/jeff/numa/secure/lib/libcrypto/man/blowfish.3 user/jeff/numa/secure/lib/libcrypto/man/bn.3 user/jeff/numa/secure/lib/libcrypto/man/bn_internal.3 user/jeff/numa/secure/lib/libcrypto/man/buffer.3 user/jeff/numa/secure/lib/libcrypto/man/crypto.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_ASN1_OBJECT.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_CMS_ContentInfo.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_DHparams.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_DSAPublicKey.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_ECPKParameters.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_ECPrivateKey.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_PKCS8PrivateKey.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_PrivateKey.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_RSAPublicKey.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_X509.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_X509_ALGOR.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_X509_CRL.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_X509_NAME.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_X509_REQ.3 user/jeff/numa/secure/lib/libcrypto/man/d2i_X509_SIG.3 user/jeff/numa/secure/lib/libcrypto/man/des.3 user/jeff/numa/secure/lib/libcrypto/man/dh.3 user/jeff/numa/secure/lib/libcrypto/man/dsa.3 user/jeff/numa/secure/lib/libcrypto/man/ec.3 user/jeff/numa/secure/lib/libcrypto/man/ecdsa.3 user/jeff/numa/secure/lib/libcrypto/man/engine.3 user/jeff/numa/secure/lib/libcrypto/man/err.3 user/jeff/numa/secure/lib/libcrypto/man/evp.3 user/jeff/numa/secure/lib/libcrypto/man/hmac.3 user/jeff/numa/secure/lib/libcrypto/man/i2d_CMS_bio_stream.3 user/jeff/numa/secure/lib/libcrypto/man/i2d_PKCS7_bio_stream.3 user/jeff/numa/secure/lib/libcrypto/man/lh_stats.3 user/jeff/numa/secure/lib/libcrypto/man/lhash.3 user/jeff/numa/secure/lib/libcrypto/man/md5.3 user/jeff/numa/secure/lib/libcrypto/man/mdc2.3 user/jeff/numa/secure/lib/libcrypto/man/pem.3 user/jeff/numa/secure/lib/libcrypto/man/rand.3 user/jeff/numa/secure/lib/libcrypto/man/rc4.3 user/jeff/numa/secure/lib/libcrypto/man/ripemd.3 user/jeff/numa/secure/lib/libcrypto/man/rsa.3 user/jeff/numa/secure/lib/libcrypto/man/sha.3 user/jeff/numa/secure/lib/libcrypto/man/threads.3 user/jeff/numa/secure/lib/libcrypto/man/ui.3 user/jeff/numa/secure/lib/libcrypto/man/ui_compat.3 user/jeff/numa/secure/lib/libcrypto/man/x509.3 user/jeff/numa/secure/lib/libssl/man/SSL_CIPHER_get_name.3 user/jeff/numa/secure/lib/libssl/man/SSL_COMP_add_compression_method.3 user/jeff/numa/secure/lib/libssl/man/SSL_CONF_CTX_new.3 user/jeff/numa/secure/lib/libssl/man/SSL_CONF_CTX_set1_prefix.3 user/jeff/numa/secure/lib/libssl/man/SSL_CONF_CTX_set_flags.3 user/jeff/numa/secure/lib/libssl/man/SSL_CONF_CTX_set_ssl_ctx.3 user/jeff/numa/secure/lib/libssl/man/SSL_CONF_cmd.3 user/jeff/numa/secure/lib/libssl/man/SSL_CONF_cmd_argv.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_add1_chain_cert.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_add_extra_chain_cert.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_add_session.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_ctrl.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_flush_sessions.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_free.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_get0_param.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_get_ex_new_index.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_get_verify_mode.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_load_verify_locations.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_new.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_sess_number.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_sess_set_cache_size.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_sess_set_get_cb.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_sessions.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set1_curves.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set1_verify_cert_store.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_alpn_select_cb.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_cert_cb.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_cert_store.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_cert_verify_callback.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_cipher_list.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_client_CA_list.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_client_cert_cb.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_custom_cli_ext.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_default_passwd_cb.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_generate_session_id.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_info_callback.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_max_cert_list.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_mode.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_msg_callback.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_options.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_psk_client_callback.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_quiet_shutdown.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_read_ahead.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_session_cache_mode.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_session_id_context.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_ssl_version.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_timeout.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_tlsext_servername_callback.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_tlsext_status_cb.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_tlsext_ticket_key_cb.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_tmp_dh_callback.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_tmp_rsa_callback.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_set_verify.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_use_certificate.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_use_psk_identity_hint.3 user/jeff/numa/secure/lib/libssl/man/SSL_CTX_use_serverinfo.3 user/jeff/numa/secure/lib/libssl/man/SSL_SESSION_free.3 user/jeff/numa/secure/lib/libssl/man/SSL_SESSION_get_ex_new_index.3 user/jeff/numa/secure/lib/libssl/man/SSL_SESSION_get_time.3 user/jeff/numa/secure/lib/libssl/man/SSL_accept.3 user/jeff/numa/secure/lib/libssl/man/SSL_alert_type_string.3 user/jeff/numa/secure/lib/libssl/man/SSL_check_chain.3 user/jeff/numa/secure/lib/libssl/man/SSL_clear.3 user/jeff/numa/secure/lib/libssl/man/SSL_connect.3 user/jeff/numa/secure/lib/libssl/man/SSL_do_handshake.3 user/jeff/numa/secure/lib/libssl/man/SSL_export_keying_material.3 user/jeff/numa/secure/lib/libssl/man/SSL_free.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_SSL_CTX.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_ciphers.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_client_CA_list.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_current_cipher.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_default_timeout.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_error.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_ex_data_X509_STORE_CTX_idx.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_ex_new_index.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_fd.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_peer_cert_chain.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_peer_certificate.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_psk_identity.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_rbio.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_session.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_verify_result.3 user/jeff/numa/secure/lib/libssl/man/SSL_get_version.3 user/jeff/numa/secure/lib/libssl/man/SSL_library_init.3 user/jeff/numa/secure/lib/libssl/man/SSL_load_client_CA_file.3 user/jeff/numa/secure/lib/libssl/man/SSL_new.3 user/jeff/numa/secure/lib/libssl/man/SSL_pending.3 user/jeff/numa/secure/lib/libssl/man/SSL_read.3 user/jeff/numa/secure/lib/libssl/man/SSL_rstate_string.3 user/jeff/numa/secure/lib/libssl/man/SSL_session_reused.3 user/jeff/numa/secure/lib/libssl/man/SSL_set_bio.3 user/jeff/numa/secure/lib/libssl/man/SSL_set_connect_state.3 user/jeff/numa/secure/lib/libssl/man/SSL_set_fd.3 user/jeff/numa/secure/lib/libssl/man/SSL_set_session.3 user/jeff/numa/secure/lib/libssl/man/SSL_set_shutdown.3 user/jeff/numa/secure/lib/libssl/man/SSL_set_verify_result.3 user/jeff/numa/secure/lib/libssl/man/SSL_shutdown.3 user/jeff/numa/secure/lib/libssl/man/SSL_state_string.3 user/jeff/numa/secure/lib/libssl/man/SSL_want.3 user/jeff/numa/secure/lib/libssl/man/SSL_write.3 user/jeff/numa/secure/lib/libssl/man/d2i_SSL_SESSION.3 user/jeff/numa/secure/lib/libssl/man/ssl.3 user/jeff/numa/secure/usr.bin/openssl/man/CA.pl.1 user/jeff/numa/secure/usr.bin/openssl/man/asn1parse.1 user/jeff/numa/secure/usr.bin/openssl/man/c_rehash.1 user/jeff/numa/secure/usr.bin/openssl/man/ca.1 user/jeff/numa/secure/usr.bin/openssl/man/ciphers.1 user/jeff/numa/secure/usr.bin/openssl/man/cms.1 user/jeff/numa/secure/usr.bin/openssl/man/crl.1 user/jeff/numa/secure/usr.bin/openssl/man/crl2pkcs7.1 user/jeff/numa/secure/usr.bin/openssl/man/dgst.1 user/jeff/numa/secure/usr.bin/openssl/man/dhparam.1 user/jeff/numa/secure/usr.bin/openssl/man/dsa.1 user/jeff/numa/secure/usr.bin/openssl/man/dsaparam.1 user/jeff/numa/secure/usr.bin/openssl/man/ec.1 user/jeff/numa/secure/usr.bin/openssl/man/ecparam.1 user/jeff/numa/secure/usr.bin/openssl/man/enc.1 user/jeff/numa/secure/usr.bin/openssl/man/errstr.1 user/jeff/numa/secure/usr.bin/openssl/man/gendsa.1 user/jeff/numa/secure/usr.bin/openssl/man/genpkey.1 user/jeff/numa/secure/usr.bin/openssl/man/genrsa.1 user/jeff/numa/secure/usr.bin/openssl/man/nseq.1 user/jeff/numa/secure/usr.bin/openssl/man/ocsp.1 user/jeff/numa/secure/usr.bin/openssl/man/openssl.1 user/jeff/numa/secure/usr.bin/openssl/man/passwd.1 user/jeff/numa/secure/usr.bin/openssl/man/pkcs12.1 user/jeff/numa/secure/usr.bin/openssl/man/pkcs7.1 user/jeff/numa/secure/usr.bin/openssl/man/pkcs8.1 user/jeff/numa/secure/usr.bin/openssl/man/pkey.1 user/jeff/numa/secure/usr.bin/openssl/man/pkeyparam.1 user/jeff/numa/secure/usr.bin/openssl/man/pkeyutl.1 user/jeff/numa/secure/usr.bin/openssl/man/rand.1 user/jeff/numa/secure/usr.bin/openssl/man/req.1 user/jeff/numa/secure/usr.bin/openssl/man/rsa.1 user/jeff/numa/secure/usr.bin/openssl/man/rsautl.1 user/jeff/numa/secure/usr.bin/openssl/man/s_client.1 user/jeff/numa/secure/usr.bin/openssl/man/s_server.1 user/jeff/numa/secure/usr.bin/openssl/man/s_time.1 user/jeff/numa/secure/usr.bin/openssl/man/sess_id.1 user/jeff/numa/secure/usr.bin/openssl/man/smime.1 user/jeff/numa/secure/usr.bin/openssl/man/speed.1 user/jeff/numa/secure/usr.bin/openssl/man/spkac.1 user/jeff/numa/secure/usr.bin/openssl/man/ts.1 user/jeff/numa/secure/usr.bin/openssl/man/tsget.1 user/jeff/numa/secure/usr.bin/openssl/man/verify.1 user/jeff/numa/secure/usr.bin/openssl/man/version.1 user/jeff/numa/secure/usr.bin/openssl/man/x509.1 user/jeff/numa/secure/usr.bin/openssl/man/x509v3_config.1 user/jeff/numa/share/examples/BSD_daemon/beastie.fig user/jeff/numa/share/examples/libusb20/bulk.c user/jeff/numa/share/examples/libusb20/control.c user/jeff/numa/share/man/man3/pthread_condattr.3 user/jeff/numa/share/man/man3/pthread_join.3 user/jeff/numa/share/man/man4/Makefile user/jeff/numa/share/man/man4/cloudabi.4 user/jeff/numa/share/man/man4/tap.4 user/jeff/numa/share/man/man4/tun.4 user/jeff/numa/share/man/man5/autofs.5 user/jeff/numa/share/man/man5/rc.conf.5 user/jeff/numa/share/man/man7/hier.7 user/jeff/numa/share/man/man9/bhnd.9 user/jeff/numa/share/man/man9/crypto.9 user/jeff/numa/share/man/man9/ifnet.9 user/jeff/numa/share/misc/bsd-family-tree user/jeff/numa/share/misc/committers-src.dot user/jeff/numa/share/misc/pci_vendors user/jeff/numa/share/mk/bsd.dep.mk user/jeff/numa/share/mk/bsd.obj.mk user/jeff/numa/share/mk/bsd.sys.mk user/jeff/numa/share/mk/src.libnames.mk user/jeff/numa/share/mk/src.opts.mk user/jeff/numa/share/mk/src.sys.env.mk user/jeff/numa/share/mk/src.sys.obj.mk user/jeff/numa/stand/Makefile.amd64 user/jeff/numa/stand/Makefile.i386 user/jeff/numa/stand/Makefile.inc user/jeff/numa/stand/arm/uboot/start.S user/jeff/numa/stand/common/bootstrap.h user/jeff/numa/stand/common/interp_backslash.c user/jeff/numa/stand/common/interp_parse.c user/jeff/numa/stand/common/load_elf.c user/jeff/numa/stand/common/load_elf_obj.c user/jeff/numa/stand/common/reloc_elf.c user/jeff/numa/stand/defs.mk user/jeff/numa/stand/efi/boot1/Makefile user/jeff/numa/stand/efi/boot1/boot1.c user/jeff/numa/stand/efi/include/efichar.h user/jeff/numa/stand/efi/libefi/Makefile user/jeff/numa/stand/efi/libefi/efichar.c user/jeff/numa/stand/efi/libefi/efipart.c user/jeff/numa/stand/efi/loader/main.c user/jeff/numa/stand/ficl.mk user/jeff/numa/stand/ficl/Makefile user/jeff/numa/stand/ficl/float.c user/jeff/numa/stand/geli/Makefile user/jeff/numa/stand/geli/geliboot.c user/jeff/numa/stand/geli/geliboot_internal.h user/jeff/numa/stand/i386/common/cons.c user/jeff/numa/stand/i386/common/drv.c user/jeff/numa/stand/i386/gptboot/Makefile user/jeff/numa/stand/i386/gptboot/gptboot.c user/jeff/numa/stand/i386/gptboot/gptldr.S user/jeff/numa/stand/i386/gptzfsboot/Makefile user/jeff/numa/stand/i386/libi386/biosdisk.c user/jeff/numa/stand/i386/zfsboot/Makefile user/jeff/numa/stand/i386/zfsboot/zfsboot.c user/jeff/numa/stand/i386/zfsboot/zfsldr.S user/jeff/numa/stand/libsa/Makefile user/jeff/numa/stand/libsa/bootp.c user/jeff/numa/stand/libsa/bootp.h user/jeff/numa/stand/libsa/cd9660.c user/jeff/numa/stand/libsa/environment.c user/jeff/numa/stand/libsa/gpt.c user/jeff/numa/stand/libsa/libstand.3 user/jeff/numa/stand/libsa/random.c user/jeff/numa/stand/libsa/sbrk.c user/jeff/numa/stand/libsa/stand.h user/jeff/numa/stand/mips/beri/boot2/Makefile user/jeff/numa/stand/mips/beri/boot2/boot2.c user/jeff/numa/stand/mips/beri/common/altera_jtag_uart.c user/jeff/numa/stand/mips/beri/common/cfi.c user/jeff/numa/stand/mips/beri/loader/Makefile user/jeff/numa/stand/mips/beri/loader/devicename.c user/jeff/numa/stand/mips/beri/loader/exec.c user/jeff/numa/stand/mips/beri/loader/loader.h user/jeff/numa/stand/ofw/libofw/elf_freebsd.c user/jeff/numa/stand/ofw/libofw/libofw.h user/jeff/numa/stand/ofw/libofw/openfirm.c user/jeff/numa/stand/ofw/libofw/openfirm.h user/jeff/numa/stand/ofw/libofw/ppc64_elf_freebsd.c user/jeff/numa/stand/powerpc/Makefile user/jeff/numa/stand/powerpc/boot1.chrp/Makefile user/jeff/numa/stand/powerpc/boot1.chrp/boot1.c user/jeff/numa/stand/powerpc/kboot/host_syscall.h user/jeff/numa/stand/powerpc/kboot/hostdisk.c user/jeff/numa/stand/powerpc/kboot/kbootfdt.c user/jeff/numa/stand/powerpc/kboot/ppc64_elf_freebsd.c user/jeff/numa/stand/powerpc/ofw/start.c user/jeff/numa/stand/sparc64/boot1/Makefile user/jeff/numa/stand/sparc64/loader/main.c user/jeff/numa/stand/sparc64/loader/metadata.c user/jeff/numa/stand/uboot/lib/libuboot.h user/jeff/numa/stand/userboot/test/Makefile user/jeff/numa/stand/userboot/test/test.c user/jeff/numa/stand/userboot/userboot.h user/jeff/numa/stand/userboot/userboot/main.c user/jeff/numa/stand/zfs/zfsimpl.c user/jeff/numa/sys/amd64/amd64/machdep.c user/jeff/numa/sys/amd64/amd64/trap.c user/jeff/numa/sys/amd64/conf/GENERIC user/jeff/numa/sys/amd64/vmm/amd/amdvi_hw.c user/jeff/numa/sys/amd64/vmm/amd/ivrs_drv.c user/jeff/numa/sys/arm/allwinner/a10_gpio.c user/jeff/numa/sys/arm/allwinner/aw_mp.c user/jeff/numa/sys/arm/allwinner/clkng/aw_ccung.c user/jeff/numa/sys/arm/allwinner/clkng/ccu_h3.c user/jeff/numa/sys/arm/allwinner/clkng/ccu_sun8i_r.c user/jeff/numa/sys/arm/allwinner/h3/h3_padconf.c user/jeff/numa/sys/arm/allwinner/h3/h3_r_padconf.c user/jeff/numa/sys/arm/arm/pmap-v4.c user/jeff/numa/sys/arm/arm/pmap-v6.c user/jeff/numa/sys/arm/conf/CRB user/jeff/numa/sys/arm/include/sysreg.h user/jeff/numa/sys/arm64/arm64/locore.S user/jeff/numa/sys/arm64/arm64/pmap.c user/jeff/numa/sys/arm64/conf/GENERIC user/jeff/numa/sys/arm64/include/profile.h user/jeff/numa/sys/cam/ata/ata_da.c user/jeff/numa/sys/cam/ata/ata_pmp.c user/jeff/numa/sys/cam/ata/ata_xpt.c user/jeff/numa/sys/cam/cam_periph.c user/jeff/numa/sys/cam/cam_periph.h user/jeff/numa/sys/cam/cam_xpt.c user/jeff/numa/sys/cam/cam_xpt.h user/jeff/numa/sys/cam/mmc/mmc_da.c user/jeff/numa/sys/cam/mmc/mmc_xpt.c user/jeff/numa/sys/cam/nvme/nvme_da.c user/jeff/numa/sys/cam/nvme/nvme_xpt.c user/jeff/numa/sys/cam/scsi/scsi_cd.c user/jeff/numa/sys/cam/scsi/scsi_ch.c user/jeff/numa/sys/cam/scsi/scsi_da.c user/jeff/numa/sys/cam/scsi/scsi_enc.c user/jeff/numa/sys/cam/scsi/scsi_pass.c user/jeff/numa/sys/cam/scsi/scsi_pt.c user/jeff/numa/sys/cam/scsi/scsi_sa.c user/jeff/numa/sys/cam/scsi/scsi_sg.c user/jeff/numa/sys/cam/scsi/scsi_target.c user/jeff/numa/sys/cam/scsi/scsi_xpt.c user/jeff/numa/sys/cddl/boot/zfs/zfssubr.c user/jeff/numa/sys/cddl/contrib/opensolaris/uts/common/dtrace/dtrace.c user/jeff/numa/sys/cddl/contrib/opensolaris/uts/common/fs/zfs/vdev_geom.c user/jeff/numa/sys/cddl/contrib/opensolaris/uts/common/sys/fasttrap_impl.h user/jeff/numa/sys/cddl/contrib/opensolaris/uts/intel/dtrace/fasttrap_isa.c user/jeff/numa/sys/cddl/contrib/opensolaris/uts/powerpc/dtrace/fasttrap_isa.c user/jeff/numa/sys/conf/NOTES user/jeff/numa/sys/conf/files user/jeff/numa/sys/conf/files.arm64 user/jeff/numa/sys/conf/kern.post.mk user/jeff/numa/sys/conf/options user/jeff/numa/sys/contrib/dev/acpica/changes.txt user/jeff/numa/sys/contrib/dev/acpica/common/adisasm.c user/jeff/numa/sys/contrib/dev/acpica/common/dmswitch.c user/jeff/numa/sys/contrib/dev/acpica/common/dmtable.c user/jeff/numa/sys/contrib/dev/acpica/common/dmtables.c user/jeff/numa/sys/contrib/dev/acpica/common/dmtbdump.c user/jeff/numa/sys/contrib/dev/acpica/compiler/aslcodegen.c user/jeff/numa/sys/contrib/dev/acpica/compiler/aslcompile.c user/jeff/numa/sys/contrib/dev/acpica/compiler/asldebug.c user/jeff/numa/sys/contrib/dev/acpica/compiler/aslfiles.c user/jeff/numa/sys/contrib/dev/acpica/compiler/asloptions.c user/jeff/numa/sys/contrib/dev/acpica/compiler/aslparseop.c user/jeff/numa/sys/contrib/dev/acpica/compiler/aslstartup.c user/jeff/numa/sys/contrib/dev/acpica/compiler/aslsupport.l user/jeff/numa/sys/contrib/dev/acpica/compiler/asltree.c user/jeff/numa/sys/contrib/dev/acpica/compiler/aslutils.c user/jeff/numa/sys/contrib/dev/acpica/compiler/cvcompiler.c user/jeff/numa/sys/contrib/dev/acpica/compiler/cvdisasm.c user/jeff/numa/sys/contrib/dev/acpica/compiler/cvparser.c user/jeff/numa/sys/contrib/dev/acpica/compiler/dtcompile.c user/jeff/numa/sys/contrib/dev/acpica/compiler/dttable1.c user/jeff/numa/sys/contrib/dev/acpica/compiler/prscan.c user/jeff/numa/sys/contrib/dev/acpica/components/debugger/dbfileio.c user/jeff/numa/sys/contrib/dev/acpica/components/disassembler/dmwalk.c user/jeff/numa/sys/contrib/dev/acpica/components/dispatcher/dspkginit.c user/jeff/numa/sys/contrib/dev/acpica/components/executer/exdump.c user/jeff/numa/sys/contrib/dev/acpica/components/hardware/hwvalid.c user/jeff/numa/sys/contrib/dev/acpica/components/namespace/nsxfeval.c user/jeff/numa/sys/contrib/dev/acpica/components/parser/psutils.c user/jeff/numa/sys/contrib/dev/acpica/components/utilities/utdebug.c user/jeff/numa/sys/contrib/dev/acpica/components/utilities/utnonansi.c user/jeff/numa/sys/contrib/dev/acpica/components/utilities/utosi.c user/jeff/numa/sys/contrib/dev/acpica/components/utilities/uttrack.c user/jeff/numa/sys/contrib/dev/acpica/include/acexcep.h user/jeff/numa/sys/contrib/dev/acpica/include/acglobal.h user/jeff/numa/sys/contrib/dev/acpica/include/acpixf.h user/jeff/numa/sys/contrib/dev/acpica/include/actypes.h user/jeff/numa/sys/contrib/dev/acpica/include/acutils.h user/jeff/numa/sys/contrib/dev/acpica/os_specific/service_layers/osgendbg.c user/jeff/numa/sys/contrib/zstd/lib/common/bitstream.h user/jeff/numa/sys/contrib/zstd/lib/common/zstd_internal.h user/jeff/numa/sys/contrib/zstd/lib/compress/zstd_compress.h user/jeff/numa/sys/contrib/zstd/programs/fileio.c user/jeff/numa/sys/contrib/zstd/programs/zstdcli.c user/jeff/numa/sys/ddb/db_access.c user/jeff/numa/sys/ddb/db_access.h user/jeff/numa/sys/ddb/db_break.c user/jeff/numa/sys/ddb/db_break.h user/jeff/numa/sys/ddb/db_command.c user/jeff/numa/sys/ddb/db_command.h user/jeff/numa/sys/ddb/db_examine.c user/jeff/numa/sys/ddb/db_expr.c user/jeff/numa/sys/ddb/db_input.c user/jeff/numa/sys/ddb/db_lex.c user/jeff/numa/sys/ddb/db_lex.h user/jeff/numa/sys/ddb/db_main.c user/jeff/numa/sys/ddb/db_output.c user/jeff/numa/sys/ddb/db_output.h user/jeff/numa/sys/ddb/db_print.c user/jeff/numa/sys/ddb/db_run.c user/jeff/numa/sys/ddb/db_sym.c user/jeff/numa/sys/ddb/db_sym.h user/jeff/numa/sys/ddb/db_variables.c user/jeff/numa/sys/ddb/db_variables.h user/jeff/numa/sys/ddb/db_watch.c user/jeff/numa/sys/ddb/db_watch.h user/jeff/numa/sys/ddb/db_write_cmd.c user/jeff/numa/sys/dev/ata/chipsets/ata-micron.c user/jeff/numa/sys/dev/ath/ath_hal/ah.c user/jeff/numa/sys/dev/ath/ath_hal/ah.h user/jeff/numa/sys/dev/ath/ath_hal/ah_btcoex.h user/jeff/numa/sys/dev/ath/ath_hal/ah_debug.h user/jeff/numa/sys/dev/ath/ath_hal/ah_decode.h user/jeff/numa/sys/dev/ath/ath_hal/ah_desc.h user/jeff/numa/sys/dev/ath/ath_hal/ah_devid.h user/jeff/numa/sys/dev/ath/ath_hal/ah_diagcodes.h user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom.h user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_9287.c user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_9287.h user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v1.c user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v1.h user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v14.c user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v14.h user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v3.c user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v3.h user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v4k.c user/jeff/numa/sys/dev/ath/ath_hal/ah_eeprom_v4k.h user/jeff/numa/sys/dev/ath/ath_hal/ah_internal.h user/jeff/numa/sys/dev/ath/ath_hal/ah_regdomain.c user/jeff/numa/sys/dev/ath/ath_hal/ah_regdomain.h user/jeff/numa/sys/dev/ath/ath_hal/ah_regdomain/ah_rd_ctry.h user/jeff/numa/sys/dev/ath/ath_hal/ah_regdomain/ah_rd_domains.h user/jeff/numa/sys/dev/ath/ath_hal/ah_regdomain/ah_rd_freqbands.h user/jeff/numa/sys/dev/ath/ath_hal/ah_regdomain/ah_rd_regenum.h user/jeff/numa/sys/dev/ath/ath_hal/ah_regdomain/ah_rd_regmap.h user/jeff/numa/sys/dev/ath/ath_hal/ah_soc.h user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210.h user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_beacon.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_interrupts.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_keycache.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_misc.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_phy.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_power.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_recv.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_reset.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210_xmit.c user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210desc.h user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210phy.h user/jeff/numa/sys/dev/ath/ath_hal/ar5210/ar5210reg.h user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211.h user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_beacon.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_interrupts.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_keycache.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_misc.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_phy.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_power.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_recv.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_reset.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211_xmit.c user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211desc.h user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211phy.h user/jeff/numa/sys/dev/ath/ath_hal/ar5211/ar5211reg.h user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar2316.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar2317.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar2413.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar2425.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5111.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5112.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212.h user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_ani.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_beacon.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_eeprom.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_gpio.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_interrupts.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_keycache.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_misc.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_phy.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_power.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_recv.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_reset.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_rfgain.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212_xmit.c user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212desc.h user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212phy.h user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5212reg.h user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5311reg.h user/jeff/numa/sys/dev/ath/ath_hal/ar5212/ar5413.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312.h user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312_eeprom.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312_gpio.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312_interrupts.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312_misc.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312_power.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312_reset.c user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312phy.h user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5312reg.h user/jeff/numa/sys/dev/ath/ath_hal/ar5312/ar5315_gpio.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar2133.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416.h user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_ani.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_beacon.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_btcoex.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_btcoex.h user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_cal.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_cal.h user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_cal_adcdc.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_cal_adcgain.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_cal_iq.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_eeprom.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_gpio.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_interrupts.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_keycache.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_misc.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_phy.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_power.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_radar.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_recv.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_reset.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_spectral.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416_xmit.c user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416desc.h user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416phy.h user/jeff/numa/sys/dev/ath/ath_hal/ar5416/ar5416reg.h user/jeff/numa/sys/dev/ath/ath_hal/ar9001/ar9130_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar9001/ar9130_eeprom.c user/jeff/numa/sys/dev/ath/ath_hal/ar9001/ar9130_eeprom.h user/jeff/numa/sys/dev/ath/ath_hal/ar9001/ar9130_phy.c user/jeff/numa/sys/dev/ath/ath_hal/ar9001/ar9130_phy.h user/jeff/numa/sys/dev/ath/ath_hal/ar9001/ar9130reg.h user/jeff/numa/sys/dev/ath/ath_hal/ar9001/ar9160_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9280.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9280.h user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9280_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9285.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9285.h user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9285_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9285_btcoex.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9285_reset.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9285an.h user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287.h user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287_attach.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287_olc.h user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287_reset.c user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287_reset.h user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287an.h user/jeff/numa/sys/dev/ath/ath_hal/ar9002/ar9287phy.h user/jeff/numa/sys/dev/ath/ath_hal/ar9003/ar9300_btcoex.h user/jeff/numa/sys/dev/bhnd/bcma/bcma.c user/jeff/numa/sys/dev/bhnd/bcma/bcma.h user/jeff/numa/sys/dev/bhnd/bcma/bcma_bhndb.c user/jeff/numa/sys/dev/bhnd/bcma/bcma_dmp.h user/jeff/numa/sys/dev/bhnd/bcma/bcma_erom.c user/jeff/numa/sys/dev/bhnd/bcma/bcma_eromreg.h user/jeff/numa/sys/dev/bhnd/bcma/bcma_eromvar.h user/jeff/numa/sys/dev/bhnd/bcma/bcma_subr.c user/jeff/numa/sys/dev/bhnd/bcma/bcmavar.h user/jeff/numa/sys/dev/bhnd/bhnd.c user/jeff/numa/sys/dev/bhnd/bhnd.h user/jeff/numa/sys/dev/bhnd/bhnd_debug.h user/jeff/numa/sys/dev/bhnd/bhnd_erom.c user/jeff/numa/sys/dev/bhnd/bhnd_erom.h user/jeff/numa/sys/dev/bhnd/bhnd_erom_types.h user/jeff/numa/sys/dev/bhnd/bhnd_eromvar.h user/jeff/numa/sys/dev/bhnd/bhnd_ids.h user/jeff/numa/sys/dev/bhnd/bhnd_match.h user/jeff/numa/sys/dev/bhnd/bhnd_private.h user/jeff/numa/sys/dev/bhnd/bhnd_subr.c user/jeff/numa/sys/dev/bhnd/bhnd_types.h user/jeff/numa/sys/dev/bhnd/bhndb/bhndb.c user/jeff/numa/sys/dev/bhnd/bhndb/bhndb_pci.c user/jeff/numa/sys/dev/bhnd/bhndb/bhndb_subr.c user/jeff/numa/sys/dev/bhnd/bhndreg.h user/jeff/numa/sys/dev/bhnd/bhndvar.h user/jeff/numa/sys/dev/bhnd/cores/chipc/bhnd_pmu_chipc.c user/jeff/numa/sys/dev/bhnd/cores/chipc/bhnd_sprom_chipc.c user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc.c user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc.h user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_cfi.c user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_gpio.c user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_gpiovar.h user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_private.h user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_slicer.c user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_slicer.h user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_spi.c user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_spi.h user/jeff/numa/sys/dev/bhnd/cores/chipc/chipc_subr.c user/jeff/numa/sys/dev/bhnd/cores/chipc/chipcreg.h user/jeff/numa/sys/dev/bhnd/cores/chipc/chipcvar.h user/jeff/numa/sys/dev/bhnd/cores/pci/bhnd_pci.c user/jeff/numa/sys/dev/bhnd/cores/pci/bhnd_pci_hostb.c user/jeff/numa/sys/dev/bhnd/cores/pci/bhnd_pci_hostbvar.h user/jeff/numa/sys/dev/bhnd/cores/pci/bhnd_pcib.c user/jeff/numa/sys/dev/bhnd/cores/pci/bhnd_pcibvar.h user/jeff/numa/sys/dev/bhnd/cores/pci/bhnd_pcireg.h user/jeff/numa/sys/dev/bhnd/cores/pci/bhnd_pcivar.h user/jeff/numa/sys/dev/bhnd/cores/pcie2/bhnd_pcie2.c user/jeff/numa/sys/dev/bhnd/cores/pcie2/bhnd_pcie2_hostb.c user/jeff/numa/sys/dev/bhnd/cores/pcie2/bhnd_pcie2_hostbvar.h user/jeff/numa/sys/dev/bhnd/cores/pcie2/bhnd_pcie2_reg.h user/jeff/numa/sys/dev/bhnd/cores/pcie2/bhnd_pcie2_var.h user/jeff/numa/sys/dev/bhnd/cores/pcie2/bhnd_pcie2b.c user/jeff/numa/sys/dev/bhnd/cores/pcie2/bhnd_pcie2b_var.h user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmu.c user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmu.h user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmu_core.c user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmu_private.h user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmu_subr.c user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmu_types.h user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmureg.h user/jeff/numa/sys/dev/bhnd/cores/pmu/bhnd_pmuvar.h user/jeff/numa/sys/dev/bhnd/cores/usb/bhnd_ehci.c user/jeff/numa/sys/dev/bhnd/cores/usb/bhnd_ohci.c user/jeff/numa/sys/dev/bhnd/cores/usb/bhnd_usb.c user/jeff/numa/sys/dev/bhnd/cores/usb/bhnd_usbvar.h user/jeff/numa/sys/dev/bhnd/nvram/bhnd_nvram_data_sprom.c user/jeff/numa/sys/dev/bhnd/siba/siba.c user/jeff/numa/sys/dev/bhnd/tools/bus_macro.sh user/jeff/numa/sys/dev/bnxt/bnxt.h user/jeff/numa/sys/dev/bnxt/if_bnxt.c user/jeff/numa/sys/dev/bwn/if_bwn.c user/jeff/numa/sys/dev/bwn/if_bwn_pci.c user/jeff/numa/sys/dev/bwn/if_bwn_pcivar.h user/jeff/numa/sys/dev/bwn/if_bwn_phy_common.c user/jeff/numa/sys/dev/bwn/if_bwn_phy_g.c user/jeff/numa/sys/dev/bwn/if_bwn_phy_lp.c user/jeff/numa/sys/dev/bwn/if_bwn_phy_n.c user/jeff/numa/sys/dev/bwn/if_bwn_util.c user/jeff/numa/sys/dev/bwn/if_bwnreg.h user/jeff/numa/sys/dev/bwn/if_bwnvar.h user/jeff/numa/sys/dev/cardbus/cardbus_cis.c user/jeff/numa/sys/dev/dpaa/bman_fdt.c user/jeff/numa/sys/dev/dpaa/qman_fdt.c user/jeff/numa/sys/dev/fb/gfb.h user/jeff/numa/sys/dev/firewire/if_fwe.c user/jeff/numa/sys/dev/firewire/if_fwip.c user/jeff/numa/sys/dev/hyperv/storvsc/hv_storvsc_drv_freebsd.c user/jeff/numa/sys/dev/iicbus/ds3231.c user/jeff/numa/sys/dev/ioat/ioat.c user/jeff/numa/sys/dev/iscsi/icl_soft.c user/jeff/numa/sys/dev/led/led.c user/jeff/numa/sys/dev/lmc/if_lmc.c user/jeff/numa/sys/dev/mc146818/mc146818reg.h user/jeff/numa/sys/dev/md/md.c user/jeff/numa/sys/dev/mlx4/mlx4_core/icm.h user/jeff/numa/sys/dev/mlx4/mlx4_en/en.h user/jeff/numa/sys/dev/mlx5/device.h user/jeff/numa/sys/dev/mlx5/mlx5_en/en.h user/jeff/numa/sys/dev/mlx5/mlx5_en/mlx5_en_main.c user/jeff/numa/sys/dev/mlx5/mlx5_en/mlx5_en_rx.c user/jeff/numa/sys/dev/mn/if_mn.c user/jeff/numa/sys/dev/ppbus/pps.c user/jeff/numa/sys/dev/rtwn/usb/rtwn_usb_attach.h user/jeff/numa/sys/dev/smc/if_smc.c user/jeff/numa/sys/dev/uart/uart_cpu_arm64.c user/jeff/numa/sys/dev/usb/net/if_mos.c user/jeff/numa/sys/dev/usb/usbdevs user/jeff/numa/sys/dev/usb/wlan/if_uath.c user/jeff/numa/sys/dev/vnic/nicvf_queues.c user/jeff/numa/sys/dev/vt/hw/fb/vt_fb.c user/jeff/numa/sys/dev/vt/vt.h user/jeff/numa/sys/dev/vt/vt_buf.c user/jeff/numa/sys/dev/vt/vt_core.c user/jeff/numa/sys/fs/devfs/devfs_vnops.c user/jeff/numa/sys/fs/ext2fs/ext2_acl.c user/jeff/numa/sys/fs/ext2fs/ext2_acl.h user/jeff/numa/sys/fs/ext2fs/ext2_csum.c user/jeff/numa/sys/fs/ext2fs/ext2_extattr.c user/jeff/numa/sys/fs/ext2fs/ext2_extattr.h user/jeff/numa/sys/fs/ext2fs/ext2_hash.c user/jeff/numa/sys/fs/ext2fs/ext2_inode_cnv.c user/jeff/numa/sys/fs/nfs/nfsport.h user/jeff/numa/sys/fs/nfsserver/nfs_nfsdstate.c user/jeff/numa/sys/fs/tmpfs/tmpfs.h user/jeff/numa/sys/fs/tmpfs/tmpfs_fifoops.c user/jeff/numa/sys/fs/tmpfs/tmpfs_subr.c user/jeff/numa/sys/fs/tmpfs/tmpfs_vfsops.c user/jeff/numa/sys/fs/tmpfs/tmpfs_vnops.c user/jeff/numa/sys/geom/eli/g_eli_hmac.c user/jeff/numa/sys/geom/eli/pkcs5v2.c user/jeff/numa/sys/geom/mirror/g_mirror.c user/jeff/numa/sys/geom/mirror/g_mirror.h user/jeff/numa/sys/geom/raid/tr_concat.c user/jeff/numa/sys/geom/raid/tr_raid5.c user/jeff/numa/sys/gnu/dev/bwn/phy_n/if_bwn_phy_n_core.c user/jeff/numa/sys/gnu/dev/bwn/phy_n/if_bwn_phy_n_ppr.c user/jeff/numa/sys/gnu/dev/bwn/phy_n/if_bwn_phy_n_tables.c user/jeff/numa/sys/gnu/dev/bwn/phy_n/if_bwn_radio_2055.c user/jeff/numa/sys/gnu/dev/bwn/phy_n/if_bwn_radio_2056.c user/jeff/numa/sys/gnu/dev/bwn/phy_n/if_bwn_radio_2057.c user/jeff/numa/sys/i386/acpica/acpi_wakecode.S user/jeff/numa/sys/i386/conf/GENERIC user/jeff/numa/sys/i386/conf/NOTES user/jeff/numa/sys/i386/i386/elan-mmcr.c user/jeff/numa/sys/i386/i386/mp_clock.c user/jeff/numa/sys/i386/i386/pmap.c user/jeff/numa/sys/i386/i386/trap.c user/jeff/numa/sys/i386/include/param.h user/jeff/numa/sys/kern/imgact_gzip.c user/jeff/numa/sys/kern/inflate.c user/jeff/numa/sys/kern/kern_tc.c user/jeff/numa/sys/kern/md4c.c user/jeff/numa/sys/kern/sched_ule.c user/jeff/numa/sys/kern/subr_disk.c user/jeff/numa/sys/kern/subr_kdb.c user/jeff/numa/sys/kern/subr_prf.c user/jeff/numa/sys/kern/sys_generic.c user/jeff/numa/sys/kern/vfs_cache.c user/jeff/numa/sys/kern/vfs_extattr.c user/jeff/numa/sys/mips/broadcom/bhnd_nexus.c user/jeff/numa/sys/mips/conf/OCTEON1 user/jeff/numa/sys/mips/include/cdefs.h user/jeff/numa/sys/mips/include/setjmp.h user/jeff/numa/sys/mips/mips/machdep.c user/jeff/numa/sys/modules/Makefile user/jeff/numa/sys/modules/aic7xxx/ahc/Makefile user/jeff/numa/sys/modules/aic7xxx/ahd/Makefile user/jeff/numa/sys/modules/bwn/Makefile user/jeff/numa/sys/modules/bwn_pci/Makefile user/jeff/numa/sys/modules/dtb/allwinner/Makefile user/jeff/numa/sys/modules/vmm/Makefile user/jeff/numa/sys/net/if.h user/jeff/numa/sys/net/if_tap.c user/jeff/numa/sys/net/if_tun.c user/jeff/numa/sys/net/if_vlan_var.h user/jeff/numa/sys/net/if_vxlan.c user/jeff/numa/sys/net/iflib.c user/jeff/numa/sys/net/iflib.h user/jeff/numa/sys/net/route.c user/jeff/numa/sys/net/sff8472.h user/jeff/numa/sys/net80211/ieee80211_proto.c user/jeff/numa/sys/net80211/ieee80211_proto.h user/jeff/numa/sys/netinet/sctp_crc32.c user/jeff/numa/sys/netinet/sctp_crc32.h user/jeff/numa/sys/netinet/sctp_input.c user/jeff/numa/sys/netinet/sctp_input.h user/jeff/numa/sys/netinet/sctp_output.c user/jeff/numa/sys/netinet/sctp_sysctl.c user/jeff/numa/sys/netinet/sctp_uio.h user/jeff/numa/sys/netinet/tcp_output.c user/jeff/numa/sys/netinet/tcp_var.h user/jeff/numa/sys/netinet6/frag6.c user/jeff/numa/sys/netinet6/icmp6.c user/jeff/numa/sys/netinet6/in6.h user/jeff/numa/sys/netinet6/nd6_nbr.c user/jeff/numa/sys/netinet6/nd6_rtr.c user/jeff/numa/sys/netinet6/sctp6_usrreq.c user/jeff/numa/sys/netipsec/key.c user/jeff/numa/sys/netpfil/pf/if_pflog.c user/jeff/numa/sys/netpfil/pf/if_pfsync.c user/jeff/numa/sys/netpfil/pf/in4_cksum.c user/jeff/numa/sys/netpfil/pf/pf.h user/jeff/numa/sys/netpfil/pf/pf_osfp.c user/jeff/numa/sys/opencrypto/xform_userland.h user/jeff/numa/sys/powerpc/booke/pmap.c user/jeff/numa/sys/powerpc/conf/GENERIC user/jeff/numa/sys/powerpc/conf/GENERIC64 user/jeff/numa/sys/powerpc/include/profile.h user/jeff/numa/sys/powerpc/include/trap.h user/jeff/numa/sys/powerpc/mpc85xx/fsl_diu.c user/jeff/numa/sys/powerpc/powerpc/cpu.c user/jeff/numa/sys/powerpc/powerpc/pmap_dispatch.c user/jeff/numa/sys/powerpc/powerpc/trap.c user/jeff/numa/sys/powerpc/powerpc/vm_machdep.c user/jeff/numa/sys/riscv/include/profile.h user/jeff/numa/sys/riscv/riscv/pmap.c user/jeff/numa/sys/sparc64/conf/GENERIC user/jeff/numa/sys/sparc64/include/profile.h user/jeff/numa/sys/sparc64/pci/sbbc.c user/jeff/numa/sys/sparc64/sparc64/pmap.c user/jeff/numa/sys/sys/_ucontext.h user/jeff/numa/sys/sys/_vm_domain.h user/jeff/numa/sys/sys/auxv.h user/jeff/numa/sys/sys/bus_dma.h user/jeff/numa/sys/sys/bus_dma_internal.h user/jeff/numa/sys/sys/capsicum.h user/jeff/numa/sys/sys/cdefs.h user/jeff/numa/sys/sys/cnv.h user/jeff/numa/sys/sys/devmap.h user/jeff/numa/sys/sys/disk.h user/jeff/numa/sys/sys/disk_zone.h user/jeff/numa/sys/sys/dnv.h user/jeff/numa/sys/sys/dtrace_bsd.h user/jeff/numa/sys/sys/errno.h user/jeff/numa/sys/sys/fbio.h user/jeff/numa/sys/sys/gpio.h user/jeff/numa/sys/sys/gtaskqueue.h user/jeff/numa/sys/sys/gzio.h user/jeff/numa/sys/sys/imgact_binmisc.h user/jeff/numa/sys/sys/intr.h user/jeff/numa/sys/sys/iov.h user/jeff/numa/sys/sys/iov_schema.h user/jeff/numa/sys/sys/md4.h user/jeff/numa/sys/sys/md5.h user/jeff/numa/sys/sys/mouse.h user/jeff/numa/sys/sys/msg.h user/jeff/numa/sys/sys/numa.h user/jeff/numa/sys/sys/nv.h user/jeff/numa/sys/sys/rman.h user/jeff/numa/sys/sys/smp.h user/jeff/numa/sys/sys/snoop.h user/jeff/numa/sys/sys/socketvar.h user/jeff/numa/sys/sys/soundcard.h user/jeff/numa/sys/sys/spigenio.h user/jeff/numa/sys/sys/syslimits.h user/jeff/numa/sys/sys/tiio.h user/jeff/numa/sys/sys/timepps.h user/jeff/numa/sys/sys/timetc.h user/jeff/numa/sys/sys/zlib.h user/jeff/numa/sys/ufs/ffs/ffs_alloc.c user/jeff/numa/sys/ufs/ufs/ufs_dirhash.c user/jeff/numa/sys/vm/default_pager.c user/jeff/numa/sys/vm/vm.h user/jeff/numa/sys/vm/vm_domain.c user/jeff/numa/sys/vm/vm_domain.h user/jeff/numa/sys/vm/vm_fault.c user/jeff/numa/sys/vm/vm_glue.c user/jeff/numa/sys/vm/vm_init.c user/jeff/numa/sys/vm/vm_kern.c user/jeff/numa/sys/vm/vm_kern.h user/jeff/numa/sys/vm/vm_map.c user/jeff/numa/sys/vm/vm_map.h user/jeff/numa/sys/vm/vm_object.c user/jeff/numa/sys/vm/vm_object.h user/jeff/numa/sys/vm/vm_page.c user/jeff/numa/sys/vm/vm_page.h user/jeff/numa/sys/vm/vm_pageout.c user/jeff/numa/sys/vm/vm_pageout.h user/jeff/numa/sys/vm/vm_pager.c user/jeff/numa/sys/vm/vm_param.h user/jeff/numa/sys/vm/vm_phys.c user/jeff/numa/sys/vm/vm_swapout.c user/jeff/numa/sys/vm/vm_swapout_dummy.c user/jeff/numa/sys/x86/cpufreq/hwpstate.c user/jeff/numa/sys/x86/include/x86_smp.h user/jeff/numa/sys/x86/isa/isa.c user/jeff/numa/targets/pseudo/userland/Makefile.depend user/jeff/numa/targets/pseudo/userland/lib/Makefile.depend user/jeff/numa/tests/sys/Makefile user/jeff/numa/tests/sys/geom/class/geom_subr.sh user/jeff/numa/tests/sys/geom/class/mirror/8_test.sh user/jeff/numa/tests/sys/geom/class/mirror/9_test.sh user/jeff/numa/tests/sys/geom/class/mirror/Makefile user/jeff/numa/tests/sys/geom/class/mirror/conf.sh user/jeff/numa/tests/sys/geom/class/nop/nop_test.sh user/jeff/numa/tools/boot/universe.sh user/jeff/numa/tools/build/mk/OptionalObsoleteFiles.inc user/jeff/numa/tools/diag/README user/jeff/numa/tools/tools/kernxref/kernxref.sh user/jeff/numa/tools/tools/nanobsd/embedded/common user/jeff/numa/tools/tools/nanobsd/embedded/qemu-amd64.cfg user/jeff/numa/tools/tools/nanobsd/nanobsd.sh user/jeff/numa/tools/tools/netmap/pkt-gen.c user/jeff/numa/usr.bin/at/parsetime.c user/jeff/numa/usr.bin/ctlstat/ctlstat.c user/jeff/numa/usr.bin/dc/Makefile user/jeff/numa/usr.bin/dc/bcode.c user/jeff/numa/usr.bin/dc/bcode.h user/jeff/numa/usr.bin/dc/dc.1 user/jeff/numa/usr.bin/dc/extern.h user/jeff/numa/usr.bin/dc/inout.c user/jeff/numa/usr.bin/dc/mem.c user/jeff/numa/usr.bin/diff/diffreg.c user/jeff/numa/usr.bin/find/extern.h user/jeff/numa/usr.bin/find/main.c user/jeff/numa/usr.bin/fmt/fmt.1 user/jeff/numa/usr.bin/gencat/gencat.c user/jeff/numa/usr.bin/grep/tests/grep_freebsd_test.sh user/jeff/numa/usr.bin/gzip/Makefile user/jeff/numa/usr.bin/gzip/gzip.c user/jeff/numa/usr.bin/ipcs/ipc.c user/jeff/numa/usr.bin/logger/logger.1 user/jeff/numa/usr.bin/logger/logger.c user/jeff/numa/usr.bin/man/man.sh user/jeff/numa/usr.bin/ministat/ministat.c user/jeff/numa/usr.bin/sdiff/Makefile user/jeff/numa/usr.bin/sdiff/sdiff.c user/jeff/numa/usr.bin/sdiotool/brcmfmac_bus.h user/jeff/numa/usr.bin/sdiotool/brcmfmac_sdio.h user/jeff/numa/usr.bin/sdiotool/cam_sdio.h user/jeff/numa/usr.bin/sdiotool/linux_compat.h user/jeff/numa/usr.bin/sdiotool/linux_sdio_compat.h user/jeff/numa/usr.bin/su/su.c user/jeff/numa/usr.bin/systat/sctp.c user/jeff/numa/usr.bin/truss/syscall.h user/jeff/numa/usr.bin/vmstat/Makefile user/jeff/numa/usr.bin/vmstat/vmstat.c user/jeff/numa/usr.bin/wc/wc.c user/jeff/numa/usr.sbin/Makefile user/jeff/numa/usr.sbin/acpi/acpiconf/acpiconf.c user/jeff/numa/usr.sbin/bhyveload/bhyveload.c user/jeff/numa/usr.sbin/bsdinstall/partedit/gpart_ops.c user/jeff/numa/usr.sbin/bsdinstall/partedit/partedit.h user/jeff/numa/usr.sbin/bsdinstall/partedit/partedit_arm64.c user/jeff/numa/usr.sbin/bsdinstall/partedit/partedit_generic.c user/jeff/numa/usr.sbin/bsdinstall/partedit/partedit_powerpc.c user/jeff/numa/usr.sbin/bsdinstall/partedit/partedit_sparc64.c user/jeff/numa/usr.sbin/bsdinstall/partedit/partedit_x86.c user/jeff/numa/usr.sbin/bsnmpd/modules/snmp_hostres/hostres_snmp.c user/jeff/numa/usr.sbin/ctm/ctm/ctm.c user/jeff/numa/usr.sbin/ctm/ctm/ctm_ed.c user/jeff/numa/usr.sbin/ctm/ctm/ctm_input.c user/jeff/numa/usr.sbin/ctm/ctm/ctm_pass1.c user/jeff/numa/usr.sbin/ctm/ctm/ctm_pass2.c user/jeff/numa/usr.sbin/ctm/ctm/ctm_pass3.c user/jeff/numa/usr.sbin/ctm/ctm/ctm_passb.c user/jeff/numa/usr.sbin/ctm/ctm/ctm_syntax.c user/jeff/numa/usr.sbin/efidp/Makefile user/jeff/numa/usr.sbin/efidp/efidp.8 user/jeff/numa/usr.sbin/efidp/efidp.c user/jeff/numa/usr.sbin/efivar/Makefile user/jeff/numa/usr.sbin/efivar/efiutil.c user/jeff/numa/usr.sbin/fdformat/Makefile user/jeff/numa/usr.sbin/fdwrite/fdwrite.c user/jeff/numa/usr.sbin/mailwrapper/Makefile user/jeff/numa/usr.sbin/mailwrapper/Makefile.depend user/jeff/numa/usr.sbin/mailwrapper/mailwrapper.c user/jeff/numa/usr.sbin/newsyslog/newsyslog.c user/jeff/numa/usr.sbin/ppp/arp.c user/jeff/numa/usr.sbin/pw/psdate.c user/jeff/numa/usr.sbin/pw/psdate.h user/jeff/numa/usr.sbin/pw/pw.8 user/jeff/numa/usr.sbin/pw/pw.h user/jeff/numa/usr.sbin/pw/pw_conf.c user/jeff/numa/usr.sbin/pw/pw_user.c user/jeff/numa/usr.sbin/rarpd/rarpd.c user/jeff/numa/usr.sbin/syslogd/syslogd.8 user/jeff/numa/usr.sbin/syslogd/syslogd.c user/jeff/numa/usr.sbin/watch/watch.c Directory Properties: user/jeff/numa/ (props changed) user/jeff/numa/cddl/ (props changed) user/jeff/numa/cddl/contrib/opensolaris/ (props changed) user/jeff/numa/contrib/binutils/ (props changed) user/jeff/numa/contrib/compiler-rt/ (props changed) user/jeff/numa/contrib/dma/ (props changed) user/jeff/numa/contrib/less/ (props changed) user/jeff/numa/contrib/libc++/ (props changed) user/jeff/numa/contrib/llvm/ (props changed) user/jeff/numa/contrib/llvm/tools/clang/ (props changed) user/jeff/numa/contrib/llvm/tools/lld/ (props changed) user/jeff/numa/contrib/llvm/tools/lldb/ (props changed) user/jeff/numa/contrib/mdocml/ (props changed) user/jeff/numa/contrib/tcpdump/ (props changed) user/jeff/numa/crypto/openssl/ (props changed) user/jeff/numa/sys/cddl/contrib/opensolaris/ (props changed) user/jeff/numa/sys/contrib/dev/acpica/ (props changed) user/jeff/numa/sys/contrib/zstd/ (props changed) Modified: user/jeff/numa/.arclint ============================================================================== --- user/jeff/numa/.arclint Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/.arclint Fri Dec 15 23:50:26 2017 (r326890) @@ -9,7 +9,8 @@ "type": "spelling" }, "chmod": { - "type": "chmod" + "type": "chmod", + "exclude": "(/tests/)" }, "merge-conflict": { "type": "merge-conflict" @@ -23,3 +24,4 @@ } } } + Modified: user/jeff/numa/Makefile ============================================================================== --- user/jeff/numa/Makefile Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/Makefile Fri Dec 15 23:50:26 2017 (r326890) @@ -577,7 +577,7 @@ universe_${target}_kernels: universe_${target}_prologu "check _.${target}.makeLINT for details"| ${MAKEFAIL})) .endif @cd ${.CURDIR}; ${SUB_MAKE} ${.MAKEFLAGS} TARGET=${target} \ - universe_kernels MK_AUTO_OBJ=no + universe_kernels .endif # !MAKE_JUST_WORLDS # Tell the user the worlds and kernels have completed @@ -585,6 +585,7 @@ universe_${target}: universe_${target}_done universe_${target}_done: @echo ">> ${target} completed on `LC_ALL=C date`" .endfor +.if make(universe_kernconfs) || make(universe_kernels) universe_kernels: universe_kernconfs .PHONY .if !defined(TARGET) TARGET!= uname -m @@ -621,6 +622,7 @@ universe_kernconf_${TARGET}_${kernel}: .MAKE (echo "${TARGET} ${kernel} kernel failed," \ "check _.${TARGET}.${kernel} for details"| ${MAKEFAIL})) .endfor +.endif # make(universe_kernels) universe: universe_epilogue universe_epilogue: .PHONY @echo "--------------------------------------------------------------" Modified: user/jeff/numa/Makefile.inc1 ============================================================================== --- user/jeff/numa/Makefile.inc1 Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/Makefile.inc1 Fri Dec 15 23:50:26 2017 (r326890) @@ -641,9 +641,9 @@ XCXXFLAGS+= -isystem ${WORLDTMP}/usr/include/c++/v1 -s .elif ${WANT_COMPILER_TYPE} == clang || \ (defined(X_COMPILER_TYPE) && ${X_COMPILER_TYPE} == clang) MACHINE_ABI?= unknown -MACHINE_TRIPLE?=${MACHINE_ARCH:C/amd64/x86_64/}-${MACHINE_ABI}-freebsd12.0 +MACHINE_TRIPLE?=${MACHINE_ARCH:S/amd64/x86_64/:C/hf$//:S/mipsn32/mips64/}-${MACHINE_ABI}-freebsd12.0 TARGET_ABI?= unknown -TARGET_TRIPLE?= ${TARGET_ARCH:C/amd64/x86_64/}-${TARGET_ABI}-freebsd12.0 +TARGET_TRIPLE?= ${TARGET_ARCH:S/amd64/x86_64/:C/hf$//:S/mipsn32/mips64/}-${TARGET_ABI}-freebsd12.0 XCFLAGS+= -target ${TARGET_TRIPLE} .endif XCFLAGS+= --sysroot=${WORLDTMP} @@ -2261,7 +2261,7 @@ NXBMAKE+= SUBDIR_OVERRIDE='$${NXBDIRS:M*}' # even if the TARGET being built for wants GCC. NXBMAKE+= WANT_COMPILER_TYPE='$${X_COMPILER_TYPE}' native-xtools: .PHONY - ${_+_}cd ${.CURDIR}; ${NXBTMAKE} _cleanobj + ${_+_}cd ${.CURDIR}; ${NXBTMAKE} _cleanobj MK_GCC=yes # Build the bootstrap/host/cross tools that produce native binaries # Pass along MK_GCC=yes to ensure GCC-needed build tools are built. # We don't quite know what the NXB_TARGET wants so just build it. @@ -2274,6 +2274,8 @@ native-xtools: .PHONY # needed build tools are built. ${_+_}cd ${.CURDIR}; ${NXBTMAKE} _includes MK_CLANG=no MK_GCC=no ${_+_}cd ${.CURDIR}; ${NXBTMAKE} _libraries MK_CLANG=no MK_GCC=no + # Clean out improper TARGET=MACHINE files + ${_+_}cd ${.CURDIR}/gnu/usr.bin/cc/cc_tools; ${NXBTMAKE} cleandir .if !defined(NO_OBJWALK) ${_+_}cd ${.CURDIR}; ${NXBMAKE} _obj .endif Modified: user/jeff/numa/Makefile.sys.inc ============================================================================== --- user/jeff/numa/Makefile.sys.inc Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/Makefile.sys.inc Fri Dec 15 23:50:26 2017 (r326890) @@ -38,6 +38,10 @@ MK_AUTO_OBJ= no # just want to read any existing OBJDIR but we don't care if we can create # or write to them. .MAKEOVERRIDES+= MK_AUTO_OBJ +.else +# For top-level we always assume the MAKEOBJDIRPREFIX is writable rather than +# falling back to .CURDIR. +__objdir_writable= yes .endif .endif # empty(.MAKEOVERRIDES:MMK_AUTO_OBJ) Modified: user/jeff/numa/ObsoleteFiles.inc ============================================================================== --- user/jeff/numa/ObsoleteFiles.inc Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/ObsoleteFiles.inc Fri Dec 15 23:50:26 2017 (r326890) @@ -38,6 +38,130 @@ # xargs -n1 | sort | uniq -d; # done +# 20171208: Remove basename_r(3) +OLD_FILES+=usr/share/man/man3/basename_r.3.gz +# 20171204: Move fdformat man page from volume 1 to volume 8. +OLD_FILES+=usr/share/man/man1/fdformat.1.gz +# 20171203: libproc version bump +OLD_LIBS+=usr/lib/libproc.so.4 +OLD_LIBS+=usr/lib32/libproc.so.4 +# 20171203: new clang import which bumps version from 5.0.0 to 5.0.1. +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/allocator_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/asan_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/common_interface_defs.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/coverage_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/dfsan_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/esan_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/linux_syscall_hooks.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/lsan_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/msan_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/tsan_interface.h +OLD_FILES+=usr/lib/clang/5.0.0/include/sanitizer/tsan_interface_atomic.h +OLD_DIRS+=usr/lib/clang/5.0.0/include/sanitizer +OLD_FILES+=usr/lib/clang/5.0.0/include/__clang_cuda_builtin_vars.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__clang_cuda_cmath.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__clang_cuda_complex_builtins.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__clang_cuda_intrinsics.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__clang_cuda_math_forward_declares.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__clang_cuda_runtime_wrapper.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__stddef_max_align_t.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__wmmintrin_aes.h +OLD_FILES+=usr/lib/clang/5.0.0/include/__wmmintrin_pclmul.h +OLD_FILES+=usr/lib/clang/5.0.0/include/adxintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/altivec.h +OLD_FILES+=usr/lib/clang/5.0.0/include/ammintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/arm_acle.h +OLD_FILES+=usr/lib/clang/5.0.0/include/arm_neon.h +OLD_FILES+=usr/lib/clang/5.0.0/include/armintr.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx2intrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512bwintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512cdintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512dqintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512erintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512fintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512ifmaintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512ifmavlintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512pfintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512vbmiintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512vbmivlintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512vlbwintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512vlcdintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512vldqintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512vlintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avx512vpopcntdqintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/avxintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/bmi2intrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/bmiintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/clflushoptintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/clzerointrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/cpuid.h +OLD_FILES+=usr/lib/clang/5.0.0/include/emmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/f16cintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/fma4intrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/fmaintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/fxsrintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/htmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/htmxlintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/ia32intrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/immintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/lwpintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/lzcntintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/mm3dnow.h +OLD_FILES+=usr/lib/clang/5.0.0/include/mm_malloc.h +OLD_FILES+=usr/lib/clang/5.0.0/include/mmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/module.modulemap +OLD_FILES+=usr/lib/clang/5.0.0/include/msa.h +OLD_FILES+=usr/lib/clang/5.0.0/include/mwaitxintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/nmmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/opencl-c.h +OLD_FILES+=usr/lib/clang/5.0.0/include/pkuintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/pmmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/popcntintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/prfchwintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/rdseedintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/rtmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/s390intrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/shaintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/smmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/tbmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/tmmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/vadefs.h +OLD_FILES+=usr/lib/clang/5.0.0/include/vecintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/wmmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/x86intrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/xmmintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/xopintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/xsavecintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/xsaveintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/xsaveoptintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/xsavesintrin.h +OLD_FILES+=usr/lib/clang/5.0.0/include/xtestintrin.h +OLD_DIRS+=usr/lib/clang/5.0.0/include +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan-i386.so +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan-preinit-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan-preinit-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan-x86_64.so +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan_cxx-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.asan_cxx-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.profile-arm.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.profile-armhf.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.profile-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.profile-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.safestack-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.safestack-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.stats-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.stats-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.stats_client-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.stats_client-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.ubsan_standalone-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.ubsan_standalone-x86_64.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.ubsan_standalone_cxx-i386.a +OLD_FILES+=usr/lib/clang/5.0.0/lib/freebsd/libclang_rt.ubsan_standalone_cxx-x86_64.a +OLD_DIRS+=usr/lib/clang/5.0.0/lib/freebsd +OLD_DIRS+=usr/lib/clang/5.0.0/lib +OLD_DIRS+=usr/lib/clang/5.0.0 # 20171118: Remove old etc casper files OLD_FILES+=etc/casper/system.dns OLD_FILES+=etc/casper/system.grp Modified: user/jeff/numa/README ============================================================================== --- user/jeff/numa/README Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/README Fri Dec 15 23:50:26 2017 (r326890) @@ -66,6 +66,8 @@ secure Cryptographic libraries and commands. share Shared resources. +stand Boot loader sources. + sys Kernel sources. tests Regression tests which can be run by Kyua. See tests/README Modified: user/jeff/numa/README.md ============================================================================== --- user/jeff/numa/README.md Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/README.md Fri Dec 15 23:50:26 2017 (r326890) @@ -68,6 +68,8 @@ secure Cryptographic libraries and commands. share Shared resources. +stand Boot loader sources. + sys Kernel sources. tests Regression tests which can be run by Kyua. See tests/README Modified: user/jeff/numa/UPDATING ============================================================================== --- user/jeff/numa/UPDATING Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/UPDATING Fri Dec 15 23:50:26 2017 (r326890) @@ -51,6 +51,16 @@ NOTE TO PEOPLE WHO THINK THAT FreeBSD 12.x IS SLOW: ****************************** SPECIAL WARNING: ****************************** +20171215: + r326887 fixes the issue described in the 20171214 UPDATING entry. + r326888 flips the switch back to building GELI support always. + +20171214: + r362593 broke ZFS + GELI support for reasons unknown. However, + it also broke ZFS support generally, so GELI has been turned off + by default as the lessor evil in r326857. If you boot off ZFS and/or + GELI, it might not be a good time to update. + 20171125: PowerPC users must update loader(8) by rebuilding world before installing a new kernel, as the protocol connecting them has Modified: user/jeff/numa/bin/cat/cat.1 ============================================================================== --- user/jeff/numa/bin/cat/cat.1 Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/bin/cat/cat.1 Fri Dec 15 23:50:26 2017 (r326890) @@ -195,8 +195,8 @@ utility appeared in .At v1 . .An Dennis Ritchie designed and wrote the first man page. -It appears to have been -.Xr cat 1 . +It appears to have been for +.Nm . .Sh BUGS Because of the shell language mechanism used to perform output redirection, the command Modified: user/jeff/numa/bin/date/date.1 ============================================================================== --- user/jeff/numa/bin/date/date.1 Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/bin/date/date.1 Fri Dec 15 23:50:26 2017 (r326890) @@ -131,7 +131,8 @@ The option suppresses this behavior and causes the time to be set only on the current machine. .It Fl R -Use RFC 2822 date and time output format. This is equivalent to use +Use RFC 2822 date and time output format. +This is equivalent to using .Dq Li %a, %d %b %Y \&%T %z as .Ar output_fmt Modified: user/jeff/numa/bin/kenv/kenv.1 ============================================================================== --- user/jeff/numa/bin/kenv/kenv.1 Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/bin/kenv/kenv.1 Fri Dec 15 23:50:26 2017 (r326890) @@ -91,11 +91,17 @@ The file can contain lines of the form .Pp .Dl name = "value" # this is a comment .Pp -where whitespace around name and '=', and -everything after a '#' character, are ignored. Almost any printable -character except '=' is acceptable as part of a name. Quotes -are optional and necessary only if the value contains -whitespace. +where whitespace around +.Sq name +and +.Sq = , +and everything after a +.Sq # +character, are ignored. +Almost any printable character except +.Sq = +is acceptable as part of a name. +Quotes are optional and necessary only if the value contains whitespace. .Sh SEE ALSO .Xr kenv 2 , .Xr config 5 , Modified: user/jeff/numa/bin/ps/keyword.c ============================================================================== --- user/jeff/numa/bin/ps/keyword.c Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/bin/ps/keyword.c Fri Dec 15 23:50:26 2017 (r326890) @@ -225,6 +225,8 @@ static VAR var[] = { {"usertime", "USERTIME", NULL, "user-time", USER, usertime, 0, CHAR, NULL, 0}, {"usrpri", "", "upr", NULL, 0, NULL, 0, CHAR, NULL, 0}, + {"vmaddr", "VMADDR", NULL, "vmspace-address", 0, kvar, KOFF(ki_vmspace), + KPTR, "lx", 0}, {"vsize", "", "vsz", NULL, 0, NULL, 0, CHAR, NULL, 0}, {"vsz", "VSZ", NULL, "virtual-size", 0, vsize, 0, CHAR, NULL, 0}, {"wchan", "WCHAN", NULL, "wait-channel", LJUST, wchan, 0, CHAR, NULL, Modified: user/jeff/numa/bin/ps/ps.1 ============================================================================== --- user/jeff/numa/bin/ps/ps.1 Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/bin/ps/ps.1 Fri Dec 15 23:50:26 2017 (r326890) @@ -29,7 +29,7 @@ .\" @(#)ps.1 8.3 (Berkeley) 4/18/94 .\" $FreeBSD$ .\" -.Dd October 9, 2017 +.Dd December 1, 2017 .Dt PS 1 .Os .Sh NAME @@ -710,6 +710,8 @@ process pointer user name (from UID) .It Cm usertime accumulated user CPU time +.It Cm vmaddr +vmspace pointer .It Cm vsz virtual size in Kbytes (alias .Cm vsize ) Modified: user/jeff/numa/bin/setfacl/setfacl.1 ============================================================================== --- user/jeff/numa/bin/setfacl/setfacl.1 Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/bin/setfacl/setfacl.1 Fri Dec 15 23:50:26 2017 (r326890) @@ -114,7 +114,8 @@ is the input is taken from stdin. .It Fl n Do not recalculate the permissions associated with the ACL -mask entry. This option is not applicable to NFSv4 ACLs. +mask entry. +This option is not applicable to NFSv4 ACLs. .It Fl x Ar entries | position If .Ar entries @@ -291,7 +292,8 @@ specifying the access granted to the owner of the file .Dq Li group@ specifying the access granted to the file owning group; .Dq Li everyone@ -specifying everyone. Note that +specifying everyone. +Note that .Dq Li everyone@ is not the same as traditional Unix .Dq Li other @@ -301,8 +303,8 @@ literally, everyone, including file owner and owning g The ACL qualifier field describes the user or group associated with the ACL entry. It may consist of one of the following: uid or -user name, or gid or group name. In entries whose tag type is -one of +user name, or gid or group name. +In entries whose tag type is one of .Dq Li owner@ , .Dq Li group@ , or Modified: user/jeff/numa/bin/sh/sh.1 ============================================================================== --- user/jeff/numa/bin/sh/sh.1 Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/bin/sh/sh.1 Fri Dec 15 23:50:26 2017 (r326890) @@ -1033,7 +1033,7 @@ The syntax of the command is: .Bd -unfilled -offset indent -compact .Ic case Ar word Ic in -.Ar pattern Ns ) Ar list Li ;; +.Ar pattern ) Ar list Li ;; .Ar ... .Ic esac .Ed Modified: user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_open.c ============================================================================== --- user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_open.c Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_open.c Fri Dec 15 23:50:26 2017 (r326890) @@ -1182,7 +1182,7 @@ alloc: #endif dtp->dt_provbuckets = _dtrace_strbuckets; dtp->dt_provs = calloc(dtp->dt_provbuckets, sizeof (dt_provider_t *)); - dt_proc_hash_create(dtp); + dt_proc_init(dtp); dtp->dt_vmax = DT_VERS_LATEST; dtp->dt_cpp_path = strdup(_dtrace_defcpp); dtp->dt_cpp_argv = malloc(sizeof (char *)); @@ -1199,12 +1199,13 @@ alloc: (void) uname(&dtp->dt_uts); if (dtp->dt_mods == NULL || dtp->dt_provs == NULL || - dtp->dt_procs == NULL || dtp->dt_ld_path == NULL || + dtp->dt_procs == NULL || dtp->dt_proc_env == NULL || + dtp->dt_ld_path == NULL || dtp->dt_cpp_path == NULL || #ifdef __FreeBSD__ dtp->dt_kmods == NULL || dtp->dt_objcopy_path == NULL || #endif - dtp->dt_cpp_path == NULL || dtp->dt_cpp_argv == NULL) + dtp->dt_cpp_argv == NULL) return (set_open_errno(dtp, errp, EDT_NOMEM)); for (i = 0; i < DTRACEOPT_MAX; i++) @@ -1631,7 +1632,7 @@ dtrace_close(dtrace_hdl_t *dtp) int i; if (dtp->dt_procs != NULL) - dt_proc_hash_destroy(dtp); + dt_proc_fini(dtp); while ((pgp = dt_list_next(&dtp->dt_programs)) != NULL) dt_program_destroy(dtp, pgp); Modified: user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.c ============================================================================== --- user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.c Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.c Fri Dec 15 23:50:26 2017 (r326890) @@ -25,6 +25,10 @@ */ /* + * Copyright (c) 2012 by Delphix. All rights reserved. + */ + +/* * DTrace Process Control * * This file provides a set of routines that permit libdtrace and its clients @@ -504,7 +508,7 @@ dt_proc_control(void *arg) dt_proc_control_data_t *datap = arg; dtrace_hdl_t *dtp = datap->dpcd_hdl; dt_proc_t *dpr = datap->dpcd_proc; - dt_proc_hash_t *dph = dpr->dpr_hdl->dt_procs; + dt_proc_hash_t *dph = dtp->dt_procs; struct ps_prochandle *P = dpr->dpr_proc; int pid = dpr->dpr_pid; @@ -965,14 +969,18 @@ dt_proc_create(dtrace_hdl_t *dtp, const char *file, ch (void) pthread_cond_init(&dpr->dpr_cv, NULL); #ifdef illumos - if ((dpr->dpr_proc = Pcreate(file, argv, &err, NULL, 0)) == NULL) { + dpr->dpr_proc = Pxcreate(file, argv, dtp->dt_proc_env, &err, NULL, 0); + if (dpr->dpr_proc == NULL) { + return (dt_proc_error(dtp, dpr, + "failed to execute %s: %s\n", file, Pcreate_error(err))); + } #else - if ((err = proc_create(file, argv, pcf, child_arg, + if ((err = proc_create(file, argv, dtp->dt_proc_env, pcf, child_arg, &dpr->dpr_proc)) != 0) { -#endif return (dt_proc_error(dtp, dpr, "failed to execute %s: %s\n", file, Pcreate_error(err))); } +#endif dpr->dpr_hdl = dtp; #ifdef illumos @@ -1141,30 +1149,74 @@ dt_proc_unlock(dtrace_hdl_t *dtp, struct ps_prochandle } void -dt_proc_hash_create(dtrace_hdl_t *dtp) +dt_proc_init(dtrace_hdl_t *dtp) { + extern char **environ; + static char *envdef[] = { + "LD_NOLAZYLOAD=1", /* linker lazy loading hides funcs */ + NULL + }; + char **p; + int i; + if ((dtp->dt_procs = dt_zalloc(dtp, sizeof (dt_proc_hash_t) + - sizeof (dt_proc_t *) * _dtrace_pidbuckets - 1)) != NULL) { + sizeof (dt_proc_t *) * _dtrace_pidbuckets - 1)) == NULL) + return; - (void) pthread_mutex_init(&dtp->dt_procs->dph_lock, NULL); - (void) pthread_cond_init(&dtp->dt_procs->dph_cv, NULL); + (void) pthread_mutex_init(&dtp->dt_procs->dph_lock, NULL); + (void) pthread_cond_init(&dtp->dt_procs->dph_cv, NULL); - dtp->dt_procs->dph_hashlen = _dtrace_pidbuckets; - dtp->dt_procs->dph_lrulim = _dtrace_pidlrulim; + dtp->dt_procs->dph_hashlen = _dtrace_pidbuckets; + dtp->dt_procs->dph_lrulim = _dtrace_pidlrulim; + + /* + * Count how big our environment needs to be. + */ + for (i = 1, p = environ; *p != NULL; i++, p++) + continue; + for (p = envdef; *p != NULL; i++, p++) + continue; + + if ((dtp->dt_proc_env = dt_zalloc(dtp, sizeof (char *) * i)) == NULL) + return; + + for (i = 0, p = environ; *p != NULL; i++, p++) { + if ((dtp->dt_proc_env[i] = strdup(*p)) == NULL) + goto err; } + for (p = envdef; *p != NULL; i++, p++) { + if ((dtp->dt_proc_env[i] = strdup(*p)) == NULL) + goto err; + } + + return; + +err: + while (--i != 0) { + dt_free(dtp, dtp->dt_proc_env[i]); + } + dt_free(dtp, dtp->dt_proc_env); + dtp->dt_proc_env = NULL; } void -dt_proc_hash_destroy(dtrace_hdl_t *dtp) +dt_proc_fini(dtrace_hdl_t *dtp) { dt_proc_hash_t *dph = dtp->dt_procs; dt_proc_t *dpr; + char **p; while ((dpr = dt_list_next(&dph->dph_lrulist)) != NULL) dt_proc_destroy(dtp, dpr->dpr_proc); dtp->dt_procs = NULL; dt_free(dtp, dph); + + for (p = dtp->dt_proc_env; *p != NULL; p++) + dt_free(dtp, *p); + + dt_free(dtp, dtp->dt_proc_env); + dtp->dt_proc_env = NULL; } struct ps_prochandle * Modified: user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.h ============================================================================== --- user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.h Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/cddl/contrib/opensolaris/lib/libdtrace/common/dt_proc.h Fri Dec 15 23:50:26 2017 (r326890) @@ -24,11 +24,13 @@ * Use is subject to license terms. */ +/* + * Copyright (c) 2012 by Delphix. All rights reserved. + */ + #ifndef _DT_PROC_H #define _DT_PROC_H -#pragma ident "%Z%%M% %I% %E% SMI" - #include #include #include @@ -106,8 +108,8 @@ extern void dt_proc_lock(dtrace_hdl_t *, struct ps_pro extern void dt_proc_unlock(dtrace_hdl_t *, struct ps_prochandle *); extern dt_proc_t *dt_proc_lookup(dtrace_hdl_t *, struct ps_prochandle *, int); -extern void dt_proc_hash_create(dtrace_hdl_t *); -extern void dt_proc_hash_destroy(dtrace_hdl_t *); +extern void dt_proc_init(dtrace_hdl_t *); +extern void dt_proc_fini(dtrace_hdl_t *); #ifdef __cplusplus } Modified: user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/Makefile ============================================================================== --- user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/Makefile Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/Makefile Fri Dec 15 23:50:26 2017 (r326890) @@ -19,6 +19,7 @@ TESTS_SUBDIRS+= aggs \ drops \ dtraceUtil \ end \ + env \ enum \ error \ exit \ Modified: user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/probes/Makefile ============================================================================== --- user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/probes/Makefile Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/probes/Makefile Fri Dec 15 23:50:26 2017 (r326890) @@ -35,5 +35,4 @@ CFILES= \ tst.probestar.c \ - .include "../../dtrace.test.mk" Modified: user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/speculation/Makefile ============================================================================== --- user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/speculation/Makefile Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/cddl/usr.sbin/dtrace/tests/common/speculation/Makefile Fri Dec 15 23:50:26 2017 (r326890) @@ -70,7 +70,6 @@ ${PACKAGE}FILES= \ TESTEXES= \ tst.NoSpecBuffer.exe \ - CFILES= \ Modified: user/jeff/numa/cddl/usr.sbin/dtrace/tests/tools/exclude.sh ============================================================================== --- user/jeff/numa/cddl/usr.sbin/dtrace/tests/tools/exclude.sh Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/cddl/usr.sbin/dtrace/tests/tools/exclude.sh Fri Dec 15 23:50:26 2017 (r326890) @@ -166,6 +166,9 @@ exclude EXFAIL common/vars/tst.ucaller.ksh exclude EXFAIL common/scripting/tst.projid.ksh exclude EXFAIL common/scripting/tst.taskid.ksh +# Depends on tst.chasestrings.exe being ELF32. See r326181 and r326285. +exclude EXFAIL common/uctf/err.user64mode.ksh + # This test expects its test program to be installed without CTF data, but # the rest of the programs for this feature need CTF data. Not yet sure how # to build that. Modified: user/jeff/numa/contrib/binutils/libiberty/make-relative-prefix.c ============================================================================== --- user/jeff/numa/contrib/binutils/libiberty/make-relative-prefix.c Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/binutils/libiberty/make-relative-prefix.c Fri Dec 15 23:50:26 2017 (r326890) @@ -299,10 +299,18 @@ make_relative_prefix_1 (const char *progname, const ch full_progname = strdup(progname); prog_dirs = split_directories (full_progname, &prog_num); - bin_dirs = split_directories (bin_prefix, &bin_num); + if (prog_dirs == NULL) + { + free (full_progname); + return NULL; + } free (full_progname); - if (bin_dirs == NULL || prog_dirs == NULL) - return NULL; + bin_dirs = split_directories (bin_prefix, &bin_num); + if (bin_dirs == NULL) + { + free_split_directories(prog_dirs); + return NULL; + } /* Remove the program name from comparison of directory names. */ prog_num--; @@ -365,7 +373,12 @@ make_relative_prefix_1 (const char *progname, const ch ret = (char *) malloc (needed_len); if (ret == NULL) - return NULL; + { + free_split_directories (prog_dirs); + free_split_directories (bin_dirs); + free_split_directories (prefix_dirs); + return NULL; + } /* Build up the pathnames in argv[0]. */ *ret = '\0'; Modified: user/jeff/numa/contrib/bsnmp/snmpd/config.c ============================================================================== --- user/jeff/numa/contrib/bsnmp/snmpd/config.c Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/bsnmp/snmpd/config.c Fri Dec 15 23:50:26 2017 (r326890) @@ -663,7 +663,7 @@ gettoken() printf("(EOL)"); break; case TOK_NUM: - printf("(NUM %llu)", numval); + printf("(NUM %ju)", (uintmax_t)numval); break; case TOK_STR: printf("(STR %.*s)", (int)strvallen, strval); Modified: user/jeff/numa/contrib/compiler-rt/lib/builtins/int_lib.h ============================================================================== --- user/jeff/numa/contrib/compiler-rt/lib/builtins/int_lib.h Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/compiler-rt/lib/builtins/int_lib.h Fri Dec 15 23:50:26 2017 (r326890) @@ -55,12 +55,16 @@ #define UNUSED __attribute__((unused)) #endif -#if defined(__NetBSD__) && (defined(_KERNEL) || defined(_STANDALONE)) +#if (defined(__FreeBSD__) || defined(__NetBSD__)) && (defined(_KERNEL) || defined(_STANDALONE)) /* * Kernel and boot environment can't use normal headers, * so use the equivalent system headers. */ +#ifdef __FreeBSD__ +# include +#else # include +#endif # include # include #else Modified: user/jeff/numa/contrib/dma/mail.c ============================================================================== --- user/jeff/numa/contrib/dma/mail.c Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/dma/mail.c Fri Dec 15 23:50:26 2017 (r326890) @@ -41,6 +41,8 @@ #include "dma.h" +#define MAX_LINE_RFC822 1000 + void bounce(struct qitem *it, const char *reason) { @@ -341,19 +343,47 @@ newaddr: goto again; } +static int +writeline(struct queue *queue, const char *line, ssize_t linelen) +{ + ssize_t len; + + while (linelen > 0) { + len = linelen; + if (linelen > MAX_LINE_RFC822) { + len = MAX_LINE_RFC822 - 10; + } + + if (fwrite(line, len, 1, queue->mailf) != 1) + return (-1); + + if (linelen <= MAX_LINE_RFC822) + break; + + if (fwrite("\n", 1, 1, queue->mailf) != 1) + return (-1); + + line += MAX_LINE_RFC822 - 10; + linelen = strlen(line); + } + return (0); +} + int readmail(struct queue *queue, int nodot, int recp_from_header) { struct parse_state parse_state; - char line[1000]; /* by RFC2822 */ - size_t linelen; + char *line = NULL; + ssize_t linelen; + size_t linecap = 0; + char newline[MAX_LINE_RFC822]; size_t error; int had_headers = 0; int had_from = 0; int had_messagid = 0; int had_date = 0; - int had_last_line = 0; int nocopy = 0; + int ret = -1; parse_state.state = NONE; @@ -372,24 +402,17 @@ readmail(struct queue *queue, int nodot, int recp_from return (-1); while (!feof(stdin)) { - if (fgets(line, sizeof(line) - 1, stdin) == NULL) + newline[0] = '\0'; + if ((linelen = getline(&line, &linecap, stdin)) <= 0) break; - if (had_last_line) - errlogx(EX_DATAERR, "bad mail input format:" - " from %s (uid %d) (envelope-from %s)", - username, useruid, queue->sender); - linelen = strlen(line); - if (linelen == 0 || line[linelen - 1] != '\n') { - /* - * This line did not end with a newline character. - * If we fix it, it better be the last line of - * the file. - */ - line[linelen] = '\n'; - line[linelen + 1] = 0; - had_last_line = 1; - } + if (!had_headers) { + if (linelen > MAX_LINE_RFC822) { + /* XXX also split headers */ + errlogx(EX_DATAERR, "bad mail input format:" + " from %s (uid %d) (envelope-from %s)", + username, useruid, queue->sender); + } /* * Unless this is a continuation, switch of * the Bcc: nocopy flag. @@ -430,31 +453,39 @@ readmail(struct queue *queue, int nodot, int recp_from while (!had_date || !had_messagid || !had_from) { if (!had_date) { had_date = 1; - snprintf(line, sizeof(line), "Date: %s\n", rfc822date()); + snprintf(newline, sizeof(newline), "Date: %s\n", rfc822date()); } else if (!had_messagid) { /* XXX msgid, assign earlier and log? */ had_messagid = 1; - snprintf(line, sizeof(line), "Message-Id: <%"PRIxMAX".%s.%"PRIxMAX"@%s>\n", + snprintf(newline, sizeof(newline), "Message-Id: <%"PRIxMAX".%s.%"PRIxMAX"@%s>\n", (uintmax_t)time(NULL), queue->id, (uintmax_t)random(), hostname()); } else if (!had_from) { had_from = 1; - snprintf(line, sizeof(line), "From: <%s>\n", queue->sender); + snprintf(newline, sizeof(newline), "From: <%s>\n", queue->sender); } - if (fwrite(line, strlen(line), 1, queue->mailf) != 1) - return (-1); + if (fwrite(newline, strlen(newline), 1, queue->mailf) != 1) + goto fail; } - strcpy(line, "\n"); + strlcpy(newline, "\n", sizeof(newline)); } if (!nodot && linelen == 2 && line[0] == '.') break; if (!nocopy) { - if (fwrite(line, strlen(line), 1, queue->mailf) != 1) - return (-1); + if (newline[0]) { + if (fwrite(newline, strlen(newline), 1, queue->mailf) != 1) + goto fail; + } else { + if (writeline(queue, line, linelen) != 0) + goto fail; + } } } - return (0); + ret = 0; +fail: + free(line); + return (ret); } Modified: user/jeff/numa/contrib/jemalloc/include/jemalloc/internal/jemalloc_internal_inlines_c.h ============================================================================== --- user/jeff/numa/contrib/jemalloc/include/jemalloc/internal/jemalloc_internal_inlines_c.h Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/jemalloc/include/jemalloc/internal/jemalloc_internal_inlines_c.h Fri Dec 15 23:50:26 2017 (r326890) @@ -91,7 +91,8 @@ idalloctm(tsdn_t *tsdn, void *ptr, tcache_t *tcache, a if (config_stats && is_internal) { arena_internal_sub(iaalloc(tsdn, ptr), isalloc(tsdn, ptr)); } - if (!is_internal && tsd_reentrancy_level_get(tsdn_tsd(tsdn)) != 0) { + if (!is_internal && !tsdn_null(tsdn) && + tsd_reentrancy_level_get(tsdn_tsd(tsdn)) != 0) { assert(tcache == NULL); } arena_dalloc(tsdn, ptr, tcache, alloc_ctx, slow_path); Modified: user/jeff/numa/contrib/less/main.c ============================================================================== --- user/jeff/numa/contrib/less/main.c Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/less/main.c Fri Dec 15 23:50:26 2017 (r326890) @@ -73,7 +73,6 @@ main(argc, argv) { IFILE ifile; char *s; - extern char *__progname; #ifdef __EMX__ _response(&argc, &argv); Modified: user/jeff/numa/contrib/libc++/include/algorithm ============================================================================== --- user/jeff/numa/contrib/libc++/include/algorithm Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/libc++/include/algorithm Fri Dec 15 23:50:26 2017 (r326890) @@ -3013,6 +3013,7 @@ template _UIntType __independent_bits_engine<_Engine, _UIntType>::__eval(true_type) { + const size_t _WRt = numeric_limits::digits; result_type _Sp = 0; for (size_t __k = 0; __k < __n0_; ++__k) { @@ -3021,7 +3022,7 @@ __independent_bits_engine<_Engine, _UIntType>::__eval( { __u = __e_() - _Engine::min(); } while (__u >= __y0_); - if (__w0_ < _WDt) + if (__w0_ < _WRt) _Sp <<= __w0_; else _Sp = 0; @@ -3034,7 +3035,7 @@ __independent_bits_engine<_Engine, _UIntType>::__eval( { __u = __e_() - _Engine::min(); } while (__u >= __y1_); - if (__w0_ < _WDt - 1) + if (__w0_ < _WRt - 1) _Sp <<= __w0_ + 1; else _Sp = 0; Modified: user/jeff/numa/contrib/libc++/include/deque ============================================================================== --- user/jeff/numa/contrib/libc++/include/deque Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/libc++/include/deque Fri Dec 15 23:50:26 2017 (r326890) @@ -1356,7 +1356,6 @@ class _LIBCPP_TEMPLATE_VIS deque (public) iterator insert(const_iterator __p, initializer_list __il) {return insert(__p, __il.begin(), __il.end());} #endif // _LIBCPP_CXX03_LANG - iterator insert(const_iterator __p, const value_type& __v); iterator insert(const_iterator __p, size_type __n, const value_type& __v); template @@ -2224,7 +2223,11 @@ deque<_Tp, _Allocator>::__append(_InpIter __f, _InpIte !__is_forward_iterator<_InpIter>::value>::type*) { for (; __f != __l; ++__f) +#ifdef _LIBCPP_CXX03_LANG push_back(*__f); +#else + emplace_back(*__f); +#endif } template Modified: user/jeff/numa/contrib/libc++/include/functional ============================================================================== --- user/jeff/numa/contrib/libc++/include/functional Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/libc++/include/functional Fri Dec 15 23:50:26 2017 (r326890) @@ -1597,9 +1597,11 @@ class _LIBCPP_TEMPLATE_VIS function<_Rp(_ArgTypes...)> return reinterpret_cast<__base*>(p); } - template ::value && - __invokable<_Fp&, _ArgTypes...>::value> - struct __callable; + template , function>::value>, + __invokable<_Fp&, _ArgTypes...> + >::value> + struct __callable; template struct __callable<_Fp, true> { @@ -1612,6 +1614,9 @@ class _LIBCPP_TEMPLATE_VIS function<_Rp(_ArgTypes...)> { static const bool value = false; }; + + template + using _EnableIfCallable = typename enable_if<__callable<_Fp>::value>::type; public: typedef _Rp result_type; @@ -1622,9 +1627,7 @@ class _LIBCPP_TEMPLATE_VIS function<_Rp(_ArgTypes...)> function(nullptr_t) _NOEXCEPT : __f_(0) {} function(const function&); function(function&&) _NOEXCEPT; - template::value && !is_same<_Fp, function>::value - >::type> + template> function(_Fp); #if _LIBCPP_STD_VER <= 14 @@ -1638,21 +1641,15 @@ class _LIBCPP_TEMPLATE_VIS function<_Rp(_ArgTypes...)> function(allocator_arg_t, const _Alloc&, const function&); template function(allocator_arg_t, const _Alloc&, function&&); - template::value>::type> + template> function(allocator_arg_t, const _Alloc& __a, _Fp __f); #endif function& operator=(const function&); function& operator=(function&&) _NOEXCEPT; function& operator=(nullptr_t) _NOEXCEPT; - template - typename enable_if - < - __callable::type>::value && - !is_same::type, function>::value, - function& - >::type - operator=(_Fp&&); + template> + function& operator=(_Fp&&); ~function(); @@ -1854,13 +1851,8 @@ function<_Rp(_ArgTypes...)>::operator=(nullptr_t) _NOE } template -template -typename enable_if -< - function<_Rp(_ArgTypes...)>::template __callable::type>::value && - !is_same::type, function<_Rp(_ArgTypes...)>>::value, - function<_Rp(_ArgTypes...)>& ->::type +template +function<_Rp(_ArgTypes...)>& function<_Rp(_ArgTypes...)>::operator=(_Fp&& __f) { function(_VSTD::forward<_Fp>(__f)).swap(*this); Modified: user/jeff/numa/contrib/libc++/include/list ============================================================================== --- user/jeff/numa/contrib/libc++/include/list Fri Dec 15 23:35:20 2017 (r326889) +++ user/jeff/numa/contrib/libc++/include/list Fri Dec 15 23:50:26 2017 (r326890) @@ -992,6 +992,15 @@ class _LIBCPP_TEMPLATE_VIS list (public) void push_front(const value_type& __x); void push_back(const value_type& __x); +#ifndef _LIBCPP_CXX03_LANG + template + _LIBCPP_INLINE_VISIBILITY + void __emplace_back(_Arg&& __arg) { emplace_back(_VSTD::forward<_Arg>(__arg)); } +#else + _LIBCPP_INLINE_VISIBILITY + void __emplace_back(value_type const& __arg) { push_back(__arg); } +#endif + iterator insert(const_iterator __p, const value_type& __x); *** DIFF OUTPUT TRUNCATED AT 1000 LINES ***