Searched refs:pg (Results 51 - 75 of 172) sorted by relevance

1234567

/freebsd-current/contrib/arm-optimized-routines/pl/math/
H A Dsv_powf_2u6.c54 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 Dsv_expm1f_inline.h35 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 Dsv_tanhf_2u6.c35 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 Dsv_tan_3u5.c40 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 Dsv_exp10f_1u5.c49 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 Dsv_log10f_3u5.c47 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 Dsv_erff_2u.c42 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 Dsv_sin_3u5.c46 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 Dsv_expf_2u.c44 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 Dsv_exp2f_1u6.c40 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 Dsv_log2f_2u5.c44 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 Dsv_cexpi_3u5.c25 _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 Dsv_cexpif_1u8.c27 _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 Dsv_expf_inline.h36 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 Dsv_sincos_3u5.c39 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 Dsv_sincosf_1u8.c40 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 Dsv_tanf_3u5.c49 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 Dsv_cosf_2u1.c40 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 Dsv_cos_2u5.c40 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 Dbt_overflow.c77 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 Dbt_delete.c91 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 Dbt_seq.c146 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 Dadlink.c132 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 Dnat64lsn.c140 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 Drec_search.c64 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;

Completed in 244 milliseconds

1234567