Home
last modified time | relevance | path

Searched refs:sr (Results 1 – 25 of 224) sorted by relevance

123456789

/freebsd/contrib/llvm-project/compiler-rt/lib/builtins/
H A Dudivmoddi4.c36 unsigned sr; in __udivmoddi4() local
90 sr = clzsi(d.s.high) - clzsi(n.s.high); in __udivmoddi4()
92 if (sr > n_uword_bits - 2) { in __udivmoddi4()
97 ++sr; in __udivmoddi4()
101 q.s.high = n.s.low << (n_uword_bits - sr); in __udivmoddi4()
103 r.s.high = n.s.high >> sr; in __udivmoddi4()
104 r.s.low = (n.s.high << (n_uword_bits - sr)) | (n.s.low >> sr); in __udivmoddi4()
115 sr = ctzsi(d.s.low); in __udivmoddi4()
116 q.s.high = n.s.high >> sr; in __udivmoddi4()
117 q.s.low = (n.s.high << (n_uword_bits - sr)) | (n.s.low >> sr); in __udivmoddi4()
[all …]
H A Dint_div_impl.inc19 unsigned sr = (d ? clz(d) : N) - (n ? clz(n) : N);
20 // 0 <= sr <= N - 1 or sr is very large.
21 if (sr > N - 1) // n < d
23 if (sr == N - 1) // d == 1
25 ++sr;
26 // 1 <= sr <= N - 1. Shifts do not trigger UB.
27 fixuint_t r = n >> sr;
28 n <<= N - sr;
30 for (; sr > 0; --sr) {
48 unsigned sr = (d ? clz(d) : N) - (n ? clz(n) : N);
[all …]
/freebsd/sys/contrib/openzfs/module/zfs/
H A Dspace_reftree.c77 space_ref_t *sr; in space_reftree_destroy() local
80 while ((sr = avl_destroy_nodes(t, &cookie)) != NULL) in space_reftree_destroy()
81 kmem_free(sr, sizeof (*sr)); in space_reftree_destroy()
89 space_ref_t *sr; in space_reftree_add_node() local
91 sr = kmem_alloc(sizeof (*sr), KM_SLEEP); in space_reftree_add_node()
92 sr->sr_offset = offset; in space_reftree_add_node()
93 sr->sr_refcnt = refcnt; in space_reftree_add_node()
95 avl_add(t, sr); in space_reftree_add_node()
130 space_ref_t *sr; in space_reftree_generate_map() local
134 for (sr = avl_first(t); sr != NULL; sr = AVL_NEXT(t, sr)) { in space_reftree_generate_map()
[all …]
/freebsd/lib/libiconv_modules/mapper_serial/
H A Dcitrus_mapper_serial.c105 uninit(struct _citrus_mapper_serial *sr) in uninit() argument
109 while ((ml = STAILQ_FIRST(&sr->sr_mappers)) != NULL) { in uninit()
110 STAILQ_REMOVE_HEAD(&sr->sr_mappers, ml_entry); in uninit()
118 struct _citrus_mapper_serial *sr, struct _memstream *ms) in parse_var() argument
125 STAILQ_INIT(&sr->sr_mappers); in parse_var()
153 STAILQ_INSERT_TAIL(&sr->sr_mappers, ml, ml_entry); in parse_var()
165 struct _citrus_mapper_serial *sr; in _citrus_mapper_serial_mapper_init() local
172 sr = malloc(sizeof(*sr)); in _citrus_mapper_serial_mapper_init()
173 if (sr == NULL) in _citrus_mapper_serial_mapper_init()
178 if (parse_var(ma, sr, &ms)) { in _citrus_mapper_serial_mapper_init()
[all …]
/freebsd/crypto/openssl/crypto/ripemd/asm/
H A Drmd-586.pl62 @sr=( 8, 9, 9,11,13,15,15, 5, 7, 7, 8,11,14,14,12, 6,
456 &RIP5($A,$B,$C,$D,$E,$wr[ 0],$sr[ 0],$KR0,-2);
457 &RIP5($E,$A,$B,$C,$D,$wr[ 1],$sr[ 1],$KR0,0);
458 &RIP5($D,$E,$A,$B,$C,$wr[ 2],$sr[ 2],$KR0,0);
459 &RIP5($C,$D,$E,$A,$B,$wr[ 3],$sr[ 3],$KR0,0);
460 &RIP5($B,$C,$D,$E,$A,$wr[ 4],$sr[ 4],$KR0,0);
461 &RIP5($A,$B,$C,$D,$E,$wr[ 5],$sr[ 5],$KR0,0);
462 &RIP5($E,$A,$B,$C,$D,$wr[ 6],$sr[ 6],$KR0,0);
463 &RIP5($D,$E,$A,$B,$C,$wr[ 7],$sr[ 7],$KR0,0);
464 &RIP5($C,$D,$E,$A,$B,$wr[ 8],$sr[ 8],$KR0,0);
[all …]
/freebsd/sys/powerpc/mpc85xx/
H A Dmpc85xx.c112 law_write(uint32_t n, uint64_t bar, uint32_t sr) in law_write() argument
118 ccsr_write4(OCP85XX_LAWSR_QORIQ(n), sr); in law_write()
122 ccsr_write4(OCP85XX_LAWSR_85XX(n), sr); in law_write()
137 law_read(uint32_t n, uint64_t *bar, uint32_t *sr) in law_read() argument
143 *sr = ccsr_read4(OCP85XX_LAWSR_QORIQ(n)); in law_read()
146 *sr = ccsr_read4(OCP85XX_LAWSR_85XX(n)); in law_read()
153 uint32_t i,sr; in law_find_free() local
160 law_read(i, &bar, &sr); in law_find_free()
161 if ((sr & 0x80000000) == 0) in law_find_free()
175 uint32_t sr, sr_tmp; in law_enable() local
[all …]
/freebsd/contrib/llvm-project/lld/ELF/
H A DARMErrataFix.cpp413 static void implementPatch(ScanResult sr, InputSection *isec, in implementPatch() argument
417 utohexstr(isec->getVA(sr.off)) + " in unpatched output."); in implementPatch()
430 if (sr.rel) { in implementPatch()
437 int64_t patchRelAddend = sr.rel->addend; in implementPatch()
439 if (isBL(sr.instr) || isBLX(sr.instr)) { in implementPatch()
443 uint64_t dstSymAddr = (sr.rel->expr == R_PLT_PC) ? sr.rel->sym->getPltVA() in implementPatch()
444 : sr.rel->sym->getVA(); in implementPatch()
447 psec = make<Patch657417Section>(isec, sr.off, sr.instr, destIsARM); in implementPatch()
455 Relocation{sr.rel->expr, patchRelType, 0, patchRelAddend, sr.rel->sym}); in implementPatch()
457 sr.rel->expr = R_PC; in implementPatch()
[all …]
/freebsd/sys/contrib/device-tree/Bindings/phy/
H A Dbrcm,sr-pcie-phy.txt4 - compatible: must be "brcm,sr-pcie-phy"
6 - brcm,sr-cdru: phandle to the CDRU syscon node
7 - brcm,sr-mhb: phandle to the MHB syscon node
17 compatible = "brcm,sr-mhb", "syscon";
22 compatible = "brcm,sr-cdru", "syscon";
27 compatible = "brcm,sr-pcie-phy";
29 brcm,sr-cdru = <&cdru>;
30 brcm,sr-mhb = <&mhb>;
H A Dbrcm,stingray-usb-phy.txt5 - "brcm,sr-usb-combo-phy" is combo PHY has two PHYs, one SS and one HS.
6 - "brcm,sr-usb-hs-phy" is a single HS PHY.
9 - Must be 1 for brcm,sr-usb-combo-phy as it expects one argument to indicate
11 - Must be 0 for brcm,sr-usb-hs-phy.
17 compatible = "brcm,sr-usb-combo-phy";
23 compatible = "brcm,sr-usb-combo-phy";
29 compatible = "brcm,sr-usb-hs-phy";
/freebsd/sys/contrib/openzfs/lib/libnvpair/
H A Dlibnvpair.c969 int sr; in nvpair_value_match_regex() local
994 sr = EOF; in nvpair_value_match_regex()
1033 sr = sscanf(value, "%c", &val_arg); in nvpair_value_match_regex()
1034 if ((sr == 1) && (nvpair_value_byte(nvp, &val) == 0) && in nvpair_value_match_regex()
1044 sr = sscanf(value, "%c", &val_arg); in nvpair_value_match_regex()
1045 if ((sr == 1) && in nvpair_value_match_regex()
1056 sr = sscanf(value, "%"SCNi8, &val_arg); in nvpair_value_match_regex()
1057 if ((sr == 1) && in nvpair_value_match_regex()
1067 sr = sscanf(value, "%"SCNi8, &val_arg); in nvpair_value_match_regex()
1068 if ((sr == 1) && in nvpair_value_match_regex()
[all …]
/freebsd/tools/tools/mfi/
H A Dmfi_checkq.c52 union mfi_statrequest sr; in main() local
66 bzero(&sr, sizeof(union mfi_statrequest)); in main()
67 sr.ms_item = queue; in main()
68 retval = ioctl(fd, MFIIO_STATS, &sr); in main()
74 printf("length= %d, max= %d\n",sr.ms_qstat.q_length, sr.ms_qstat.q_max); in main()
/freebsd/tools/tools/aac/
H A Daac_checkq.c55 union aac_statrequest sr; in main() local
69 bzero(&sr, sizeof(union aac_statrequest)); in main()
70 sr.as_item = queue; in main()
71 retval = ioctl(fd, AACIO_STATS, &sr); in main()
77 printf("length= %d, max= %d\n",sr.as_qstat.q_length, sr.as_qstat.q_max); in main()
/freebsd/sys/powerpc/aim/
H A Dtrap_subr32.S44 #define RESTORE_SRS(pmap,sr) mtsr 0,sr; \ argument
45 lwz sr,1*4(pmap); mtsr 1,sr; \
46 lwz sr,2*4(pmap); mtsr 2,sr; \
47 lwz sr,3*4(pmap); mtsr 3,sr; \
48 lwz sr,4*4(pmap); mtsr 4,sr; \
49 lwz sr,5*4(pmap); mtsr 5,sr; \
50 lwz sr,6*4(pmap); mtsr 6,sr; \
51 lwz sr,7*4(pmap); mtsr 7,sr; \
52 lwz sr,8*4(pmap); mtsr 8,sr; \
53 lwz sr,9*4(pmap); mtsr 9,sr; \
[all …]
/freebsd/contrib/arm-optimized-routines/math/aarch64/sve/
H A Dsv_sincospi_common.h51 svfloat64_t sr = svsub_x (pt, x, rx); in sv_sincospi_inline() local
54 svfloat64_t cr = svsubr_x (pg, svabs_x (pg, sr), 0.5); in sv_sincospi_inline()
58 svfloat64_t sr2 = svmul_x (pt, sr, sr); in sv_sincospi_inline()
67 sr = svreinterpret_f64 (sveor_x (pt, svreinterpret_u64 (sr), odd)); in sv_sincospi_inline()
71 pt, sv_lw_pw_horner_9_f64_x (pg, sr2, sr4, &(d->c0), &(d->c1)), sr); in sv_sincospi_inline()
H A Dsv_sincospif_common.h44 svfloat32_t sr = svsub_x (pt, x, rx); in sv_sincospif_inline() local
47 svfloat32_t cr = svsubr_x (pt, svabs_x (pg, sr), 0.5f); in sv_sincospif_inline()
50 svfloat32_t sr2 = svmul_x (pt, sr, sr); in sv_sincospif_inline()
59 sr = svreinterpret_f32 (sveor_x (pt, svreinterpret_u32 (sr), odd)); in sv_sincospif_inline()
78 svfloat32_t sinpix = svmul_x (pt, sp, sr); in sv_sincospif_inline()
/freebsd/contrib/wpa/src/drivers/
H A Ddriver_bsd.c1381 struct ieee80211_scan_req sr; in wpa_driver_bsd_scan() local
1410 os_memset(&sr, 0, sizeof(sr)); in wpa_driver_bsd_scan()
1411 sr.sr_flags = IEEE80211_IOC_SCAN_ACTIVE | IEEE80211_IOC_SCAN_ONCE | in wpa_driver_bsd_scan()
1413 sr.sr_duration = IEEE80211_IOC_SCAN_FOREVER; in wpa_driver_bsd_scan()
1415 sr.sr_nssid = params->num_ssids; in wpa_driver_bsd_scan()
1418 if (sr.sr_nssid > IEEE80211_IOC_SCAN_MAX_SSID) in wpa_driver_bsd_scan()
1419 sr.sr_nssid = IEEE80211_IOC_SCAN_MAX_SSID; in wpa_driver_bsd_scan()
1423 sr.sr_flags |= IEEE80211_IOC_SCAN_CHECK; in wpa_driver_bsd_scan()
1425 for (i = 0; i < sr.sr_nssid; i++) { in wpa_driver_bsd_scan()
1426 sr.sr_ssid[i].len = params->ssids[i].ssid_len; in wpa_driver_bsd_scan()
[all …]
/freebsd/tools/tools/net80211/mlme_assoc/
H A Dmlme_assoc.c119 struct ieee80211req_scan_result *sr; in mlme_assoc_scan_results() local
138 while (len > (ssize_t)sizeof(*sr)) { in mlme_assoc_scan_results()
139 sr = (struct ieee80211req_scan_result *)(void *)p; in mlme_assoc_scan_results()
140 p += sr->isr_len; in mlme_assoc_scan_results()
141 len -= sr->isr_len; in mlme_assoc_scan_results()
143 error = try_mlme_assoc(sd, ifnam, (void *)(sr + 1), sr->isr_ssid_len, in mlme_assoc_scan_results()
144 sr->isr_bssid); in mlme_assoc_scan_results()
/freebsd/sys/arm/freescale/vybrid/
H A Dvf_sai.c152 struct sai_rate *sr; member
305 struct sai_rate *sr; in saichan_setspeed() local
314 sr = NULL; in saichan_setspeed()
319 sr = &rate_map[i]; in saichan_setspeed()
323 if (sr == NULL) { in saichan_setspeed()
325 sr = &rate_map[i]; in saichan_setspeed()
326 threshold = sr->speed + ((rate_map[i + 1].speed != 0) ? in saichan_setspeed()
327 ((rate_map[i + 1].speed - sr->speed) >> 1) : 0); in saichan_setspeed()
333 sc->sr = sr; in saichan_setspeed()
337 return (sr->speed); in saichan_setspeed()
[all …]
/freebsd/sys/net80211/
H A Dieee80211_ioctl.c235 struct ieee80211req_scan_result *sr; member
268 struct ieee80211req_scan_result *sr; in get_scan_result() local
276 sr = req->sr; in get_scan_result()
279 sr->isr_len = len; in get_scan_result()
280 sr->isr_ie_off = sizeof(struct ieee80211req_scan_result); in get_scan_result()
281 sr->isr_ie_len = ielen; in get_scan_result()
282 sr->isr_freq = se->se_chan->ic_freq; in get_scan_result()
283 sr->isr_flags = se->se_chan->ic_flags; in get_scan_result()
284 sr->isr_rssi = se->se_rssi; in get_scan_result()
285 sr->isr_noise = se->se_noise; in get_scan_result()
[all …]
/freebsd/contrib/expat/tests/
H A Druntests.c85 SRunner *sr = srunner_create(s); in main() local
108 srunner_run_all(sr, context, verbosity); in main()
111 srunner_summarize(sr, verbosity); in main()
112 nf = srunner_ntests_failed(sr); in main()
113 srunner_free(sr); in main()
/freebsd/tests/sys/netpfil/pf/
H A Danchor.sh52 atf_check -s exit:0 -o ignore jexec alcatraz pfctl -sr -a '*'
84 jexec alcatraz pfctl -sr -a "*"
118 " jexec alcatraz pfctl -sr -a "*"
155 jexec alcatraz pfctl -sr -a "*"
227 jexec alcatraz pfctl -sr -v
267 jexec alcatraz pfctl -sr -v
272 jexec alcatraz pfctl -sr -v
311 jexec alcatraz pfctl -sr -vv
/freebsd/contrib/arm-optimized-routines/math/aarch64/advsimd/
H A Dv_sincospif_common.h38 float32x4_t sr = vsubq_f32 (x, vrndaq_f32 (x)); in v_sincospif_inline() local
40 float32x4_t cr = vsubq_f32 (v_f32 (0.5f), vabsq_f32 (sr)); in v_sincospif_inline()
43 float32x4_t sr2 = vmulq_f32 (sr, sr); in v_sincospif_inline()
48 float32x4_t ss = vmulq_f32 (v_pw_horner_5_f32 (sr2, sr4, d->poly), sr); in v_sincospif_inline()
H A Dv_sincospi_common.h44 float64x2_t sr = vsubq_f64 (x, vrndaq_f64 (x)); in v_sincospi_inline() local
46 float64x2_t cr = vsubq_f64 (v_f64 (0.5), vabsq_f64 (sr)); in v_sincospi_inline()
49 float64x2_t sr2 = vmulq_f64 (sr, sr); in v_sincospi_inline()
54 float64x2_t ss = vmulq_f64 (v_pw_horner_9_f64 (sr2, sr4, d->poly), sr); in v_sincospi_inline()
/freebsd/sys/arm/freescale/imx/
H A Dimx6_ssi.c185 struct ssi_rate *sr; member
343 struct ssi_rate *sr; in ssichan_setspeed() local
352 sr = NULL; in ssichan_setspeed()
357 sr = &rate_map[i]; in ssichan_setspeed()
361 if (sr == NULL) { in ssichan_setspeed()
363 sr = &rate_map[i]; in ssichan_setspeed()
364 threshold = sr->speed + ((rate_map[i + 1].speed != 0) ? in ssichan_setspeed()
365 ((rate_map[i + 1].speed - sr->speed) >> 1) : 0); in ssichan_setspeed()
371 sc->sr = sr; in ssichan_setspeed()
375 return (sr->speed); in ssichan_setspeed()
[all …]
/freebsd/tests/sys/kern/
H A Dreaper.c295 ssize_t sr; in ATF_TC_BODY() local
342 sr = read(pip[0], &st, sizeof(st)); in ATF_TC_BODY()
343 ATF_REQUIRE_EQ((ssize_t)sizeof(st), sr); in ATF_TC_BODY()
350 sr = read(pip[0], &st, sizeof(st)); in ATF_TC_BODY()
351 ATF_REQUIRE_EQ((ssize_t)sizeof(st), sr); in ATF_TC_BODY()
379 ssize_t sr; in ATF_TC_BODY() local
441 sr = write(pipa[1], &(uint8_t){ 0 }, 1); in ATF_TC_BODY()
442 ATF_REQUIRE_EQ(1, sr); in ATF_TC_BODY()
443 sr = read(pipb[0], &(uint8_t){ 0 }, 1); in ATF_TC_BODY()
444 ATF_REQUIRE_EQ(1, sr); in ATF_TC_BODY()
[all …]

123456789