Home
last modified time | relevance | path

Searched +full:100 +full:pg (Results 1 – 25 of 82) sorted by relevance

1234

/freebsd/contrib/arm-optimized-routines/math/aarch64/sve/
H A Dlogf.c50 svfloat32_t SV_NAME_F1 (log) (svfloat32_t x, const svbool_t pg) in SV_NAME_F1()
56 u_off = svsub_x (pg, u_off, d->off); in SV_NAME_F1()
57 svbool_t cmp = svcmpge (pg, svsub_x (pg, u_off, d->lower), Thresh); in SV_NAME_F1()
61 pg, svasr_x (pg, svreinterpret_s32 (u_off), 23)); /* Sign-extend. */ in SV_NAME_F1()
63 svuint32_t u = svand_x (pg, u_off, Mask); in SV_NAME_F1()
64 u = svadd_x (pg, u, d->off); in SV_NAME_F1()
65 svfloat32_t r = svsub_x (pg, svreinterpret_f32 (u), 1.0f); in SV_NAME_F1()
76 q = svmla_x (pg, q, r2, p); in SV_NAME_F1()
77 y = svmla_x (pg, y, r2, q); in SV_NAME_F1()
78 p = svmla_x (pg, r, n, d->ln2); in SV_NAME_F1()
[all …]
H A Dlog10.c47 svfloat64_t SV_NAME_D1 (log10) (svfloat64_t x, const svbool_t pg) in SV_NAME_D1()
52 svbool_t special = svcmpge (pg, svsub_x (pg, ix, Min), Thres); in SV_NAME_D1()
57 svuint64_t tmp = svsub_x (pg, ix, d->off); in SV_NAME_D1()
58 svuint64_t i = svlsr_x (pg, tmp, 51 - V_LOG10_TABLE_BITS); in SV_NAME_D1()
59 i = svand_x (pg, i, (N - 1) << 1); in SV_NAME_D1()
60 svfloat64_t k = svcvt_f64_x (pg, svasr_x (pg, svreinterpret_s64 (tmp), 52)); in SV_NAME_D1()
62 svsub_x (pg, ix, svand_x (pg, tmp, 0xfffULL << 52))); in SV_NAME_D1()
65 svfloat64_t invc = svld1_gather_index (pg, &__v_log10_data.table[0].invc, i); in SV_NAME_D1()
67 = svld1_gather_index (pg, &__v_log10_data.table[0].log10c, i); in SV_NAME_D1()
72 svfloat64_t r = svmad_x (pg, invc, z, -1.0); in SV_NAME_D1()
[all …]
H A Dlog10f.c53 svfloat32_t SV_NAME_F1 (log10) (svfloat32_t x, const svbool_t pg) in SV_NAME_F1()
59 u_off = svsub_x (pg, u_off, d->off); in SV_NAME_F1()
60 svbool_t special = svcmpge (pg, svsub_x (pg, u_off, d->lower), Thres); in SV_NAME_F1()
64 pg, svasr_x (pg, svreinterpret_s32 (u_off), 23)); /* signextend. */ in SV_NAME_F1()
65 svuint32_t ix = svand_x (pg, u_off, MantissaMask); in SV_NAME_F1()
66 ix = svadd_x (pg, ix, d->off); in SV_NAME_F1()
67 svfloat32_t r = svsub_x (pg, svreinterpret_f32 (ix), 1.0f); in SV_NAME_F1()
80 svfloat32_t q_47 = svmla_x (pg, q_45, r2, q_67); in SV_NAME_F1()
81 svfloat32_t q_03 = svmla_x (pg, q_01, r2, q_23); in SV_NAME_F1()
82 svfloat32_t y = svmla_x (pg, q_03, r4, q_47); in SV_NAME_F1()
[all …]
H A Dtanf.c49 svfloat32_t SV_NAME_F1 (tan) (svfloat32_t x, const svbool_t pg) in SV_NAME_F1()
57 svfloat32_t n = svrintn_x (pg, svmul_lane (x, pi_vals, 3)); in SV_NAME_F1()
59 svint32_t in = svcvt_s32_x (pg, n); in SV_NAME_F1()
61 svint32_t alt = svand_x (pg, in, 1); in SV_NAME_F1()
62 svbool_t pred_alt = svcmpne (pg, alt, 0); in SV_NAME_F1()
86 svfloat32_t z4 = svmul_x (pg, z2, z2); in SV_NAME_F1()
87 svfloat32_t p = svmla_x (pg, p01, z4, p23); in SV_NAME_F1()
89 svfloat32_t z8 = svmul_x (pg, z4, z4); in SV_NAME_F1()
90 p = svmla_x (pg, p, z8, p45); in SV_NAME_F1()
92 svfloat32_t y = svmla_x (pg, z, p, svmul_x (pg, z, z2)); in SV_NAME_F1()
[all …]
H A Dlog2.c47 svfloat64_t SV_NAME_D1 (log2) (svfloat64_t x, const svbool_t pg) in SV_NAME_D1()
52 svbool_t special = svcmpge (pg, svsub_x (pg, ix, Min), Thresh); in SV_NAME_D1()
57 svuint64_t tmp = svsub_x (pg, ix, d->off); in SV_NAME_D1()
58 svuint64_t i = svlsr_x (pg, tmp, 51 - V_LOG2_TABLE_BITS); in SV_NAME_D1()
59 i = svand_x (pg, i, (N - 1) << 1); in SV_NAME_D1()
60 svfloat64_t k = svcvt_f64_x (pg, svasr_x (pg, svreinterpret_s64 (tmp), 52)); in SV_NAME_D1()
62 svsub_x (pg, ix, svand_x (pg, tmp, 0xfffULL << 52))); in SV_NAME_D1()
64 svfloat64_t invc = svld1_gather_index (pg, &__v_log2_data.table[0].invc, i); in SV_NAME_D1()
66 = svld1_gather_index (pg, &__v_log2_data.table[0].log2c, i); in SV_NAME_D1()
71 svfloat64_t r = svmad_x (pg, invc, z, -1.0); in SV_NAME_D1()
[all …]
H A Dlog.c45 svfloat64_t SV_NAME_D1 (log) (svfloat64_t x, const svbool_t pg) in SV_NAME_D1()
50 svbool_t special = svcmpge (pg, svsub_x (pg, ix, Min), Thresh); in SV_NAME_D1()
55 svuint64_t tmp = svsub_x (pg, ix, d->off); in SV_NAME_D1()
59 = svand_x (pg, svlsr_x (pg, tmp, (51 - V_LOG_TABLE_BITS)), (N - 1) << 1); in SV_NAME_D1()
60 svuint64_t iz = svsub_x (pg, ix, svand_x (pg, tmp, 0xfffULL << 52)); in SV_NAME_D1()
63 svfloat64_t invc = svld1_gather_index (pg, &__v_log_data.table[0].invc, i); in SV_NAME_D1()
64 svfloat64_t logc = svld1_gather_index (pg, &__v_log_data.table[0].logc, i); in SV_NAME_D1()
67 svfloat64_t kd = svcvt_f64_x (pg, svasr_x (pg, svreinterpret_s64 (tmp), 52)); in SV_NAME_D1()
70 svfloat64_t r = svmad_x (pg, invc, z, -1); in SV_NAME_D1()
72 hi = svadd_x (pg, r, hi); in SV_NAME_D1()
[all …]
H A Dlog2f.c50 svfloat32_t SV_NAME_F1 (log2) (svfloat32_t x, const svbool_t pg) in SV_NAME_F1()
56 u_off = svsub_x (pg, u_off, d->off); in SV_NAME_F1()
57 svbool_t special = svcmpge (pg, svsub_x (pg, u_off, d->lower), Thresh); in SV_NAME_F1()
61 pg, svasr_x (pg, svreinterpret_s32 (u_off), 23)); /* Sign-extend. */ in SV_NAME_F1()
62 svuint32_t u = svand_x (pg, u_off, MantissaMask); in SV_NAME_F1()
63 u = svadd_x (pg, u, d->off); in SV_NAME_F1()
64 svfloat32_t r = svsub_x (pg, svreinterpret_f32 (u), 1.0f); in SV_NAME_F1()
75 svfloat32_t y = svmla_x (pg, q_67, r2, sv_f32 (d->poly_02468[4])); in SV_NAME_F1()
76 y = svmla_x (pg, q_45, r2, y); in SV_NAME_F1()
77 y = svmla_x (pg, q_23, r2, y); in SV_NAME_F1()
[all …]
H A Dtanhf.c29 special_case (svfloat32_t x, svbool_t pg, svbool_t is_boring, in special_case() argument
33 = svsel_f32 (is_boring, boring, svdiv_x (pg, q, svadd_x (pg, q, 2.0))); in special_case()
41 svfloat32_t SV_NAME_F1 (tanh) (svfloat32_t x, const svbool_t pg) in SV_NAME_F1()
45 svfloat32_t ax = svabs_x (pg, x); in SV_NAME_F1()
47 svuint32_t sign = sveor_x (pg, svreinterpret_u32 (x), iax); in SV_NAME_F1()
48 svfloat32_t boring = svreinterpret_f32 (svorr_x (pg, sign, d->onef)); in SV_NAME_F1()
49 svbool_t special = svcmpgt (pg, iax, d->special_bound); in SV_NAME_F1()
50 svbool_t is_boring = svacgt (pg, x, d->boring_bound); in SV_NAME_F1()
53 svfloat32_t q = expm1f_inline (svmul_x (svptrue_b32 (), x, 2.0), pg, in SV_NAME_F1()
56 if (unlikely (svptest_any (pg, special))) in SV_NAME_F1()
[all …]
H A Datanh.c28 svfloat64_t SV_NAME_D1 (atanh) (svfloat64_t x, const svbool_t pg) in SV_NAME_D1()
31 svfloat64_t ax = svabs_x (pg, x); in SV_NAME_D1()
33 svuint64_t sign = sveor_x (pg, svreinterpret_u64 (x), iax); in SV_NAME_D1()
34 svfloat64_t halfsign = svreinterpret_f64 (svorr_x (pg, sign, Half)); in SV_NAME_D1()
37 svbool_t special = svacge (pg, x, 1.0); in SV_NAME_D1()
42 y = svadd_x (pg, ax, ax); in SV_NAME_D1()
43 y = svdiv_x (pg, y, svsub_x (pg, sv_f64 (1), ax)); in SV_NAME_D1()
45 y = sv_log1p_inline (y, pg); in SV_NAME_D1()
47 if (unlikely (svptest_any (pg, special))) in SV_NAME_D1()
48 return special_case (x, svmul_x (pg, halfsign, y), special); in SV_NAME_D1()
[all …]
H A Datan2f.c36 zeroinfnan (svuint32_t i, const svbool_t pg) in zeroinfnan() argument
38 return svcmpge (pg, svsub_x (pg, svlsl_x (pg, i, 1), 1), in zeroinfnan()
48 const svbool_t pg) in SV_NAME_F2()
55 svbool_t cmp_x = zeroinfnan (ix, pg); in SV_NAME_F2()
56 svbool_t cmp_y = zeroinfnan (iy, pg); in SV_NAME_F2()
57 svbool_t cmp_xy = svorr_z (pg, cmp_x, cmp_y); in SV_NAME_F2()
59 svfloat32_t ax = svabs_x (pg, x); in SV_NAME_F2()
60 svfloat32_t ay = svabs_x (pg, y); in SV_NAME_F2()
64 svuint32_t sign_x = sveor_x (pg, ix, iax); in SV_NAME_F2()
65 svuint32_t sign_y = sveor_x (pg, iy, iay); in SV_NAME_F2()
[all …]
H A Datan2.c41 zeroinfnan (svuint64_t i, const svbool_t pg) in zeroinfnan() argument
43 return svcmpge (pg, svsub_x (pg, svlsl_x (pg, i, 1), 1), in zeroinfnan()
52 const svbool_t pg) in SV_NAME_D2()
59 svbool_t cmp_x = zeroinfnan (ix, pg); in SV_NAME_D2()
60 svbool_t cmp_y = zeroinfnan (iy, pg); in SV_NAME_D2()
61 svbool_t cmp_xy = svorr_z (pg, cmp_x, cmp_y); in SV_NAME_D2()
63 svfloat64_t ax = svabs_x (pg, x); in SV_NAME_D2()
64 svfloat64_t ay = svabs_x (pg, y); in SV_NAME_D2()
68 svuint64_t sign_x = sveor_x (pg, ix, iax); in SV_NAME_D2()
69 svuint64_t sign_y = sveor_x (pg, iy, iay); in SV_NAME_D2()
[all …]
H A Dcoshf.c25 svbool_t pg) in special_case() argument
28 pg); in special_case()
35 svfloat32_t SV_NAME_F1 (cosh) (svfloat32_t x, svbool_t pg) in SV_NAME_F1()
39 svbool_t special = svacge (pg, x, d->special_bound); in SV_NAME_F1()
46 svfloat32_t e = expf_inline (x, pg, &d->expf_consts); in SV_NAME_F1()
48 svfloat32_t half_over_e = svdivr_x (pg, e, 0.5); in SV_NAME_F1()
50 if (unlikely (svptest_any (pg, special))) in SV_NAME_F1()
59 TEST_SYM_INTERVAL (SV_NAME_F1 (cosh), 0, 0x1p-63, 100)
H A Datanf.c33 svfloat32_t SV_NAME_F1 (atan) (svfloat32_t x, const svbool_t pg) in SV_NAME_F1()
40 svuint32_t sign = svand_x (pg, ix, SignMask); in SV_NAME_F1()
46 svbool_t red = svacgt (pg, x, 1.0f); in SV_NAME_F1()
48 svfloat32_t z = svsel (red, svdiv_x (pg, sv_f32 (1.0f), x), x); in SV_NAME_F1()
50 svfloat32_t az = svabs_x (pg, z); in SV_NAME_F1()
54 svfloat32_t z2 = svmul_x (pg, z, z); in SV_NAME_F1()
55 svfloat32_t z4 = svmul_x (pg, z2, z2); in SV_NAME_F1()
56 svfloat32_t z8 = svmul_x (pg, z4, z4); in SV_NAME_F1()
58 svfloat32_t y = sv_estrin_7_f32_x (pg, z2, z4, z8, d->poly); in SV_NAME_F1()
61 svfloat32_t z3 = svmul_x (pg, z2, az); in SV_NAME_F1()
[all …]
H A Datan.c39 svfloat64_t SV_NAME_D1 (atan) (svfloat64_t x, const svbool_t pg) in SV_NAME_D1()
46 svuint64_t sign = svand_x (pg, ix, SignMask); in SV_NAME_D1()
52 svbool_t red = svacgt (pg, x, 1.0); in SV_NAME_D1()
54 svfloat64_t z = svsel (red, svdivr_x (pg, x, 1.0), x); in SV_NAME_D1()
56 svfloat64_t az = svabs_x (pg, z); in SV_NAME_D1()
60 svfloat64_t z2 = svmul_x (pg, z, z); in SV_NAME_D1()
61 svfloat64_t x2 = svmul_x (pg, z2, z2); in SV_NAME_D1()
62 svfloat64_t x4 = svmul_x (pg, x2, x2); in SV_NAME_D1()
63 svfloat64_t x8 = svmul_x (pg, x4, x4); in SV_NAME_D1()
66 = svmla_x (pg, sv_estrin_7_f64_x (pg, z2, x2, x4, d->poly), in SV_NAME_D1()
[all …]
/freebsd/sys/contrib/device-tree/Bindings/iio/pressure/
H A Dhoneywell,hsc030pa.yaml64 006MD, 010MD, 016MD, 025MD, 040MD, 060MD, 100MD, 160MD, 250MD,
66 010MG, 016MG, 025MG, 040MG, 060MG, 100MG, 160MG, 250MG, 400MG,
67 600MG, 001BG, 1.6BG, 2.5BG, 004BG, 006BG, 010BG, 100KA, 160KA,
70 100KD, 160KD, 250KD, 400KD, 250LG, 400LG, 600LG, 001KG, 1.6KG,
71 2.5KG, 004KG, 006KG, 010KG, 016KG, 025KG, 040KG, 060KG, 100KG,
72 160KG, 250KG, 400KG, 600KG, 001GG, 015PA, 030PA, 060PA, 100PA,
75 010NG, 020NG, 030NG, 001PG, 005PG, 015PG, 030PG, 060PG, 100PG,
76 150PG, NA]
/freebsd/sys/dev/mlx4/mlx4_core/
H A Dfw_qos.h71 * tc_tx_bw, pg and ratelimit are arrays where each index represents a TC.
78 * classes within a TC group must equal 100% for correct operation.
79 * @pg: The TC group the traffic class is associated with.
85 u8 *pg, u16 *ratelimit);
H A Dmlx4_fw_qos.c56 __be16 pg; member
58 __be16 max_bw_units; /* 3-100Mbps, 4-1Gbps, other values - reserved */
112 u8 *pg, u16 *ratelimit) in mlx4_SET_PORT_SCHEDULER() argument
146 tc->pg = htons(pg[i]); in mlx4_SET_PORT_SCHEDULER()
/freebsd/sys/kern/
H A Dkern_fork.c221 /* generate a random PID modulus between 100 and 1123 */ in sysctl_kern_randompid()
222 randompid = 100 + arc4random() % 1024; in sysctl_kern_randompid()
223 else if (pid < 0 || pid > pid_max - 100) in sysctl_kern_randompid()
225 randompid = pid_max - 100; in sysctl_kern_randompid()
226 else if (pid < 100) in sysctl_kern_randompid()
228 randompid = 100; in sysctl_kern_randompid()
856 struct pgrp *pg; in fork1() local
957 pg = p1->p_pgrp; in fork1()
959 if (sx_try_slock(&pg->pg_killsx) != 0) { in fork1()
977 if (!killsx_locked && sx_slock_sig(&pg->pg_killsx) != 0) { in fork1()
[all …]
H A Dkern_resource.c99 struct pgrp *pg; in kern_getpriority() local
121 pg = td->td_proc->p_pgrp; in kern_getpriority()
122 PGRP_LOCK(pg); in kern_getpriority()
124 pg = pgfind(who); in kern_getpriority()
125 if (pg == NULL) { in kern_getpriority()
131 LIST_FOREACH(p, &pg->pg_members, p_pglist) { in kern_getpriority()
140 PGRP_UNLOCK(pg); in kern_getpriority()
188 struct pgrp *pg; in kern_setpriority() local
213 pg = curp->p_pgrp; in kern_setpriority()
214 PGRP_LOCK(pg); in kern_setpriority()
[all …]
H A Dtty.c179 * higher priority than timeout if the IO completed in the last 100mS. in tty_drain()
424 struct pgrp *pg; in tty_wait_background() local
433 pg = p->p_pgrp; in tty_wait_background()
434 PGRP_LOCK(pg); in tty_wait_background()
438 * pg may no longer be our process group. in tty_wait_background()
441 if (p->p_pgrp != pg) { in tty_wait_background()
443 PGRP_UNLOCK(pg); in tty_wait_background()
459 PGRP_UNLOCK(pg); in tty_wait_background()
467 PGRP_UNLOCK(pg); in tty_wait_background()
472 (pg->pg_flags & PGRP_ORPHANED) != 0) { in tty_wait_background()
[all …]
/freebsd/sys/dev/bwn/
H A Dif_bwn_phy_g.c153 struct bwn_phy_g *pg = &phy->phy_g; in bwn_phy_g_attach() local
176 &pg->pg_pa0maxpwr); in bwn_phy_g_attach()
180 pg->pg_flags = 0; in bwn_phy_g_attach()
183 pg->pg_idletssi = 52; in bwn_phy_g_attach()
184 pg->pg_tssi2dbm = bwn_phy_g_tssi2dbm_table; in bwn_phy_g_attach()
188 pg->pg_idletssi = (bg == 0 || bg == -1) ? 62 : bg; in bwn_phy_g_attach()
189 pg->pg_tssi2dbm = (uint8_t *)malloc(64, M_DEVBUF, M_NOWAIT | M_ZERO); in bwn_phy_g_attach()
190 if (pg->pg_tssi2dbm == NULL) { in bwn_phy_g_attach()
206 free(pg->pg_tssi2dbm, M_DEVBUF); in bwn_phy_g_attach()
216 pg->pg_tssi2dbm[i] = MIN(MAX(BWN_TSSI2DBM(m1 * f, 8192), -127), in bwn_phy_g_attach()
[all …]
/freebsd/sbin/bsdlabel/
H A Ddisktab106 cp3100|Connor Peripherals 100MB IDE:\
120 cp3100new|Connor Peripherals 100MB IDE, with a different configuration:\
127 :pg#15840:og#55968:tg=4.2BSD:bg#4096:fg#512: \
154 :pg#302400:og#1330560:bg#4096:fg#512:tg=4.2BSD:
189 zip100|zip 100:\
/freebsd/contrib/netbsd-tests/sys/uvm/
H A Dt_uvm_physseg_load.c156 uvm_pagefree(struct vm_page *pg) in uvm_pagefree() argument
295 //uvm_vm_page_to_phys(const struct vm_page *pg)
298 // return pg->phys_addr;
326 100 calls, VM_PHYSSEG_MAX is 32."); in ATF_TC_HEAD()
343 for(int i = 0; i < 100; i++) { in ATF_TC_BODY()
413 100,000 calls, VM_PHYSSEG_MAX is 32."); in ATF_TC_HEAD()
500 100,000,000 calls, VM_PHYSSEG_MAX is 32."); in ATF_TC_HEAD()
/freebsd/contrib/arm-optimized-routines/math/test/
H A Dmathbench.c71 __sv_dummy (svfloat64_t x, svbool_t pg) in __sv_dummy() argument
77 __sv_dummyf (svfloat32_t x, svbool_t pg) in __sv_dummyf() argument
378 ns100 = (100 * dt + itercount * N / 2) / (itercount * N); in bench1()
381 (unsigned) (ns100 / 100), (unsigned) (ns100 % 100), in bench1()
386 ns100 = (100 * dt + itercount * N / vlen / 2) / (itercount * N / vlen); in bench1()
389 (unsigned) (ns100 / 100), (unsigned) (ns100 % 100), in bench1()
/freebsd/sys/contrib/device-tree/src/arm/allwinner/
H A Dsun9i-a80-cubieboard4.dts200 vcc-pg-supply = <&reg_ldo_io0>;
327 regulator-name = "vcc-pg";
416 * Set a 100ms delay to account for PMIC

1234