Home
last modified time | relevance | path

Searched +full:5 +full:kd (Results 1 – 25 of 87) sorted by relevance

1234

/freebsd/lib/libkvm/
H A Dkvm_minidump_powerpc64_hpt.c135 * s(ava) = 5 - n
143 #define AVA_PAGE_SHIFT(b) (5 - (MIN(54, 77-(b)) + 1 - 50))
183 slb_init(kvm_t *kd) in slb_init() argument
191 hdr = &kd->vmst->hdr; in slb_init()
192 data = PPC64_MMU_DATA(kd); in slb_init()
198 data->slbs = _kvm_malloc(kd, slbsize); in slb_init()
200 _kvm_err(kd, kd->program, "cannot allocate slbs"); in slb_init()
236 ppc64mmu_hpt_cleanup(kvm_t *kd) in ppc64mmu_hpt_cleanup() argument
240 if (kd->vmst == NULL) in ppc64mmu_hpt_cleanup()
243 data = PPC64_MMU_DATA(kd); in ppc64mmu_hpt_cleanup()
[all …]
H A Dkvm_vnet.c58 _kvm_vnet_selectpid(kvm_t *kd, pid_t pid) in _kvm_vnet_selectpid() argument
79 #define NLIST_PROC0 5 in _kvm_vnet_selectpid()
94 if (!kvm_native(kd)) in _kvm_vnet_selectpid()
103 if (_kvm_nlist(kd, nl, 0) != 0) { in _kvm_vnet_selectpid()
112 /* _kvm_err(kd, kd->program, "%s: no namelist", __func__); */ in _kvm_vnet_selectpid()
121 if (kvm_read(kd, nl[NLIST_DUMPTID].n_value, &dumptid, in _kvm_vnet_selectpid()
123 _kvm_err(kd, kd->program, "%s: dumptid", __func__); in _kvm_vnet_selectpid()
143 if (kvm_read(kd, procp, &proc, sizeof(proc)) != sizeof(proc)) { in _kvm_vnet_selectpid()
144 _kvm_err(kd, kd->program, "%s: proc", __func__); in _kvm_vnet_selectpid()
151 if (kvm_read(kd, tdp, &td, sizeof(td)) != in _kvm_vnet_selectpid()
[all …]
H A Dkvm_proc.c80 #define KREAD(kd, addr, obj) \ argument
81 (kvm_read(kd, addr, (char *)(obj), sizeof(*obj)) != sizeof(*obj))
105 kvm_proclist(kvm_t *kd, int what, int arg, struct proc *p, in kvm_proclist() argument
138 if (KREAD(kd, (u_long)p, &proc)) { in kvm_proclist()
139 _kvm_err(kd, kd->program, "can't read proc at %p", p); in kvm_proclist()
144 if (KREAD(kd, (u_long)proc.p_ucred, &ucred) == 0) { in kvm_proclist()
158 kvm_read(kd, (u_long)ucred.cr_groups, kp->ki_groups, in kvm_proclist()
161 if (KREAD(kd, (u_long)ucred.cr_prison, &pr)) { in kvm_proclist()
162 _kvm_err(kd, kd->program, in kvm_proclist()
204 _kvm_err(kd, kd->program, "nprocs corrupt"); in kvm_proclist()
[all …]
/freebsd/crypto/heimdal/lib/krb5/
H A Dkrbhst.c171 krbhst_empty(const struct krb5_krbhst_data *kd) in krbhst_empty() argument
173 return kd->index == &kd->hosts; in krbhst_empty()
177 * Return the default protocol for the `kd' (either TCP or UDP)
181 krbhst_get_default_proto(struct krb5_krbhst_data *kd) in krbhst_get_default_proto() argument
183 if (kd->flags & KD_LARGE_MSG) in krbhst_get_default_proto()
204 parse_hostspec(krb5_context context, struct krb5_krbhst_data *kd, in parse_hostspec() argument
214 hi->proto = krbhst_get_default_proto(kd); in parse_hostspec()
219 } else if(strncmp(p, "http/", 5) == 0) { in parse_hostspec()
221 p += 5; in parse_hostspec()
296 append_host_hostinfo(struct krb5_krbhst_data *kd, struct krb5_krbhst_info *host) in append_host_hostinfo() argument
[all …]
/freebsd/usr.sbin/pstat/
H A Dpstat.c92 static kvm_t *kd; variable
175 kd = kvm_openfiles(nlistf, memf, NULL, O_RDONLY, buf); in main()
176 if (kd == NULL) in main()
178 if ((ret = kvm_nlist(kd, nl)) != 0) { in main()
180 errx(1, "kvm_nlist: %s", kvm_geterr(kd)); in main()
231 if (kvm_read(kd, nl[NL_TTY_LIST].n_value, &tl, sizeof tl) != sizeof tl) in ttymode_kvm()
232 errx(1, "kvm_read(): %s", kvm_geterr(kd)); in ttymode_kvm()
235 if (kvm_read(kd, (u_long)tp, &tty, sizeof tty) != sizeof tty) in ttymode_kvm()
236 errx(1, "kvm_read(): %s", kvm_geterr(kd)); in ttymode_kvm()
280 if (kd ! in ttymode()
[all...]
/freebsd/contrib/arm-optimized-routines/pl/math/
H A Dexp.c19 #define C2 __exp_data.poly[5 - EXP_POLY_ORDER]
85 double_t kd, z, r, r2, scale, tail, tmp; in exp_inline() local
113 kd = roundtoint (z); in exp_inline()
116 /* z - kd is in [-0.5-2^-16, 0.5] in all rounding modes. */ in exp_inline()
117 kd = eval_as_double (z + Shift); in exp_inline()
118 ki = asuint64 (kd) >> 16; in exp_inline()
119 kd = (double_t) (int32_t) ki; in exp_inline()
121 /* z - kd is in [-1, 1] in non-nearest rounding modes. */ in exp_inline()
122 kd = eval_as_double (z + Shift); in exp_inline()
123 ki = asuint64 (kd); in exp_inline()
[all …]
H A Dsv_exp2_2u.c25 .poly = { 0x1.62e42fefa3686p-1, 0x1.ebfbdff82c241p-3, 0x1.c6b09b16de99ap-5,
79 svfloat64_t kd = svadd_x (pg, x, shift); in SV_NAME_D1() local
80 svuint64_t ki = svreinterpret_u64 (kd); in SV_NAME_D1()
81 /* kd = k/N. */ in SV_NAME_D1()
82 kd = svsub_x (pg, kd, shift); in SV_NAME_D1()
83 svfloat64_t r = svsub_x (pg, x, kd); in SV_NAME_D1()
99 return special_case (pg, scale, y, kd, d); in SV_NAME_D1()
H A Dv_log_inline.h12 # error Cannot use inline log helper without specifying poly order (options are 4 or 5)
21 #elif V_LOG_INLINE_POLY_ORDER == 5
29 # error Can only choose order 4 or 5 for log poly
72 float64x2_t z, r, r2, p, y, kd, hi; in v_log_inline() local
90 kd = vcvtq_f64_s64 (k); in v_log_inline()
93 hi = vfmaq_f64 (vaddq_f64 (e.logc, r), kd, d->ln2); in v_log_inline()
98 #if V_LOG_POLY_ORDER == 5 in v_log_inline()
H A Dlog.c33 double_t w, z, r, r2, r3, y, invc, logc, kd, hi, lo; in optr_aor_log_f64() local
42 #define LO asuint64 (1.0 - 0x1p-5) in optr_aor_log_f64()
43 #define HI asuint64 (1.0 + 0x1.1p-5) in optr_aor_log_f64()
61 + r3 * (B[4] + r * B[5] + r2 * B[6] + r3 * (B[7] + r * B[8]))); in optr_aor_log_f64()
71 * (B[3] + r * B[4] + r2 * B[5] in optr_aor_log_f64()
81 * (B[4] + r * B[5] + r2 * B[6] in optr_aor_log_f64()
138 kd = (double_t) k; in optr_aor_log_f64()
141 w = kd * Ln2hi + logc; in optr_aor_log_f64()
143 lo = w - hi + r + kd * Ln2lo; in optr_aor_log_f64()
147 /* Worst case error if |y| > 0x1p-5: in optr_aor_log_f64()
[all …]
/freebsd/contrib/arm-optimized-routines/math/
H A Dexp.c19 #define C2 __exp_data.poly[5 - EXP_POLY_ORDER]
85 double_t kd, z, r, r2, scale, tail, tmp; in exp_inline() local
113 kd = roundtoint (z); in exp_inline()
116 /* z - kd is in [-0.5-2^-16, 0.5] in all rounding modes. */ in exp_inline()
117 kd = eval_as_double (z + Shift); in exp_inline()
118 ki = asuint64 (kd) >> 16; in exp_inline()
119 kd = (double_t) (int32_t) ki; in exp_inline()
121 /* z - kd is in [-1, 1] in non-nearest rounding modes. */ in exp_inline()
122 kd = eval_as_double (z + Shift); in exp_inline()
123 ki = asuint64 (kd); in exp_inline()
[all …]
H A Dpow.c40 double_t z, r, y, invc, logc, logctail, kd, hi, t1, t2, lo, lo1, lo2, p; in log_inline() local
52 kd = (double_t) k; in log_inline()
73 t1 = kd * Ln2hi + logc; in log_inline()
75 lo1 = kd * Ln2lo + logctail; in log_inline()
98 * (A[1] + r * A[2] + ar2 * (A[3] + r * A[4] + ar2 * (A[5] + r * A[6])))); in log_inline()
114 #define C2 __exp_data.poly[5 - EXP_POLY_ORDER]
178 double_t kd, z, r, r2, scale, tail, tmp; in exp_inline() local
206 kd = roundtoint (z); in exp_inline()
209 /* z - kd is in [-0.5-2^-16, 0.5] in all rounding modes. */ in exp_inline()
210 kd = eval_as_double (z + Shift); in exp_inline()
[all …]
H A Dexpf.c13 EXP2F_TABLE_BITS = 5
39 double_t kd, xd, z, r, r2, y, s; in expf() local
67 kd = roundtoint (z); in expf()
71 kd = eval_as_double (z + SHIFT); in expf()
72 ki = asuint64 (kd); in expf()
73 kd -= SHIFT; in expf()
75 r = z - kd; in expf()
H A Dexp2f.c13 EXP2F_TABLE_BITS = 5
39 double_t kd, xd, z, r, r2, y, s; in exp2f() local
61 kd = eval_as_double (xd + SHIFT); in exp2f()
62 ki = asuint64 (kd); in exp2f()
63 kd -= SHIFT; /* k/N for int k. */ in exp2f()
64 r = xd - kd; in exp2f()
H A Dexp10.c13 #define UFlowBound -0x1.5ep+8 /* -350. */
86 double_t kd; in exp10() local
89 kd = roundtoint (z); in exp10()
92 kd = eval_as_double (z + Shift); in exp10()
93 kd -= Shift; in exp10()
94 ki = kd; in exp10()
99 r = __exp_data.neglog10_2hiN * kd + r; in exp10()
100 r = __exp_data.neglog10_2loN * kd + r; in exp10()
H A Dexp2.c21 #define C6 __exp_data.exp2_poly[5]
81 double_t kd, r, r2, scale, tail, tmp; in exp2() local
108 kd = eval_as_double (x + Shift); in exp2()
109 ki = asuint64 (kd); /* k. */ in exp2()
110 kd -= Shift; /* k/N for int k. */ in exp2()
111 r = x - kd; in exp2()
125 #elif EXP2_POLY_ORDER == 5 in exp2()
H A Dlog.c33 double_t w, z, r, r2, r3, y, invc, logc, kd, hi, lo; in log() local
42 # define LO asuint64 (1.0 - 0x1p-5) in log()
43 # define HI asuint64 (1.0 + 0x1.1p-5) in log()
60 + r3 * (B[4] + r * B[5] + r2 * B[6] + r3 * (B[7] + r * B[8]))); in log()
68 + r2 * (B[3] + r * B[4] + r2 * B[5] in log()
76 + r3 * (B[4] + r * B[5] + r2 * B[6] in log()
133 kd = (double_t) k; in log()
136 w = kd * Ln2hi + logc; in log()
138 lo = w - hi + r + kd * Ln2lo; in log()
142 /* Worst case error if |y| > 0x1p-5: in log()
[all …]
/freebsd/usr.bin/ktrdump/
H A Dktrdump.c96 kvm_t *kd; in main() local
181 if ((kd = kvm_openfiles(Nflag ? execfile : NULL, in main()
191 count = kvm_nlist(kd, nl); in main()
193 errx(1, "%s", kvm_geterr(kd)); in main()
196 if (kvm_read(kd, nl[0].n_value, &version, sizeof(version)) == -1) in main()
197 errx(1, "%s", kvm_geterr(kd)); in main()
219 if (kvm_read(kd, nl[1].n_value, &entries, sizeof(entries)) in main()
221 errx(1, "%s", kvm_geterr(kd)); in main()
224 if (kvm_read(kd, nl[2].n_value, &index, sizeof(index)) == -1 || in main()
225 kvm_read(kd, nl[3].n_value, &bufptr, in main()
[all …]
/freebsd/share/termcap/
H A Dtermcap44 # See termcap(5) in the Unix Programmers Manual for documentation.
163 :ku=\EY:kd=\EZ:kl=\EW:kr=\EX:pc=\177:
169 qume5|qume|Qume Sprint 5:\
176 :k0=^A@\r:k1=^AA\r:k2=^AB\r:k3=^AC\r:kd=^J:kl=^H:kr=^L:ku=^K:\
210 :cm=5\E[%i%2;%2H:co#80:dc=\E[P:dl=\E[M:ic=\E[@:\
211 :kd=\E[B:kh=\E[H:kl=\E[D:kr=\E[C:ku=\E[A:\
223 :mr=\E[7m:mh=\E[2m:mb=\E[5m:me=\E[m:ce=\E[K:cd=\E[J:cl=\E[H\E[J:\
226 :pf=\E[?4i:po=\E[?5i:\
227 :kb=\b:kC=\E[2J:kh=\E[H:ku=\E[A:kd=\E[B:kr=\E[C:kl=\E[D:
238 # AT&T Teletype 5420 Terminal (a.k.a. 4415) June 5, 1985
[all …]
/freebsd/usr.bin/systat/
H A Dmain.c55 kvm_t *kd; variable
167 kd = kvm_openfiles(NULL, NULL, NULL, O_RDONLY, errbuf); in main()
168 if (kd != NULL) { in main()
173 if (kvm_nlist(kd, namelist) != 0 || namelist[0].n_value == 0 || in main()
174 kvm_read(kd, namelist[0].n_value, &dummy, sizeof(dummy)) != in main()
176 kvm_close(kd); in main()
177 kd = NULL; in main()
180 if (kd == NULL) { in main()
186 kd = kvm_openfiles(_PATH_DEVNULL, _PATH_DEVNULL, _PATH_DEVNULL, in main()
188 if (kd == NULL) { in main()
[all …]
/freebsd/sys/contrib/openzfs/tests/zfs-tests/tests/functional/mmp/
H A Dmmp_on_zdb.ksh32 # 5. Run zdb -kd with pool and dataset arguments.
64 log_must zdb -kd $TESTPOOL
65 log_must zdb -kd $TESTPOOL/
66 log_must zdb -kd $TESTPOOL/$TESTFS
67 log_must zdb -kd $TESTPOOL/$TESTFS@snap
/freebsd/usr.sbin/iostat/
H A Diostat.c159 static int readvar(kvm_t *kd, const char *name, int nlid, void *ptr,
188 kvm_t *kd = NULL; in main() local
270 kd = kvm_openfiles(nlistf, memf, NULL, O_RDONLY, errbuf); in main()
272 if (kd == NULL) in main()
275 if (kvm_nlist(kd, namelist) == -1) in main()
276 errx(1, "kvm_nlist: %s", kvm_geterr(kd)); in main()
284 if (devstat_checkversion(kd) < 0) in main()
297 if ((num_devices = devstat_getnumdevs(kd)) < 0) in main()
308 maxshowdevs = 5; in main()
310 maxshowdevs = 5; in main()
[all …]
/freebsd/tools/test/stress2/misc/
H A Dmaxproc.sh76 #define MULTIUSERFUZZ 5
122 kvm_t *kd;
131 if ((kd = kvm_openfiles(nlistf, memf, NULL, O_RDONLY, buf)) == NULL)
133 if (kvm_nlist(kd, nl) == -1)
134 errx(1, "kvm_nlist: %s", kvm_geterr(kd));
135 if (kvm_read(kd, nl[NL_NPROCS].n_value, &nprocs,
137 errx(1, "kvm_read(): %s", kvm_geterr(kd));
138 if (kvm_read(kd, nl[NL_MAXPROC].n_value, &maxproc,
140 errx(1, "kvm_read(): %s", kvm_geterr(kd));
141 kvm_close(kd);
/freebsd/crypto/heimdal/lib/kafs/
H A Dafskrb5.c69 if (t.tkt_vno != 5) in v5_to_kt()
257 struct kafs_data kd; in krb5_afslog_uid_home() local
261 kd.name = "krb5"; in krb5_afslog_uid_home()
262 kd.afslog_uid = afslog_uid_int; in krb5_afslog_uid_home()
263 kd.get_cred = get_cred; in krb5_afslog_uid_home()
264 kd.get_realm = get_realm; in krb5_afslog_uid_home()
265 kd.get_error = get_error; in krb5_afslog_uid_home()
266 kd.free_error = free_error; in krb5_afslog_uid_home()
267 kd.data = &d; in krb5_afslog_uid_home()
281 ret = afslog_uid_int(&kd, cell, 0, uid, homedir); in krb5_afslog_uid_home()
[all …]
/freebsd/sys/contrib/openzfs/module/os/linux/spl/
H A Dspl-kmem.c512 spl_sprintf_addr(kmem_debug_t *kd, char *str, int len, int min) argument
514 int size = ((len - 1) < kd->kd_size) ? (len - 1) : kd->kd_size;
525 str[i] = ((char *)(kd->kd_addr))[i];
543 *((uint8_t *)kd->kd_addr),
544 *((uint8_t *)kd->kd_addr + 2),
545 *((uint8_t *)kd->kd_addr + 4),
546 *((uint8_t *)kd->kd_addr + 6),
547 *((uint8_t *)kd->kd_addr + 8),
548 *((uint8_t *)kd->kd_addr + 10),
549 *((uint8_t *)kd->kd_addr + 12),
[all …]
/freebsd/usr.bin/vmstat/
H A Dvmstat.c163 static kvm_t *kd; variable
292 kd = kvm_openfiles(nlistf, memf, NULL, O_RDONLY, errbuf); in main()
293 if (kd == NULL) in main()
298 if (kd != NULL && (c = kvm_nlist(kd, namelist)) != 0) { in main()
339 xo_warnx("kvm_nlist: %s", kvm_geterr(kd)); in main()
345 if (kd && Pflag) in main()
486 if (kd != NULL) { in fill_vmmeter()
489 vmmp->name = kvm_counter_u64_fetch(kd, (u_long)vm_cnt.name) in fill_vmmeter()
588 if (kd != NULL) { in fill_vmtotal()
608 if (kd != NULL) in getcpuinfo()
[all …]

1234