/freebsd-current/contrib/arm-optimized-routines/pl/math/ |
H A D | sv_powf_2u6.c | 54 svisint (svbool_t pg, svfloat32_t x) argument 56 return svcmpeq (pg, svrintz_z (pg, x), x); 61 svisnotint (svbool_t pg, svfloat32_t x) argument 63 return svcmpne (pg, svrintz_z (pg, x), x); 68 svisodd (svbool_t pg, svfloat32_t x) argument 70 svfloat32_t y = svmul_x (pg, x, 0.5f); 71 return svisnotint (pg, y); 76 sv_zeroinfnan (svbool_t pg, svuint32_ argument 161 sv_powf_core_ext(const svbool_t pg, svuint64_t i, svfloat64_t z, svint64_t k, svfloat64_t y, svuint64_t sign_bias, svfloat64_t *pylogx, const struct data *d) argument 205 sv_powf_core(const svbool_t pg, svuint32_t i, svuint32_t iz, svint32_t k, svfloat32_t y, svuint32_t sign_bias, svfloat32_t *pylogx, const struct data *d) argument 253 pow(svfloat32_t x, svfloat32_t y, const svbool_t pg) argument [all...] |
H A D | sv_expm1f_inline.h | 35 expm1f_inline (svfloat32_t x, svbool_t pg, const struct sv_expm1f_data *d) argument 47 svfloat32_t j = svmla_x (pg, sv_f32 (d->shift), x, d->inv_ln2); 48 j = svsub_x (pg, j, d->shift); 49 svint32_t i = svcvt_s32_x (pg, j); 61 svfloat32_t f2 = svmul_x (pg, f, f); 62 svfloat32_t p = svmla_x (pg, p12, f2, p34); 63 p = svmla_x (pg, C (0), f, p); 64 p = svmla_x (pg, f, f2, p); 69 svfloat32_t t = svscale_x (pg, sv_f32 (1), i); 70 return svmla_x (pg, svsub_ [all...] |
H A D | sv_tanhf_2u6.c | 35 svfloat32_t SV_NAME_F1 (tanh) (svfloat32_t x, const svbool_t pg) argument 39 svfloat32_t ax = svabs_x (pg, x); 41 svuint32_t sign = sveor_x (pg, svreinterpret_u32 (x), iax); 42 svbool_t is_boring = svcmpgt (pg, iax, d->boring_bound); 43 svfloat32_t boring = svreinterpret_f32 (svorr_x (pg, sign, d->onef)); 45 svbool_t special = svcmpgt (pg, iax, 0x7f800000); 48 svfloat32_t q = expm1f_inline (svmul_x (pg, x, 2.0), pg, &d->expm1f_consts); 49 svfloat32_t y = svdiv_x (pg, q, svadd_x (pg, [all...] |
H A D | sv_tan_3u5.c | 40 svfloat64_t SV_NAME_D1 (tan) (svfloat64_t x, svbool_t pg) argument 45 svbool_t special = svnot_z (pg, svaclt (pg, x, dat->range_val)); 49 svfloat64_t q = svmla_x (pg, shift, x, dat->inv_half_pi); 50 q = svsub_x (pg, q, shift); 51 svint64_t qi = svcvt_s64_x (pg, q); 61 r = svmul_x (pg, r, 0.5); 69 svfloat64_t r2 = svmul_x (pg, r, r); 70 svfloat64_t r4 = svmul_x (pg, r2, r2); 71 svfloat64_t r8 = svmul_x (pg, r [all...] |
H A D | sv_exp10f_1u5.c | 49 svfloat32_t SV_NAME_F1 (exp10) (svfloat32_t x, const svbool_t pg) argument 63 svfloat32_t n = svsub_x (pg, z, shift); 69 svbool_t special = svacgt (pg, x, d->special_bound); 73 svfloat32_t r2 = svmul_x (pg, r, r); 75 = svmla_x (pg, svmul_x (pg, r, d->poly[0]), 76 sv_pairwise_poly_3_f32_x (pg, r, r2, d->poly + 1), r2); 78 if (unlikely (svptest_any (pg, special))) 79 return special_case (x, svmla_x (pg, scale, scale, poly), special); 81 return svmla_x (pg, scal [all...] |
H A D | sv_log10f_3u5.c | 47 svfloat32_t SV_NAME_F1 (log10) (svfloat32_t x, const svbool_t pg) argument 51 svbool_t special = svcmpge (pg, svsub_x (pg, ix, Min), Thres); 54 ix = svsub_x (pg, ix, Offset); 56 pg, svasr_x (pg, svreinterpret_s32 (ix), 23)); /* signextend. */ 57 ix = svand_x (pg, ix, MantissaMask); 58 ix = svadd_x (pg, ix, Offset); 59 svfloat32_t r = svsub_x (pg, svreinterpret_f32 (ix), 1.0f); 65 svfloat32_t r2 = svmul_x (pg, [all...] |
H A D | sv_erff_2u.c | 42 svfloat32_t SV_NAME_F1 (erf) (svfloat32_t x, const svbool_t pg) argument 47 svbool_t a_gt_min = svacgt (pg, x, dat->min); 50 svbool_t a_ge_max = svacge (pg, x, dat->max); 51 svfloat32_t a = svabs_x (pg, x); 54 svfloat32_t z = svadd_x (pg, a, shift); 56 = svsub_x (pg, svreinterpret_u32 (z), svreinterpret_u32 (shift)); 70 svfloat32_t d = svsub_x (pg, a, r); 71 svfloat32_t d2 = svmul_x (pg, d, d); 72 svfloat32_t y = svmla_x (pg, r, d, dat->third); 73 y = svmla_x (pg, erf [all...] |
H A D | sv_sin_3u5.c | 46 svfloat64_t SV_NAME_D1 (sin) (svfloat64_t x, const svbool_t pg) argument 58 svuint64_t odd = svlsl_x (pg, svreinterpret_u64 (n), 63); 59 n = svsub_x (pg, n, shift); 68 svfloat64_t r2 = svmul_x (pg, r, r); 69 svfloat64_t r3 = svmul_x (pg, r2, r); 70 svfloat64_t r4 = svmul_x (pg, r2, r2); 72 svfloat64_t t1 = svmla_x (pg, C (4), C (5), r2); 73 svfloat64_t t2 = svmla_x (pg, C (2), C (3), r2); 74 svfloat64_t t3 = svmla_x (pg, C (0), C (1), r2); 76 svfloat64_t y = svmla_x (pg, t [all...] |
H A D | sv_expf_2u.c | 44 svfloat32_t SV_NAME_F1 (exp) (svfloat32_t x, const svbool_t pg) argument 57 svfloat32_t n = svsub_x (pg, z, d->shift); 64 svbool_t is_special_case = svacgt (pg, x, d->thres); 68 svfloat32_t p12 = svmla_x (pg, C (1), C (2), r); 69 svfloat32_t p34 = svmla_x (pg, C (3), C (4), r); 70 svfloat32_t r2 = svmul_x (pg, r, r); 71 svfloat32_t p14 = svmla_x (pg, p12, p34, r2); 72 svfloat32_t p0 = svmul_x (pg, r, C (0)); 73 svfloat32_t poly = svmla_x (pg, p0, r2, p14); 75 if (unlikely (svptest_any (pg, is_special_cas [all...] |
H A D | sv_exp2f_1u6.c | 40 svfloat32_t SV_NAME_F1 (exp2) (svfloat32_t x, const svbool_t pg) argument 46 svfloat32_t z = svadd_x (pg, x, shift); 47 svfloat32_t n = svsub_x (pg, z, shift); 48 svfloat32_t r = svsub_x (pg, x, n); 50 svbool_t special = svacgt (pg, x, d->thres); 56 svfloat32_t r2 = svmul_x (pg, r, r); 57 svfloat32_t p14 = sv_pairwise_poly_3_f32_x (pg, r, r2, d->poly + 1); 58 svfloat32_t p0 = svmul_x (pg, r, d->poly[0]); 59 svfloat32_t poly = svmla_x (pg, p0, r2, p14); 61 if (unlikely (svptest_any (pg, specia [all...] |
H A D | sv_log2f_2u5.c | 44 svfloat32_t SV_NAME_F1 (log2) (svfloat32_t x, const svbool_t pg) argument 49 svbool_t special = svcmpge (pg, svsub_x (pg, u, Min), Thres); 52 u = svsub_x (pg, u, Off); 54 pg, svasr_x (pg, svreinterpret_s32 (u), 23)); /* Sign-extend. */ 55 u = svand_x (pg, u, MantissaMask); 56 u = svadd_x (pg, u, Off); 57 svfloat32_t r = svsub_x (pg, svreinterpret_f32 (u), 1.0f); 60 svfloat32_t r2 = svmul_x (pg, [all...] |
H A D | sv_cexpi_3u5.c | 25 _ZGVsMxv_cexpi (svfloat64_t x, svbool_t pg) argument 28 svbool_t special = check_ge_rangeval (pg, x, d); 30 svfloat64x2_t sc = sv_sincos_inline (pg, x, d); 32 if (unlikely (svptest_any (pg, special)))
|
H A D | sv_cexpif_1u8.c | 27 _ZGVsMxv_cexpif (svfloat32_t x, svbool_t pg) argument 30 svbool_t special = check_ge_rangeval (pg, x, d); 32 svfloat32x2_t sc = sv_sincosf_inline (pg, x, d); 34 if (unlikely (svptest_any (pg, special)))
|
H A D | sv_expf_inline.h | 36 expf_inline (svfloat32_t x, const svbool_t pg, const struct sv_expf_data *d) argument 46 svfloat32_t n = svsub_x (pg, z, d->shift); 56 svfloat32_t p12 = svmla_x (pg, C (1), C (2), r); 58 svfloat32_t r2 = svmul_f32_x (pg, r, r); 59 svfloat32_t p14 = svmla_x (pg, p12, p34, r2); 60 svfloat32_t p0 = svmul_f32_x (pg, r, C (0)); 61 svfloat32_t poly = svmla_x (pg, p0, r2, p14); 63 return svmla_x (pg, scale, scale, poly);
|
H A D | sv_sincos_3u5.c | 39 svbool_t pg) 42 svbool_t special = check_ge_rangeval (pg, x, d); 44 svfloat64x2_t sc = sv_sincos_inline (pg, x, d); 46 svst1 (pg, out_sin, svget2 (sc, 0)); 47 svst1 (pg, out_cos, svget2 (sc, 1)); 49 if (unlikely (svptest_any (pg, special))) 38 _ZGVsMxvl8l8_sincos(svfloat64_t x, double *out_sin, double *out_cos, svbool_t pg) argument
|
H A D | sv_sincosf_1u8.c | 40 svbool_t pg) 43 svbool_t special = check_ge_rangeval (pg, x, d); 45 svfloat32x2_t sc = sv_sincosf_inline (pg, x, d); 47 svst1_f32 (pg, out_sin, svget2 (sc, 0)); 48 svst1_f32 (pg, out_cos, svget2 (sc, 1)); 50 if (unlikely (svptest_any (pg, special))) 39 _ZGVsMxvl4l4_sincosf(svfloat32_t x, float *out_sin, float *out_cos, svbool_t pg) argument
|
H A D | sv_tanf_3u5.c | 49 svfloat32_t SV_NAME_F1 (tan) (svfloat32_t x, const svbool_t pg) argument 54 svbool_t cmp = svacge (pg, x, d->range_val); 61 svfloat32_t n = svsub_x (pg, q, d->shift); 63 svint32_t in = svcvt_s32_x (pg, n); 65 svint32_t alt = svand_x (pg, in, 1); 66 svbool_t pred_alt = svcmpne (pg, alt, 0); 86 svfloat32_t z2 = svmul_x (pg, z, z); 91 svfloat32_t z4 = svmul_x (pg, z2, z2); 92 svfloat32_t p = svmla_x (pg, p01, z4, p23); 94 svfloat32_t z8 = svmul_x (pg, z [all...] |
H A D | sv_cosf_2u1.c | 40 svfloat32_t SV_NAME_F1 (cos) (svfloat32_t x, const svbool_t pg) argument 44 svfloat32_t r = svabs_x (pg, x); 45 svbool_t oob = svcmpge (pg, svreinterpret_u32 (r), RangeVal); 52 svfloat32_t n = svsub_x (pg, q, d->shift); 71 if (unlikely (svptest_any (pg, oob))) 72 return special_case (x, svmul_x (svnot_z (pg, oob), f, y), oob); 74 return svmul_x (pg, f, y);
|
H A D | sv_cos_2u5.c | 40 svfloat64_t SV_NAME_D1 (cos) (svfloat64_t x, const svbool_t pg) argument 44 svfloat64_t r = svabs_x (pg, x); 45 svbool_t oob = svcmpge (pg, svreinterpret_u64 (r), RangeVal); 54 svfloat64_t n = svsub_x (pg, q, d->shift); 76 if (unlikely (svptest_any (pg, oob))) 77 return special_case (x, svmul_x (svnot_z (pg, oob), y, f), oob); 80 return svmul_x (pg, f, y);
|
/freebsd-current/lib/libc/db/btree/ |
H A D | bt_overflow.c | 77 pgno_t pg; local 81 memmove(&pg, p, sizeof(pgno_t)); 86 if (pg == P_INVALID || sz == 0) 102 for (p = *buf;; p = (char *)p + nb, pg = h->nextpg) { 103 if ((h = mpool_get(t->bt_mp, pg, 0)) == NULL) 128 __ovfl_put(BTREE *t, const DBT *dbt, pgno_t *pg) argument 158 *pg = h->pgno; 182 pgno_t pg; local 186 memmove(&pg, p, sizeof(pgno_t)); 190 if (pg [all...] |
H A D | bt_delete.c | 91 if ((h = mpool_get(t->bt_mp, c->pg.pgno, 0)) == NULL) 102 status = __bt_dleaf(t, NULL, h, c->pg.index); 157 if (h->pgno == c->pg.pgno) 166 while (h->pgno != c->pg.pgno) { 206 if (h->pgno == c->pg.pgno) 221 while (h->pgno != c->pg.pgno) { 264 return ((*hp = mpool_get(t->bt_mp, c->pg.pgno, 0)) == NULL); 367 PAGE *pg; local 387 if ((pg = mpool_get(t->bt_mp, parent->pgno, 0)) == NULL) 391 bi = GETBINTERNAL(pg, id 523 PAGE *pg; local 616 PAGE *pg; local [all...] |
H A D | bt_seq.c | 146 pgno_t pg; local 168 for (pg = P_ROOT;;) { 169 if ((h = mpool_get(t->bt_mp, pg, 0)) == NULL) 180 pg = GETBINTERNAL(h, 0)->pgno; 189 for (pg = P_ROOT;;) { 190 if ((h = mpool_get(t->bt_mp, pg, 0)) == NULL) 201 pg = GETBINTERNAL(h, NEXTINDEX(h) - 1)->pgno; 232 pgno_t pg; local 253 if ((h = mpool_get(t->bt_mp, c->pg.pgno, 0)) == NULL) 269 idx = c->pg 330 pgno_t pg; local [all...] |
/freebsd-current/sys/dev/adlink/ |
H A D | adlink.c | 132 struct pgstat *pg; local 142 pg = sc->next; 143 *(pg->sample) = sc->sample; 154 pg = pg->next; 155 sc->next = pg; 156 *(pg->sample) = 0; 157 bus_write_4(sc->res[0], 0x24, pg->phys); 170 struct pgstat *pg; local 180 pg 198 struct pgstat *pg; local [all...] |
/freebsd-current/sys/netpfil/ipfw/nat64/ |
H A D | nat64lsn.c | 140 static void nat64lsn_destroy_pg(struct nat64lsn_pg *pg); 223 #define FREEMASK_FFSLL(pg, faddr) \ 224 ffsll(*FREEMASK_CHUNK((pg), (faddr))) 225 #define FREEMASK_BTR(pg, faddr, bit) \ 226 ck_pr_btr_64(FREEMASK_CHUNK((pg), (faddr)), (bit)) 227 #define FREEMASK_BTS(pg, faddr, bit) \ 228 ck_pr_bts_64(FREEMASK_CHUNK((pg), (faddr)), (bit)) 229 #define FREEMASK_ISSET(pg, faddr, bit) \ 230 ISSET64(*FREEMASK_CHUNK((pg), (faddr)), (bit)) 231 #define FREEMASK_COPY(pg, 264 struct nat64lsn_pg *pg, *oldpg; local 315 struct nat64lsn_pg *pg; local 485 struct nat64lsn_pg *pg; local 744 nat64lsn_maintain_pg(struct nat64lsn_cfg *cfg, struct nat64lsn_pg *pg) argument 817 struct nat64lsn_pg *pg, *tpg, *firstpg, **pgptr; local 1110 struct nat64lsn_pg *pg; local 1370 struct nat64lsn_pg *pg; local 1719 nat64lsn_destroy_pg(struct nat64lsn_pg *pg) argument 1738 struct nat64lsn_pg *pg; local [all...] |
/freebsd-current/lib/libc/db/recno/ |
H A D | rec_search.c | 64 pgno_t pg; local 70 for (pg = P_ROOT, total = 0;;) { 71 if ((h = mpool_get(t->bt_mp, pg, 0)) == NULL) 85 BT_PUSH(t, pg, idx - 1); 87 pg = r->pgno;
|