Home
last modified time | relevance | path

Searched refs:vlo (Results 1 – 15 of 15) sorted by relevance

/freebsd/contrib/llvm-project/llvm/lib/Target/VE/
H A DVEInstrPatternsVec.td137 def : Pat<(v512i1 (vec_pack v256i1:$vlo, v256i1:$vhi, (i32 srcvalue))),
140 $vlo, sub_vm_odd),
161 def : Pat<(v512i32 (vec_pack v256i32:$vlo, v256i32:$vhi, i32:$avl)),
162 (VSHFvvil $vlo, $vhi, 13, $avl)>;
163 def : Pat<(v512f32 (vec_pack v256f32:$vlo, v256f32:$vhi, i32:$avl)),
164 (VSHFvvil $vlo, $vhi, 8, $avl)>;
/freebsd/sys/dev/hwpmc/
H A Dhwpmc_powerpc.c410 pmc_value_t vlo; in powerpc_write_pmc() local
419 vlo = v % (POWERPC_MAX_PMC_VALUE + 1); in powerpc_write_pmc()
426 vlo = POWERPC_RELOAD_COUNT_TO_PERFCTR_VALUE(v); in powerpc_write_pmc()
430 (uintmax_t)vlo); in powerpc_write_pmc()
432 powerpc_pmcn_write(ri, vlo); in powerpc_write_pmc()
/freebsd/sys/dev/ath/ath_hal/ar5212/
H A Dar5112.c49 uint32_t *vlo, uint32_t *vhi);
566 uint32_t *vlo, uint32_t *vhi) in ar5212GetLowerUpperIndex() argument
576 *vlo = *vhi = 0; in ar5212GetLowerUpperIndex()
580 *vlo = *vhi = listSize - 1; in ar5212GetLowerUpperIndex()
591 *vlo = *vhi = tp - lp; in ar5212GetLowerUpperIndex()
599 *vlo = tp - lp; in ar5212GetLowerUpperIndex()
600 *vhi = *vlo + 1; in ar5212GetLowerUpperIndex()
H A Dar2316.c253 uint32_t *vlo, uint32_t *vhi) in GetLowerUpperIndex() argument
263 *vlo = *vhi = 0; in GetLowerUpperIndex()
267 *vlo = *vhi = listSize - 1; in GetLowerUpperIndex()
278 *vlo = *vhi = tp - (const int16_t *) lp; in GetLowerUpperIndex()
286 *vlo = tp - (const int16_t *) lp; in GetLowerUpperIndex()
287 *vhi = *vlo + 1; in GetLowerUpperIndex()
H A Dar2317.c230 uint32_t *vlo, uint32_t *vhi) in GetLowerUpperIndex() argument
240 *vlo = *vhi = 0; in GetLowerUpperIndex()
244 *vlo = *vhi = listSize - 1; in GetLowerUpperIndex()
255 *vlo = *vhi = tp - (const int16_t *) lp; in GetLowerUpperIndex()
263 *vlo = tp - (const int16_t *) lp; in GetLowerUpperIndex()
264 *vhi = *vlo + 1; in GetLowerUpperIndex()
H A Dar2413.c247 uint32_t *vlo, uint32_t *vhi) in GetLowerUpperIndex() argument
257 *vlo = *vhi = 0; in GetLowerUpperIndex()
261 *vlo = *vhi = listSize - 1; in GetLowerUpperIndex()
272 *vlo = *vhi = tp - (const uint16_t *) lp; in GetLowerUpperIndex()
280 *vlo = tp - (const uint16_t *) lp; in GetLowerUpperIndex()
281 *vhi = *vlo + 1; in GetLowerUpperIndex()
H A Dar2425.c248 uint32_t *vlo, uint32_t *vhi) in GetLowerUpperIndex() argument
258 *vlo = *vhi = 0; in GetLowerUpperIndex()
262 *vlo = *vhi = listSize - 1; in GetLowerUpperIndex()
273 *vlo = *vhi = tp - (const uint16_t *) lp; in GetLowerUpperIndex()
281 *vlo = tp - (const uint16_t *) lp; in GetLowerUpperIndex()
282 *vhi = *vlo + 1; in GetLowerUpperIndex()
H A Dar5413.c289 uint32_t *vlo, uint32_t *vhi) in GetLowerUpperIndex() argument
299 *vlo = *vhi = 0; in GetLowerUpperIndex()
303 *vlo = *vhi = listSize - 1; in GetLowerUpperIndex()
314 *vlo = *vhi = tp - (const uint16_t *) lp; in GetLowerUpperIndex()
322 *vlo = tp - (const uint16_t *) lp; in GetLowerUpperIndex()
323 *vhi = *vlo + 1; in GetLowerUpperIndex()
H A Dar5212_reset.c2626 uint16_t *vlo, uint16_t *vhi) in ar5212GetLowerUpperValues() argument
2635 *vlo = *vhi = lp[0]; in ar5212GetLowerUpperValues()
2639 *vlo = *vhi = ep[-1]; in ar5212GetLowerUpperValues()
2650 *vlo = *vhi = lp[0]; in ar5212GetLowerUpperValues()
2658 *vlo = lp[0]; in ar5212GetLowerUpperValues()
/freebsd/contrib/arm-optimized-routines/math/aarch64/advsimd/
H A Dpow.c240 float64x2_t vlo; in V_NAME_D2() local
241 float64x2_t vhi = v_log_inline (vix, &vlo, d); in V_NAME_D2()
246 float64x2_t neg_velo = vfmsq_f64 (vemi, y, vlo); in V_NAME_D2()
/freebsd/contrib/arm-optimized-routines/math/aarch64/sve/
H A Dpow.c417 svfloat64_t vlo; in SV_NAME_D2() local
418 svfloat64_t vhi = sv_log_inline (yint_or_xpos, vix, &vlo, d); in SV_NAME_D2()
423 svfloat64_t velo = svnmls_x (yint_or_xpos, vemi, y, vlo); in SV_NAME_D2()
/freebsd/sys/x86/x86/
H A Dlocal_apic.c282 lapic_write_icr(uint32_t vhi, uint32_t vlo) in lapic_write_icr() argument
288 v = ((uint64_t)vhi << 32) | vlo; in lapic_write_icr()
294 lapic_write32(LAPIC_ICR_LO, vlo); in lapic_write_icr()
300 lapic_write_icr_lo(uint32_t vlo) in lapic_write_icr_lo() argument
305 wrmsr(MSR_APIC_000 + LAPIC_ICR_LO, vlo); in lapic_write_icr_lo()
307 lapic_write32(LAPIC_ICR_LO, vlo); in lapic_write_icr_lo()
/freebsd/tools/tools/ath/athrd/
H A Dathrd.c1281 u_int16_t *vlo, u_int16_t *vhi) in ar5212GetLowerUpperValues() argument
1290 *vlo = *vhi = lp[0]; in ar5212GetLowerUpperValues()
1294 *vlo = *vhi = ep[-1]; in ar5212GetLowerUpperValues()
1305 *vlo = *vhi = lp[0]; in ar5212GetLowerUpperValues()
1313 *vlo = lp[0]; in ar5212GetLowerUpperValues()
/freebsd/sys/x86/cpufreq/
H A Dest.c95 #define INTEL(tab, zhi, vhi, zlo, vlo, bus_clk) \ argument
96 { CPU_VENDOR_INTEL, ID32(zhi, vhi, zlo, vlo, bus_clk), tab, nitems(tab) }
97 #define CENTAUR(tab, zhi, vhi, zlo, vlo, bus_clk) \ argument
98 { CPU_VENDOR_CENTAUR, ID32(zhi, vhi, zlo, vlo, bus_clk), tab, nitems(tab) }
/freebsd/contrib/sqlite3/
H A Dsqlite3.c207446 u32 v, vlo;
207456 && ((vlo = jsonHexToInt4(&z[8]))&0xfc00)==0xdc00
207458 *piOut = ((v&0x3ff)<<10) + (vlo&0x3ff) + 0x10000;