/freebsd-current/contrib/arm-optimized-routines/pl/math/ |
H A D | sv_cbrtf_1u7.c | 41 shifted_lookup (const svbool_t pg, const float32_t *table, svint32_t i) argument 43 return svld1_gather_index (pg, table, svadd_x (pg, i, 2)); 52 svfloat32_t SV_NAME_F1 (cbrt) (svfloat32_t x, const svbool_t pg) argument 56 svfloat32_t ax = svabs_x (pg, x); 58 svuint32_t sign = sveor_x (pg, svreinterpret_u32 (x), iax); 61 svbool_t special = svcmpge (pg, svsub_x (pg, iax, SmallestNormal), Thresh); 67 pg, svand_x (pg, svreinterpret_u3 [all...] |
H A D | sv_sincos_common.h | 32 check_ge_rangeval (svbool_t pg, svfloat64_t x, const struct sv_sincos_data *d) argument 34 svbool_t in_bounds = svaclt (pg, x, d->range_val); 35 return svnot_z (pg, in_bounds); 44 sv_sincos_inline (svbool_t pg, svfloat64_t x, const struct sv_sincos_data *d) argument 47 svfloat64_t q = svsub_x (pg, svmla_x (pg, sv_f64 (d->shift), x, d->inv_pio2), 49 svint64_t n = svcvt_s64_x (pg, q); 53 r = svmls_x (pg, r, q, d->pio2[0]); 54 r = svmls_x (pg, r, q, d->pio2[1]); 55 r = svmls_x (pg, [all...] |
H A D | sv_asinhf_2u5.c | 29 svfloat32_t SV_NAME_F1 (asinh) (svfloat32_t x, const svbool_t pg) argument 31 svfloat32_t ax = svabs_x (pg, x); 33 svuint32_t sign = sveor_x (pg, svreinterpret_u32 (x), iax); 34 svbool_t special = svcmpge (pg, iax, BigBound); 38 svfloat32_t ax2 = svmul_x (pg, ax, ax); 39 svfloat32_t d = svadd_x (pg, svsqrt_x (pg, svadd_x (pg, ax2, 1.0f)), 1.0f); 41 = sv_log1pf_inline (svadd_x (pg, ax, svdiv_x (pg, ax [all...] |
H A D | sv_sinhf_2u3.c | 26 special_case (svfloat32_t x, svfloat32_t y, svbool_t pg) argument 28 return sv_call_f32 (sinhf, x, y, pg); 36 svfloat32_t SV_NAME_F1 (sinh) (svfloat32_t x, const svbool_t pg) argument 39 svfloat32_t ax = svabs_x (pg, x); 41 = sveor_x (pg, svreinterpret_u32 (x), svreinterpret_u32 (ax)); 42 svfloat32_t halfsign = svreinterpret_f32 (svorr_x (pg, sign, d->halff)); 44 svbool_t special = svcmpge (pg, svreinterpret_u32 (ax), d->large_bound); 49 svfloat32_t t = expm1f_inline (ax, pg, &d->expm1f_consts); 50 t = svadd_x (pg, t, svdiv_x (pg, [all...] |
H A D | sv_log_2u5.c | 29 svfloat64_t SV_NAME_D1 (log) (svfloat64_t x, const svbool_t pg) argument 32 svuint64_t top = svlsr_x (pg, ix, 52); 33 svbool_t cmp = svcmpge (pg, svsub_x (pg, top, MinTop), sv_u64 (ThreshTop)); 38 svuint64_t tmp = svsub_x (pg, ix, Off); 42 = svand_x (pg, svlsr_x (pg, tmp, (51 - V_LOG_TABLE_BITS)), (N - 1) << 1); 44 = svasr_x (pg, svreinterpret_s64 (tmp), 52); /* Arithmetic shift. */ 45 svuint64_t iz = svsub_x (pg, ix, svand_x (pg, tm [all...] |
H A D | sv_cosh_2u.c | 42 exp_inline (svfloat64_t x, const svbool_t pg, const struct data *d) argument 45 svfloat64_t z = svmla_x (pg, sv_f64 (d->shift), x, d->inv_ln2); 46 svfloat64_t n = svsub_x (pg, z, d->shift); 48 svfloat64_t r = svmla_x (pg, x, n, d->ln2_hi); 49 r = svmla_x (pg, r, n, d->ln2_lo); 52 svuint64_t e = svlsl_x (pg, u, 52 - V_EXP_TAIL_TABLE_BITS); 53 svuint64_t i = svand_x (pg, u, d->index_mask); 55 svfloat64_t y = svmla_x (pg, sv_f64 (d->poly[1]), r, d->poly[2]); 56 y = svmla_x (pg, sv_f64 (d->poly[0]), r, y); 57 y = svmla_x (pg, sv_f6 77 cosh(svfloat64_t x, const svbool_t pg) argument [all...] |
H A D | sv_log1p_inline.h | 39 sv_log1p_inline (svfloat64_t x, const svbool_t pg) argument 51 svfloat64_t m = svadd_x (pg, x, 1); 53 svuint64_t u = svadd_x (pg, mi, d->one_m_hf_rt2_top); 56 = svsub_x (pg, svreinterpret_s64 (svlsr_x (pg, u, 52)), d->one_top); 57 svfloat64_t k = svcvt_f64_x (pg, ki); 61 = svadd_x (pg, svand_x (pg, u, 0x000fffff00000000), d->hf_rt2_top); 62 svuint64_t u_red = svorr_x (pg, utop, svand_x (pg, m [all...] |
H A D | sv_cbrt_2u.c | 45 shifted_lookup (const svbool_t pg, const float64_t *table, svint64_t i) argument 47 return svld1_gather_index (pg, table, svadd_x (pg, i, 2)); 57 svfloat64_t SV_NAME_D1 (cbrt) (svfloat64_t x, const svbool_t pg) argument 61 svfloat64_t ax = svabs_x (pg, x); 63 svuint64_t sign = sveor_x (pg, svreinterpret_u64 (x), iax); 66 svbool_t special = svcmpge (pg, svsub_x (pg, iax, d->tiny_bound), d->thresh); 72 pg, svand_x (pg, svreinterpret_u6 [all...] |
H A D | sv_atan2_2u5.c | 44 zeroinfnan (svuint64_t i, const svbool_t pg) argument 46 return svcmpge (pg, svsub_x (pg, svlsl_x (pg, i, 1), 1), 54 svfloat64_t SV_NAME_D2 (atan2) (svfloat64_t y, svfloat64_t x, const svbool_t pg) argument 61 svbool_t cmp_x = zeroinfnan (ix, pg); 62 svbool_t cmp_y = zeroinfnan (iy, pg); 63 svbool_t cmp_xy = svorr_z (pg, cmp_x, cmp_y); 65 svuint64_t sign_x = svand_x (pg, ix, SignMask); 66 svuint64_t sign_y = svand_x (pg, i [all...] |
H A D | sv_atanh_3u3.c | 28 svfloat64_t SV_NAME_D1 (atanh) (svfloat64_t x, const svbool_t pg) argument 31 svfloat64_t ax = svabs_x (pg, x); 33 svuint64_t sign = sveor_x (pg, svreinterpret_u64 (x), iax); 34 svfloat64_t halfsign = svreinterpret_f64 (svorr_x (pg, sign, Half)); 37 // svbool_t special = svcmpge (pg, iax, One); 38 svbool_t special = svacge (pg, x, 1.0); 43 y = svadd_x (pg, ax, ax); 44 y = svdiv_x (pg, y, svsub_x (pg, sv_f64 (1), ax)); 46 y = sv_log1p_inline (y, pg); [all...] |
H A D | sv_atanhf_2u8.c | 28 svfloat32_t SV_NAME_F1 (atanh) (svfloat32_t x, const svbool_t pg) argument 30 svfloat32_t ax = svabs_x (pg, x); 32 svuint32_t sign = sveor_x (pg, svreinterpret_u32 (x), iax); 33 svfloat32_t halfsign = svreinterpret_f32 (svorr_x (pg, sign, Half)); 34 svbool_t special = svcmpge (pg, iax, One); 38 svfloat32_t y = svadd_x (pg, ax, ax); 39 y = svdiv_x (pg, y, svsub_x (pg, sv_f32 (1), ax)); 41 y = sv_log1pf_inline (y, pg); 43 if (unlikely (svptest_any (pg, specia [all...] |
H A D | sv_log1pf_1u3.c | 41 svfloat32_t SV_NAME_F1 (log1p) (svfloat32_t x, svbool_t pg) argument 45 svbool_t special = svcmpeq (pg, svreinterpret_u32 (x), 0x7f800000); 46 special = svorn_z (pg, special, svcmpge (pg, x, -1)); 56 svfloat32_t m = svadd_x (pg, x, 1); 60 = svand_x (pg, svsub_x (pg, svreinterpret_s32 (m), d->three_quarters), 65 svsub_x (pg, svreinterpret_u32 (x), svreinterpret_u32 (k))); 69 svfloat32_t s = svreinterpret_f32 (svsubr_x (pg, k, d->four)); 70 m_scale = svadd_x (pg, m_scal [all...] |
H A D | sv_sincosf_common.h | 25 check_ge_rangeval (svbool_t pg, svfloat32_t x, const struct sv_sincosf_data *d) argument 27 svbool_t in_bounds = svaclt (pg, x, d->range_val); 28 return svnot_z (pg, in_bounds); 39 sv_sincosf_inline (svbool_t pg, svfloat32_t x, const struct sv_sincosf_data *d) argument 42 svfloat32_t q = svmla_x (pg, sv_f32 (d->shift), x, d->inv_pio2); 43 q = svsub_x (pg, q, d->shift); 44 svint32_t n = svcvt_s32_x (pg, q); 48 r = svmls_x (pg, r, q, d->pio2[0]); 49 r = svmls_x (pg, r, q, d->pio2[1]); 50 r = svmls_x (pg, [all...] |
H A D | sv_log10_2u5.c | 29 svfloat64_t SV_NAME_D1 (log10) (svfloat64_t x, const svbool_t pg) argument 32 svbool_t special = svcmpge (pg, svsub_x (pg, ix, Min), Thres); 37 svuint64_t tmp = svsub_x (pg, ix, Off); 38 svuint64_t i = svlsr_x (pg, tmp, 51 - V_LOG10_TABLE_BITS); 39 i = svand_x (pg, i, (N - 1) << 1); 40 svfloat64_t k = svcvt_f64_x (pg, svasr_x (pg, svreinterpret_s64 (tmp), 52)); 42 svsub_x (pg, ix, svand_x (pg, tm [all...] |
H A D | sv_log2_3u.c | 31 svfloat64_t SV_NAME_D1 (log2) (svfloat64_t x, const svbool_t pg) argument 34 svbool_t special = svcmpge (pg, svsub_x (pg, ix, Min), Thresh); 39 svuint64_t tmp = svsub_x (pg, ix, Off); 40 svuint64_t i = svlsr_x (pg, tmp, 51 - V_LOG2_TABLE_BITS); 41 i = svand_x (pg, i, (N - 1) << 1); 42 svfloat64_t k = svcvt_f64_x (pg, svasr_x (pg, svreinterpret_s64 (tmp), 52)); 44 svsub_x (pg, ix, svand_x (pg, tm [all...] |
H A D | sv_coshf_2u.c | 25 special_case (svfloat32_t x, svfloat32_t y, svbool_t pg) argument 27 return sv_call_f32 (coshf, x, y, pg); 34 svfloat32_t SV_NAME_F1 (cosh) (svfloat32_t x, svbool_t pg) argument 38 svfloat32_t ax = svabs_x (pg, x); 39 svbool_t special = svcmpge (pg, svreinterpret_u32 (ax), d->special_bound); 42 svfloat32_t t = expf_inline (ax, pg, &d->expf_consts); 43 svfloat32_t half_t = svmul_x (pg, t, 0.5); 44 svfloat32_t half_over_t = svdivr_x (pg, t, 0.5); 46 if (unlikely (svptest_any (pg, special))) 47 return special_case (x, svadd_x (pg, half_ [all...] |
H A D | sv_cospif_2u6.c | 29 svfloat32_t SV_NAME_F1 (cospi) (svfloat32_t x, const svbool_t pg) argument 36 svfloat32_t n = svrinta_x (pg, x); 37 svfloat32_t r = svsub_x (pg, x, n); 38 r = svsub_x (pg, sv_f32 (0.5f), svabs_x (pg, r)); 42 svbool_t cmp = svaclt (pg, x, d->range_val); 43 svuint32_t intn = svreinterpret_u32 (svcvt_s32_x (pg, n)); 47 svfloat32_t r2 = svmul_x (pg, r, r); 48 svfloat32_t y = sv_horner_5_f32_x (pg, r2, d->poly); 49 y = svmul_x (pg, [all...] |
H A D | sv_acosh_3u5.c | 28 svfloat64_t SV_NAME_D1 (acosh) (svfloat64_t x, const svbool_t pg) argument 30 svuint64_t itop = svlsr_x (pg, svreinterpret_u64 (x), 52); 32 svbool_t special = svcmpge (pg, svsub_x (pg, itop, OneTop), sv_u64 (0x1ff)); 34 svfloat64_t xm1 = svsub_x (pg, x, 1); 35 svfloat64_t u = svmul_x (pg, xm1, svadd_x (pg, x, 1)); 36 svfloat64_t y = sv_log1p_inline (svadd_x (pg, xm1, svsqrt_x (pg, u)), pg); [all...] |
H A D | sv_erf_2u5.c | 47 svfloat64_t SV_NAME_D1 (erf) (svfloat64_t x, const svbool_t pg) argument 53 svbool_t a_ge_max = svacge (pg, x, dat->max); 54 svbool_t a_lt_max = svaclt (pg, x, dat->max); 57 svfloat64_t a = svabs_x (pg, x); 59 svfloat64_t z = svadd_x (pg, a, shift); 61 = svsub_x (pg, svreinterpret_u64 (z), svreinterpret_u64 (shift)); 65 svfloat64_t r = svsub_x (pg, z, shift); 70 svfloat64_t d = svsub_x (pg, a, r); 71 svfloat64_t d2 = svmul_x (pg, d, d); 72 svfloat64_t r2 = svmul_x (pg, [all...] |
H A D | sv_log1p_2u5.c | 51 svfloat64_t SV_NAME_D1 (log1p) (svfloat64_t x, svbool_t pg) argument 55 svuint64_t ax = svand_x (pg, ix, AbsMask); 57 = svorr_z (pg, svcmpge (pg, ax, d->inf), svcmpge (pg, ix, d->mone)); 74 svfloat64_t m = svadd_x (pg, x, 1); 76 svuint64_t u = svadd_x (pg, mi, d->onemhfrt2_top); 78 svint64_t ki = svsub_x (pg, svreinterpret_s64 (svlsr_x (pg, u, 52)), 0x3ff); 79 svfloat64_t k = svcvt_f64_x (pg, k [all...] |
H A D | sv_sinh_3u.c | 40 expm1_inline (svfloat64_t x, svbool_t pg) argument 49 = svsub_x (pg, svmla_x (pg, sv_f64 (d->shift), x, d->inv_ln2), d->shift); 50 svint64_t i = svcvt_s64_x (pg, j); 51 svfloat64_t f = svmla_x (pg, x, j, d->m_ln2_hi); 52 f = svmla_x (pg, f, j, d->m_ln2_lo); 54 svfloat64_t f2 = svmul_x (pg, f, f); 55 svfloat64_t f4 = svmul_x (pg, f2, f2); 56 svfloat64_t f8 = svmul_x (pg, f4, f4); 58 = svmla_x (pg, 66 special_case(svfloat64_t x, svbool_t pg) argument 76 sinh(svfloat64_t x, svbool_t pg) argument [all...] |
H A D | sv_atan2f_3u.c | 38 zeroinfnan (svuint32_t i, const svbool_t pg) argument 40 return svcmpge (pg, svsub_x (pg, svlsl_x (pg, i, 1), 1), 49 svfloat32_t SV_NAME_F2 (atan2) (svfloat32_t y, svfloat32_t x, const svbool_t pg) argument 56 svbool_t cmp_x = zeroinfnan (ix, pg); 57 svbool_t cmp_y = zeroinfnan (iy, pg); 58 svbool_t cmp_xy = svorr_z (pg, cmp_x, cmp_y); 60 svuint32_t sign_x = svand_x (pg, ix, SignMask); 61 svuint32_t sign_y = svand_x (pg, i [all...] |
H A D | sv_asinh_3u0.c | 31 __sv_log_inline (svfloat64_t x, const svbool_t pg) argument 37 svuint64_t tmp = svsub_x (pg, ix, OFF); 39 = svand_x (pg, svlsr_x (pg, tmp, (51 - V_LOG_TABLE_BITS)), (N - 1) << 1); 40 svint64_t k = svasr_x (pg, svreinterpret_s64 (tmp), 52); 41 svuint64_t iz = svsub_x (pg, ix, svand_x (pg, tmp, 0xfffULL << 52)); 43 svfloat64_t invc = svld1_gather_index (pg, &__v_log_data.table[0].invc, i); 44 svfloat64_t logc = svld1_gather_index (pg, &__v_log_data.table[0].logc, i); 45 svfloat64_t r = svmla_x (pg, sv_f6 68 asinh(svfloat64_t x, const svbool_t pg) argument [all...] |
H A D | sv_log1pf_inline.h | 31 eval_poly (svfloat32_t m, const float32_t *c, svbool_t pg) argument 33 svfloat32_t p_12 = svmla_x (pg, sv_f32 (c[0]), m, sv_f32 (c[1])); 34 svfloat32_t m2 = svmul_x (pg, m, m); 35 svfloat32_t q = svmla_x (pg, m, m2, p_12); 36 svfloat32_t p = sv_pw_horner_6_f32_x (pg, m, m2, c + 2); 37 p = svmul_x (pg, m2, p); 39 return svmla_x (pg, q, m2, p); 43 sv_log1pf_inline (svfloat32_t x, svbool_t pg) argument 47 svfloat32_t m = svadd_x (pg, x, 1.0f); 49 svint32_t ks = svsub_x (pg, svreinterpret_s3 [all...] |
/freebsd-current/contrib/lib9p/ |
H A D | rfuncs.c | 225 r_pginit(struct r_pgdata *pg) argument 229 pg->r_pgbufsize = 1 << 9; 230 pg->r_pgbuf = NULL; /* note that realloc(NULL) == malloc */ 234 r_pgexpand(struct r_pgdata *pg) argument 238 nsize = pg->r_pgbufsize << 1; 240 (pg->r_pgbuf = realloc(pg->r_pgbuf, nsize)) == NULL) 246 r_pgfree(struct r_pgdata *pg) argument 249 free(pg->r_pgbuf); 253 r_getpwuid(uid_t uid, struct r_pgdata *pg) argument 270 r_getgrgid(gid_t gid, struct r_pgdata *pg) argument 288 r_cap_getpwuid(cap_channel_t *cap, uid_t uid, struct r_pgdata *pg) argument 305 r_cap_getgrgid(cap_channel_t *cap, gid_t gid, struct r_pgdata *pg) argument [all...] |