Home
last modified time | relevance | path

Searched +full:5 +full:kd (Results 1 – 25 of 96) 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/sys/contrib/device-tree/Bindings/iio/pressure/
H A Dhoneywell,hsc030pa.yaml52 1 - B, 5% to 95% of 2^14
53 2 - C, 5% to 85% of 2^14
68 250KA, 400KA, 600KA, 001GA, 160LD, 250LD, 400LD, 600LD, 001KD,
69 1.6KD, 2.5KD, 004KD, 006KD, 010KD, 016KD, 025KD, 040KD, 060KD,
70 100KD, 160KD, 250KD, 400KD, 250LG, 400LG, 600LG, 001KG, 1.6KG,
91 Provide VDD power to the sensor (either 3.3V or 5V depending on the chip)
/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/math/aarch64/experimental/
H A Dexp_inline.h22 #define C2 __exp_data.poly[5 - EXP_POLY_ORDER]
88 double_t kd, z, r, r2, scale, tail, tmp; in exp_inline() local
116 kd = roundtoint (z); in exp_inline()
119 /* z - kd is in [-0.5-2^-16, 0.5] in all rounding modes. */ in exp_inline()
120 kd = eval_as_double (z + Shift); in exp_inline()
121 ki = asuint64 (kd) >> 16; in exp_inline()
122 kd = (double_t) (int32_t) ki; in exp_inline()
124 /* z - kd is in [-1, 1] in non-nearest rounding modes. */ in exp_inline()
125 kd = eval_as_double (z + Shift); in exp_inline()
126 ki = asuint64 (kd); in exp_inline()
[all …]
/freebsd/contrib/arm-optimized-routines/math/
H A Dexp.c21 #define C2 __exp_data.poly[5 - EXP_POLY_ORDER]
87 double_t kd, z, r, r2, scale, tail, tmp; in exp_inline() local
115 kd = roundtoint (z); in exp_inline()
118 /* z - kd is in [-0.5-2^-16, 0.5] in all rounding modes. */ in exp_inline()
119 kd = eval_as_double (z + Shift); in exp_inline()
120 ki = asuint64 (kd) >> 16; in exp_inline()
121 kd = (double_t) (int32_t) ki; in exp_inline()
123 /* z - kd is in [-1, 1] in non-nearest rounding modes. */ in exp_inline()
124 kd = eval_as_double (z + Shift); in exp_inline()
125 ki = asuint64 (kd); in exp_inline()
[all …]
H A Dpow.c41 double_t z, r, y, invc, logc, logctail, kd, hi, t1, t2, lo, lo1, lo2, p; in log_inline() local
53 kd = (double_t) k; in log_inline()
74 t1 = kd * Ln2hi + logc; in log_inline()
76 lo1 = kd * Ln2lo + logctail; in log_inline()
99 * (A[1] + r * A[2] + ar2 * (A[3] + r * A[4] + ar2 * (A[5] + r * A[6])))); in log_inline()
115 #define C2 __exp_data.poly[5 - EXP_POLY_ORDER]
179 double_t kd, z, r, r2, scale, tail, tmp; in exp_inline() local
207 kd = roundtoint (z); in exp_inline()
210 /* z - kd is in [-0.5-2^-16, 0.5] in all rounding modes. */ in exp_inline()
211 kd = eval_as_double (z + Shift); in exp_inline()
[all …]
H A Dexpf.c15 EXP2F_TABLE_BITS = 5
41 double_t kd, xd, z, r, r2, y, s; in expf() local
69 kd = roundtoint (z); in expf()
73 kd = eval_as_double (z + SHIFT); in expf()
74 ki = asuint64 (kd); in expf()
75 kd -= SHIFT; in expf()
77 r = z - kd; in expf()
H A Dexp2f.c15 EXP2F_TABLE_BITS = 5
41 double_t kd, xd, z, r, r2, y, s; in exp2f() local
63 kd = eval_as_double (xd + SHIFT); in exp2f()
64 ki = asuint64 (kd); in exp2f()
65 kd -= SHIFT; /* k/N for int k. */ in exp2f()
66 r = xd - kd; in exp2f()
H A Dexp10.c15 #define UFlowBound -0x1.5ep+8 /* -350. */
88 double_t kd; in exp10() local
91 kd = roundtoint (z); in exp10()
94 kd = eval_as_double (z + Shift); in exp10()
95 ki = asuint64 (kd); in exp10()
96 kd -= Shift; in exp10()
101 r = __exp_data.neglog10_2hiN * kd + r; in exp10()
102 r = __exp_data.neglog10_2loN * kd + r; in exp10()
H A Dlog.c35 double_t w, z, r, r2, r3, y, invc, logc, kd, hi, lo; in log() local
44 # define LO asuint64 (1.0 - 0x1p-5) in log()
45 # define HI asuint64 (1.0 + 0x1.1p-5) in log()
62 + r3 * (B[4] + r * B[5] + r2 * B[6] + r3 * (B[7] + r * B[8]))); in log()
70 + r2 * (B[3] + r * B[4] + r2 * B[5] in log()
78 + r3 * (B[4] + r * B[5] + r2 * B[6] in log()
135 kd = (double_t) k; in log()
138 w = kd * Ln2hi + logc; in log()
140 lo = w - hi + r + kd * Ln2lo; in log()
144 /* 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/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/sys/contrib/openzfs/tests/zfs-tests/tests/functional/mmp/
H A Dmmp_on_zdb.ksh33 # 5. Run zdb -kd with pool and dataset arguments.
65 log_must zdb -kd $TESTPOOL
66 log_must zdb -kd $TESTPOOL/
67 log_must zdb -kd $TESTPOOL/$TESTFS
68 log_must zdb -kd $TESTPOOL/$TESTFS@snap
/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/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 …]
/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.c513 spl_sprintf_addr(kmem_debug_t *kd, char *str, int len, int min) argument
515 int size = ((len - 1) < kd->kd_size) ? (len - 1) : kd->kd_size;
526 str[i] = ((char *)(kd->kd_addr))[i];
544 *((uint8_t *)kd->kd_addr),
545 *((uint8_t *)kd->kd_addr + 2),
546 *((uint8_t *)kd->kd_addr + 4),
547 *((uint8_t *)kd->kd_addr + 6),
548 *((uint8_t *)kd->kd_addr + 8),
549 *((uint8_t *)kd->kd_addr + 10),
550 *((uint8_t *)kd->kd_addr + 12),
[all …]
/freebsd/contrib/arm-optimized-routines/math/aarch64/sve/
H A Dexp2.c26 .c2 = 0x1.c6b09b16de99ap-5, .c3 = 0x1.3b2abf5571ad8p-7,
78 svfloat64_t kd = svadd_x (pg, x, shift); in SV_NAME_D1() local
79 svuint64_t ki = svreinterpret_u64 (kd); in SV_NAME_D1()
80 /* kd = k/N. */ in SV_NAME_D1()
81 kd = svsub_x (pg, kd, shift); in SV_NAME_D1()
82 svfloat64_t r = svsub_x (pg, x, kd); in SV_NAME_D1()
101 return special_case (pg, scale, y, kd, d); in SV_NAME_D1()
/freebsd/contrib/arm-optimized-routines/math/aarch64/advsimd/
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()
/freebsd/lib/libdevstat/
H A Ddevstat.c155 #define X_END 5
162 static int readkmem(kvm_t *kd, unsigned long addr, void *buf, size_t nbytes);
163 static int readkmem_nl(kvm_t *kd, const char *name, void *buf, size_t nbytes);
164 static char *get_devstat_kvm(kvm_t *kd);
166 #define KREADNL(kd, var, val) \ argument
167 readkmem_nl(kd, namelist[var], &val, sizeof(val))
170 devstat_getnumdevs(kvm_t *kd) in devstat_getnumdevs() argument
180 if (kd == NULL) { in devstat_getnumdevs()
192 if (KREADNL(kd, X_NUMDEVS, numdevs) == -1) in devstat_getnumdevs()
207 devstat_getgeneration(kvm_t *kd) in devstat_getgeneration() argument
[all …]

1234