bin/csh/csh.c

167

History *hi;

bin/csh/csh.h

553

extern History *hi;

bin/csh/hist.c

106

if (hi) {

bin/csh/hist.c

110

history(hi, &ev, H_ENTER, h);

bin/csh/hist.c

90

if (hi == NULL || hp == NULL)

bin/csh/hist.c

95

history(hi, &ev, H_ENTER, h);

bin/csh/set.c

580

hi = history_init();

bin/csh/set.c

581

history(hi, &ev, H_SETSIZE, getn(value(STRhistory)));

bin/csh/set.c

583

el_set(el, EL_HIST, history, hi);

bin/csh/set.c

587

if (hi)

bin/csh/set.c

588

history_end(hi);

bin/csh/set.c

590

hi = NULL;

common/dist/zlib/examples/zran.c

349

int lo = -1, hi = index->have;

common/dist/zlib/examples/zran.c

351

while (hi - lo > 1) {

common/dist/zlib/examples/zran.c

352

int mid = (lo + hi) >> 1;

common/dist/zlib/examples/zran.c

354

hi = mid;

common/lib/libc/arch/sparc64/string/strmacros.h

53

sethi %hi(FPLWP), %l1; \

common/lib/libc/arch/sparc64/string/strmacros.h

72

sethi %hi(_C_LABEL(lwp0)), %l4; /* Yes, use lpw0 */ \

common/lib/libc/arch/sparc64/string/strmacros.h

76

sethi %hi(CURLWP), %l4; /* Use curlwp */ \

common/lib/libc/stdlib/_strtoi.h

129

if (im > hi) {

common/lib/libc/stdlib/_strtoi.h

132

return hi;

common/lib/libc/stdlib/_strtoi.h

146

__TYPE lo, __TYPE hi, int * rstatus)

common/lib/libc/stdlib/_strtoi.h

148

return INT_FUNCNAME(_int_, _FUNCNAME, _l)(nptr, endptr, base, lo, hi,

common/lib/libc/stdlib/_strtoi.h

155

__TYPE lo, __TYPE hi, int * rstatus, locale_t loc)

common/lib/libc/stdlib/_strtoi.h

157

return INT_FUNCNAME(_int_, _FUNCNAME, _l)(nptr, endptr, base, lo, hi,

common/lib/libc/stdlib/_strtoi.h

55

__TYPE lo, __TYPE hi, int * rstatus)

common/lib/libc/stdlib/_strtoi.h

65

__TYPE lo, __TYPE hi, int * rstatus, locale_t loc)

common/lib/libc/stdlib/_strtoi.h

75

_DIAGASSERT(hi >= lo);

common/lib/libc/stdlib/random.c

276

int x1, hi, lo, t;

common/lib/libc/stdlib/random.c

286

hi = x1 / 127773;

common/lib/libc/stdlib/random.c

288

t = 16807 * lo - 2836 * hi;

common/lib/libc/stdlib/random.c

512

long x, hi, lo, t;

common/lib/libc/stdlib/random.c

521

hi = x / 127773;

common/lib/libc/stdlib/random.c

523

t = 16807 * lo - 2836 * hi;

common/lib/libx86emu/x86emu.c

5924

uint32_t hi;

common/lib/libx86emu/x86emu.c

5935

hi = (lo >> 16) + (d >> 16) + (s >> 16);

common/lib/libx86emu/x86emu.c

5937

CONDITIONAL_SET_FLAG(hi & 0x10000, F_CF);

common/lib/libx86emu/x86emu.c

6000

uint32_t hi;

common/lib/libx86emu/x86emu.c

6006

hi = (lo >> 16) + (d >> 16) + (s >> 16);

common/lib/libx86emu/x86emu.c

6008

CONDITIONAL_SET_FLAG(hi & 0x10000, F_CF);

games/cribbage/io.c

327

number(int lo, int hi, const char *prompt)

games/cribbage/io.c

351

if (sum >= lo && sum <= hi)

games/cribbage/io.c

357

sum, lo, hi);

games/cribbage/score.c

296

int k, lo, hi;

games/cribbage/score.c

315

lo = hi = crd.rank;

games/cribbage/score.c

326

if (tbl[i].rank > hi)

games/cribbage/score.c

327

hi = tbl[i].rank;

games/cribbage/score.c

328

for (j = lo; j <= hi; j++)

games/cribbage/score.c

331

if (j > hi)

games/cribbage/score.c

332

k = hi - lo + 1;

include/vis_proto.h

240

vis_faligndata(vis_d64 hi, vis_d64 lo)

include/vis_proto.h

246

: "f"(hi), "f"(lo));

include/vis_proto.h

450

vis_u32 hi = (reg >> 32) & 0xffffffff;

include/vis_proto.h

451

vis_f32 out = *((vis_f32 *)&hi);

include/vis_proto.h

470

vis_u32 hi = (out >> 32) & 0xffffffff;

include/vis_proto.h

473

out = ((vis_u64)hi << 32ULL) | lo;

include/vis_proto.h

482

vis_u32 hi = *((vis_u32 *)&upper);

include/vis_proto.h

485

out = ((vis_u64)hi << 32ULL) | lo;

lib/libbluetooth/sdp.h

480

#define SDP_ATTR_RANGE(lo, hi) \

lib/libbluetooth/sdp.h

481

(uint32_t)(((uint16_t)(lo) << 16) | ((uint16_t)(hi)))

lib/libc/arch/sparc64/SYS.h

57

sethi %hi(_C_LABEL(name)),%g5; \

lib/libc/citrus/modules/citrus_ues.c

182

surrogate_to_ucs(wchar_t hi, wchar_t lo)

lib/libc/citrus/modules/citrus_ues.c

184

_DIAGASSERT(is_hi_surrogate(hi));

lib/libc/citrus/modules/citrus_ues.c

187

hi -= 0xD800;

lib/libc/citrus/modules/citrus_ues.c

189

return (hi << 10 | lo) + 0x10000;

lib/libc/citrus/modules/citrus_ues.c

193

ucs_to_surrogate(wchar_t wc, wchar_t * __restrict hi, wchar_t * __restrict lo)

lib/libc/citrus/modules/citrus_ues.c

195

_DIAGASSERT(hi != NULL);

lib/libc/citrus/modules/citrus_ues.c

200

*hi = (wc >> 10) + 0xD800;

lib/libc/citrus/modules/citrus_ues.c

218

wchar_t hi, wc;

lib/libc/citrus/modules/citrus_ues.c

233

hi = (wchar_t)0;

lib/libc/citrus/modules/citrus_ues.c

288

if (hi != (wchar_t)0)

lib/libc/citrus/modules/citrus_ues.c

292

hi = wc;

lib/libc/citrus/modules/citrus_ues.c

310

wc = surrogate_to_ucs(hi, wc);

lib/libc/citrus/modules/citrus_ues.c

333

wchar_t hi, lo;

lib/libc/citrus/modules/citrus_ues.c

349

ucs_to_surrogate(wc, &hi, &lo);

lib/libc/citrus/modules/citrus_ues.c

350

psenc->chlen += to_str(&psenc->ch[0], hi, UCS2_BIT);

lib/libc/citrus/modules/citrus_utf7.c

284

uint16_t hi, lo;

lib/libc/citrus/modules/citrus_utf7.c

300

hi = (psenc->cache >> 2) & UTF16_MAX;

lib/libc/citrus/modules/citrus_utf7.c

301

if (hi < HISRG_MIN || hi > HISRG_MAX)

lib/libc/citrus/modules/citrus_utf7.c

305

err = _citrus_UTF7_mbtoutf16(ei, &hi, &s0, n, psenc, &nr);

lib/libc/citrus/modules/citrus_utf7.c

314

if (hi < HISRG_MIN || hi > HISRG_MAX) {

lib/libc/citrus/modules/citrus_utf7.c

315

u32 = (uint32_t)hi;

lib/libc/citrus/modules/citrus_utf7.c

327

hi -= HISRG_MIN;

lib/libc/citrus/modules/citrus_utf7.c

329

u32 = (hi << 10 | lo) + SRG_BASE;

lib/libc/time/localtime.c

2283

register int hi = sp->timecnt;

lib/libc/time/localtime.c

2285

while (lo < hi) {

lib/libc/time/localtime.c

2286

register int mid = (lo + hi) / 2;

lib/libc/time/localtime.c

2289

hi = mid;

lib/libc/time/localtime.c

2745

register time_t hi;

lib/libc/time/localtime.c

2852

hi = TIME_T_MAX;

lib/libc/time/localtime.c

2857

t = lo / 2 + hi / 2;

lib/libc/time/localtime.c

2860

else if (t > hi)

lib/libc/time/localtime.c

2861

t = hi;

lib/libc/time/localtime.c

2876

} else if (t == hi) {

lib/libc/time/localtime.c

2880

--hi;

lib/libc/time/localtime.c

2883

if (ilo != lo && lo - 1 == hi && yourtm.tm_isdst < 0 &&

lib/libc/time/localtime.c

2902

if (lo > hi)

lib/libc/time/localtime.c

2905

hi = t;

lib/libc/time/zdump.c

460

intmax_t hi;

lib/libc/time/zdump.c

467

hi = lo;

lib/libc/time/zdump.c

468

cuthiyear = hi;

lib/libc/time/zdump.c

470

&& (hi = strtoimax(loend + 1, &hiend, 10),

lib/libc/time/zdump.c

473

cuthiyear = hi;

lib/libc/time/zdump.c

487

hi = lo;

lib/libc/time/zdump.c

488

if (hi < cuthitime) {

lib/libc/time/zdump.c

489

if (hi < absolute_min_time + 1)

lib/libc/time/zdump.c

490

hi = absolute_min_time + 1;

lib/libc/time/zdump.c

491

cuthitime = hi;

lib/libc/time/zdump.c

494

&& (hi = strtoimax(loend + 1, &hiend, 10),

lib/libc/time/zdump.c

501

if (hi < cuthitime) {

lib/libc/time/zdump.c

502

if (hi < absolute_min_time + 1)

lib/libc/time/zdump.c

503

hi = absolute_min_time + 1;

lib/libc/time/zdump.c

504

cuthitime = hi;

lib/libc/time/zdump.c

828

showextrema(timezone_t tz, char *zone, time_t lo, struct tm *lotmp, time_t hi)

lib/libc/time/zdump.c

831

time_t t, boundary = hunt(tz, lo, hi, true);

lib/libc/time/zdump.c

833

hi = (SECSPERDAY < hi - boundary

lib/libc/time/zdump.c

835

: hi + (hi < TIME_T_MAX));

lib/libc/time/zdump.c

851

for (t = lo + 1; t < hi; t++) {

lib/libc/time/zic.c

1194

intmax_t lo = min_time, hi = max_time;

lib/libc/time/zic.c

1205

hi = strtoimax(lo_end + 2, &hi_end, 10);

lib/libc/time/zic.c

1206

if (hi_end == lo_end + 2 || hi == INTMAX_MIN)

lib/libc/time/zic.c

1208

hi -= ! (hi == INTMAX_MAX && errno == ERANGE);

lib/libc/time/zic.c

1210

if (*hi_end || hi < lo || max_time < lo || hi < min_time)

lib/libc/time/zic.c

1213

hi_time = min(hi, max_time);

lib/libc/time/zic.c

2654

limitrange(struct timerange r, zic_t lo, zic_t hi,

lib/libc/time/zic.c

2682

if (hi < max_time) {

lib/libc/time/zic.c

2683

while (0 < r.count && hi + 1 < ats[r.base + r.count - 1])

lib/libc/time/zic.c

2685

while (0 < r.leapcount && hi + 1 < leap[r.leapbase + r.leapcount - 1].trans)

lib/libc/time/zic.c

2690

r.leapexpiry = 0 <= leapexpires && leapexpires - 1 <= hi;

lib/libexecinfo/symtab.c

191

size_t hi = ns;

lib/libexecinfo/symtab.c

207

hi = mid;

lib/libexecinfo/symtab.c

210

if (hi - lo == 1) {

lib/libexecinfo/symtab.c

214

mid = (hi + lo) / 2;

lib/libm/ld128/b_expl.c

104

return (ldexpl(1 + (hi - (lo - c)), k));

lib/libm/ld128/b_expl.c

78

long double hi, lo, z;

lib/libm/ld128/b_expl.c

94

hi = x - k * ln2hi; /* Exact. */

lib/libm/ld128/b_expl.c

96

x = hi - lo;

lib/libm/ld128/k_cospil.h

34

long double hi, lo;

lib/libm/ld128/k_cospil.h

36

hi = (double)x;

lib/libm/ld128/k_cospil.h

37

lo = x - hi;

lib/libm/ld128/k_cospil.h

38

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld128/k_cospil.h

39

hi *= pi_hi;

lib/libm/ld128/k_cospil.h

40

_2sumF(hi, lo);

lib/libm/ld128/k_cospil.h

41

return (__kernel_cosl(hi, lo));

lib/libm/ld128/k_expl.h

258

t = tbl[n2].lo + tbl[n2].hi;

lib/libm/ld128/k_expl.h

259

*hip = tbl[n2].hi;

lib/libm/ld128/k_expl.h

285

long double hi, lo, twopkm2;

lib/libm/ld128/k_expl.h

289

__k_expl(x, &hi, &lo, &k);

lib/libm/ld128/k_expl.h

291

return (lo + hi) * 2 * twopkm2;

lib/libm/ld128/k_expl.h

301

long double c, exp_x, hi, lo, s;

lib/libm/ld128/k_expl.h

307

__k_expl(x, &hi, &lo, &k);

lib/libm/ld128/k_expl.h

309

exp_x = (lo + hi) * 0x1p16382L;

lib/libm/ld128/k_expl.h

99

long double hi;

lib/libm/ld128/k_sinpil.h

34

long double hi, lo;

lib/libm/ld128/k_sinpil.h

36

hi = (double)x;

lib/libm/ld128/k_sinpil.h

37

lo = x - hi;

lib/libm/ld128/k_sinpil.h

38

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld128/k_sinpil.h

39

hi *= pi_hi;

lib/libm/ld128/k_sinpil.h

40

_2sumF(hi, lo);

lib/libm/ld128/k_sinpil.h

41

return (__kernel_sinl(hi, lo, 1));

lib/libm/ld128/s_expl.c

288

t = tbl[n2].lo + tbl[n2].hi;

lib/libm/ld128/s_expl.c

291

t = SUM2P(tbl[n2].hi - 1, tbl[n2].lo * (r1 + 1) + t * q +

lib/libm/ld128/s_expl.c

292

tbl[n2].hi * r1);

lib/libm/ld128/s_expl.c

296

t = SUM2P(tbl[n2].hi - 2, tbl[n2].lo * (r1 + 1) + t * q +

lib/libm/ld128/s_expl.c

297

tbl[n2].hi * r1);

lib/libm/ld128/s_expl.c

301

t = SUM2P(tbl[n2].hi, tbl[n2].lo + t * (q + r1));

lib/libm/ld128/s_expl.c

305

t = SUM2P(tbl[n2].hi, tbl[n2].lo + t * (q + r1));

lib/libm/ld128/s_expl.c

315

t = SUM2P(tbl[n2].hi, tbl[n2].lo - twomk + t * (q + r1));

lib/libm/ld128/s_expl.c

317

t = SUM2P(tbl[n2].hi - twomk, tbl[n2].lo + t * (q + r1));

lib/libm/ld128/s_expl.c

61

long double hi, lo, t, twopk;

lib/libm/ld128/s_expl.c

86

__k_expl(x, &hi, &lo, &k);

lib/libm/ld128/s_expl.c

87

t = SUM2P(hi, lo);

lib/libm/ld128/s_logl.c

423

(rp)->hi = (v); \

lib/libm/ld128/s_logl.c

429

(rp)->hi = (h); \

lib/libm/ld128/s_logl.c

436

long double hi;

lib/libm/ld128/s_logl.c

702

long double hi, lo;

lib/libm/ld128/s_logl.c

707

RETURNI(r.hi);

lib/libm/ld128/s_logl.c

708

_2sumF(r.hi, r.lo);

lib/libm/ld128/s_logl.c

709

hi = (float)r.hi;

lib/libm/ld128/s_logl.c

710

lo = r.lo + (r.hi - hi);

lib/libm/ld128/s_logl.c

711

RETURNI(invln10_hi * hi + (invln10_lo_plus_hi * lo + invln10_lo * hi));

lib/libm/ld128/s_logl.c

718

long double hi, lo;

lib/libm/ld128/s_logl.c

723

RETURNI(r.hi);

lib/libm/ld128/s_logl.c

724

_2sumF(r.hi, r.lo);

lib/libm/ld128/s_logl.c

725

hi = (float)r.hi;

lib/libm/ld128/s_logl.c

726

lo = r.lo + (r.hi - hi);

lib/libm/ld128/s_logl.c

727

RETURNI(invln2_hi * hi + (invln2_lo_plus_hi * lo + invln2_lo * hi));

lib/libm/ld128/s_sinpil.c

49

long double ai, ar, ax, hi, lo, s;

lib/libm/ld128/s_sinpil.c

58

hi = (double)x;

lib/libm/ld128/s_sinpil.c

59

hi *= 0x1p113L;

lib/libm/ld128/s_sinpil.c

60

lo = x * 0x1p113L - hi;

lib/libm/ld128/s_sinpil.c

62

pi_hi * hi;

lib/libm/ld128/s_tanpil.c

44

long double hi, lo, t;

lib/libm/ld128/s_tanpil.c

47

hi = (double)x;

lib/libm/ld128/s_tanpil.c

48

lo = x - hi;

lib/libm/ld128/s_tanpil.c

49

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld128/s_tanpil.c

50

hi *= pi_hi;

lib/libm/ld128/s_tanpil.c

51

_2sumF(hi, lo);

lib/libm/ld128/s_tanpil.c

52

t = __kernel_tanl(hi, lo, -1);

lib/libm/ld128/s_tanpil.c

55

hi = (double)x;

lib/libm/ld128/s_tanpil.c

56

lo = x - hi;

lib/libm/ld128/s_tanpil.c

57

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld128/s_tanpil.c

58

hi *= pi_hi;

lib/libm/ld128/s_tanpil.c

59

_2sumF(hi, lo);

lib/libm/ld128/s_tanpil.c

60

t = - __kernel_tanl(hi, lo, 1);

lib/libm/ld128/s_tanpil.c

72

long double ai, ar, ax, hi, lo, t;

lib/libm/ld128/s_tanpil.c

82

hi = (double)x;

lib/libm/ld128/s_tanpil.c

83

hi *= 0x1p113L;

lib/libm/ld128/s_tanpil.c

84

lo = x * 0x1p113L - hi;

lib/libm/ld128/s_tanpil.c

86

pi_hi * hi;

lib/libm/ld80/b_expl.c

105

return (ldexpl(1 + (hi - (lo - c)), k));

lib/libm/ld80/b_expl.c

79

long double hi, lo, z;

lib/libm/ld80/b_expl.c

95

hi = x - k * ln2hi; /* Exact. */

lib/libm/ld80/b_expl.c

97

x = hi - lo;

lib/libm/ld80/k_cospil.h

34

long double hi, lo;

lib/libm/ld80/k_cospil.h

36

hi = (float)x;

lib/libm/ld80/k_cospil.h

37

lo = x - hi;

lib/libm/ld80/k_cospil.h

38

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld80/k_cospil.h

39

hi *= pi_hi;

lib/libm/ld80/k_cospil.h

40

_2sumF(hi, lo);

lib/libm/ld80/k_cospil.h

41

return (__kernel_cosl(hi, lo));

lib/libm/ld80/k_expl.h

242

t = (long double)tbl[n2].lo + tbl[n2].hi;

lib/libm/ld80/k_expl.h

243

*hip = tbl[n2].hi;

lib/libm/ld80/k_expl.h

262

long double hi, lo, twopkm2;

lib/libm/ld80/k_expl.h

266

__k_expl(x, &hi, &lo, &k);

lib/libm/ld80/k_expl.h

268

return (lo + hi) * 2 * twopkm2;

lib/libm/ld80/k_expl.h

278

long double c, exp_x, hi, lo, s;

lib/libm/ld80/k_expl.h

284

__k_expl(x, &hi, &lo, &k);

lib/libm/ld80/k_expl.h

286

exp_x = (lo + hi) * 0x1p16382L;

lib/libm/ld80/k_expl.h

75

double hi;

lib/libm/ld80/k_sinpil.h

34

long double hi, lo;

lib/libm/ld80/k_sinpil.h

36

hi = (float)x;

lib/libm/ld80/k_sinpil.h

37

lo = x - hi;

lib/libm/ld80/k_sinpil.h

38

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld80/k_sinpil.h

39

hi *= pi_hi;

lib/libm/ld80/k_sinpil.h

40

_2sumF(hi, lo);

lib/libm/ld80/k_sinpil.h

41

return (__kernel_sinl(hi, lo, 1));

lib/libm/ld80/s_expl.c

240

t = (long double)tbl[n2].lo + tbl[n2].hi;

lib/libm/ld80/s_expl.c

243

t = SUM2P(tbl[n2].hi - 1, tbl[n2].lo * (r1 + 1) + t * q +

lib/libm/ld80/s_expl.c

244

tbl[n2].hi * r1);

lib/libm/ld80/s_expl.c

248

t = SUM2P(tbl[n2].hi - 2, tbl[n2].lo * (r1 + 1) + t * q +

lib/libm/ld80/s_expl.c

249

tbl[n2].hi * r1);

lib/libm/ld80/s_expl.c

253

t = SUM2P(tbl[n2].hi, tbl[n2].lo + t * (q + r1));

lib/libm/ld80/s_expl.c

257

t = SUM2P(tbl[n2].hi, tbl[n2].lo + t * (q + r1));

lib/libm/ld80/s_expl.c

267

t = SUM2P(tbl[n2].hi, tbl[n2].lo - twomk + t * (q + r1));

lib/libm/ld80/s_expl.c

269

t = SUM2P(tbl[n2].hi - twomk, tbl[n2].lo + t * (q + r1));

lib/libm/ld80/s_expl.c

72

long double hi, lo, t, twopk;

lib/libm/ld80/s_expl.c

97

__k_expl(x, &hi, &lo, &k);

lib/libm/ld80/s_expl.c

98

t = SUM2P(hi, lo);

lib/libm/ld80/s_logl.c

422

(rp)->hi = (v); \

lib/libm/ld80/s_logl.c

428

(rp)->hi = (h); \

lib/libm/ld80/s_logl.c

435

long double hi;

lib/libm/ld80/s_logl.c

685

long double hi, lo;

lib/libm/ld80/s_logl.c

690

RETURNI(r.hi);

lib/libm/ld80/s_logl.c

691

_2sumF(r.hi, r.lo);

lib/libm/ld80/s_logl.c

692

hi = (float)r.hi;

lib/libm/ld80/s_logl.c

693

lo = r.lo + (r.hi - hi);

lib/libm/ld80/s_logl.c

694

RETURNI(invln10_hi * hi +

lib/libm/ld80/s_logl.c

695

(invln10_lo_plus_hi * lo + invln10_lo * hi));

lib/libm/ld80/s_logl.c

702

long double hi, lo;

lib/libm/ld80/s_logl.c

707

RETURNI(r.hi);

lib/libm/ld80/s_logl.c

708

_2sumF(r.hi, r.lo);

lib/libm/ld80/s_logl.c

709

hi = (float)r.hi;

lib/libm/ld80/s_logl.c

710

lo = r.lo + (r.hi - hi);

lib/libm/ld80/s_logl.c

711

RETURNI(invln2_hi * hi +

lib/libm/ld80/s_logl.c

712

(invln2_lo_plus_hi * lo + invln2_lo * hi));

lib/libm/ld80/s_sinpil.c

50

long double ax, hi, lo, s;

lib/libm/ld80/s_sinpil.c

66

INSERT_LDBL80_WORDS(hi, hx,

lib/libm/ld80/s_sinpil.c

68

hi *= 0x1p63L;

lib/libm/ld80/s_sinpil.c

69

lo = x * 0x1p63L - hi;

lib/libm/ld80/s_sinpil.c

70

s = (pi_lo + pi_hi) * lo + pi_lo * hi +

lib/libm/ld80/s_sinpil.c

71

pi_hi * hi;

lib/libm/ld80/s_tanpil.c

43

long double hi, lo, t;

lib/libm/ld80/s_tanpil.c

46

hi = (float)x;

lib/libm/ld80/s_tanpil.c

47

lo = x - hi;

lib/libm/ld80/s_tanpil.c

48

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld80/s_tanpil.c

49

hi *= pi_hi;

lib/libm/ld80/s_tanpil.c

50

_2sumF(hi, lo);

lib/libm/ld80/s_tanpil.c

51

t = __kernel_tanl(hi, lo, -1);

lib/libm/ld80/s_tanpil.c

54

hi = (float)x;

lib/libm/ld80/s_tanpil.c

55

lo = x - hi;

lib/libm/ld80/s_tanpil.c

56

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/ld80/s_tanpil.c

57

hi *= pi_hi;

lib/libm/ld80/s_tanpil.c

58

_2sumF(hi, lo);

lib/libm/ld80/s_tanpil.c

59

t = - __kernel_tanl(hi, lo, 1);

lib/libm/ld80/s_tanpil.c

71

long double ax, hi, lo, odd, t;

lib/libm/ld80/s_tanpil.c

87

INSERT_LDBL80_WORDS(hi, hx,

lib/libm/ld80/s_tanpil.c

89

hi *= 0x1p63L;

lib/libm/ld80/s_tanpil.c

90

lo = x * 0x1p63L - hi;

lib/libm/ld80/s_tanpil.c

91

t = (pi_lo + pi_hi) * lo + pi_lo * hi +

lib/libm/ld80/s_tanpil.c

92

pi_hi * hi;

lib/libm/noieee_src/n_atan2.c

181

double t,z,signy,signx,hi,lo;

lib/libm/noieee_src/n_atan2.c

234

hi = zero; lo = zero; break;

lib/libm/noieee_src/n_atan2.c

238

hi = athfhi; lo = athflo;

lib/libm/noieee_src/n_atan2.c

245

hi = PIo4; lo = zero;

lib/libm/noieee_src/n_atan2.c

250

hi = at1fhi; lo = at1flo;

lib/libm/noieee_src/n_atan2.c

259

hi = PIo2; lo = zero;

lib/libm/noieee_src/n_atan2.c

280

z = lo - z; z += t; z += hi;

lib/libm/noieee_src/n_exp.c

127

double z,hi,lo,c;

lib/libm/noieee_src/n_exp.c

142

hi=x-k*ln2hi;

lib/libm/noieee_src/n_exp.c

143

x=hi-(lo=k*ln2lo);

lib/libm/noieee_src/n_exp.c

148

return scalb(1.0+(hi-(lo-(x*c)/(2.0-c))),k);

lib/libm/noieee_src/n_exp.c

178

double z,hi,lo;

lib/libm/noieee_src/n_exp.c

193

hi=(x-k*ln2hi); /* Exact. */

lib/libm/noieee_src/n_exp.c

194

x= hi - (lo = k*ln2lo-c);

lib/libm/noieee_src/n_exp.c

200

return scalb(1.+(hi-(lo - c)), k);

lib/libm/noieee_src/n_expm1.c

124

double z,hi,lo,c;

lib/libm/noieee_src/n_expm1.c

136

hi=x-k*ln2hi ;

lib/libm/noieee_src/n_expm1.c

137

z=hi-(lo=k*ln2lo);

lib/libm/noieee_src/n_expm1.c

138

c=(hi-z)-lo;

lib/libm/noieee_src/n_lgamma.c

216

double y, z, t, r = 0, p, q, hi, lo;

lib/libm/noieee_src/n_lgamma.c

253

hi = (double)(float) (p+a1_hi);

lib/libm/noieee_src/n_lgamma.c

254

lo = a1_hi - hi; lo += p; lo += a1_lo;

lib/libm/noieee_src/n_lgamma.c

255

r = lo*y + z*hi; /* q + r = y*(a0+p/q) */

lib/libm/noieee_src/n_lgamma.c

256

q = hi*t;

lib/libm/src/b_exp.c

100

double z,hi,lo;

lib/libm/src/b_exp.c

114

hi=(x-k*ln2hi); /* Exact. */

lib/libm/src/b_exp.c

115

x= hi - (lo = k*ln2lo-c);

lib/libm/src/b_exp.c

121

return scalb(1.+(hi-(lo - c)), k);

lib/libm/src/e_coshl.c

128

k_hexpl(fabsl(x), &hi, &lo);

lib/libm/src/e_coshl.c

129

RETURNI(lo + 0.25/(hi + lo) + hi);

lib/libm/src/e_coshl.c

94

long double hi,lo,x2;

lib/libm/src/e_exp.c

106

double y,hi,lo,c,t;

lib/libm/src/e_exp.c

110

hi = lo = 0;

lib/libm/src/e_exp.c

132

hi = x-ln2HI[xsb]; lo=ln2LO[xsb]; k = 1-xsb-xsb;

lib/libm/src/e_exp.c

136

hi = x - t*ln2HI[0]; /* t*ln2HI is exact here */

lib/libm/src/e_exp.c

139

x = hi - lo;

lib/libm/src/e_exp.c

150

else y = one-((lo-(x*c)/(2.0-c))-hi);

lib/libm/src/e_expf.c

46

float y,hi,lo,c,t;

lib/libm/src/e_expf.c

50

hi = lo = 0;

lib/libm/src/e_expf.c

69

hi = x-ln2HI[xsb]; lo=ln2LO[xsb]; k = 1-xsb-xsb;

lib/libm/src/e_expf.c

73

hi = x - t*ln2HI[0]; /* t*ln2HI is exact here */

lib/libm/src/e_expf.c

76

x = hi - lo;

lib/libm/src/e_expf.c

87

else y = one-((lo-(x*c)/((float)2.0-c))-hi);

lib/libm/src/e_sinhl.c

130

k_hexpl(fabsl(x), &hi, &lo);

lib/libm/src/e_sinhl.c

131

RETURNI(s*(lo - 0.25/(hi + lo) + hi));

lib/libm/src/e_sinhl.c

93

long double hi,lo,x2;

lib/libm/src/k_cospi.h

35

double_t hi, lo;

lib/libm/src/k_cospi.h

37

hi = (float)x;

lib/libm/src/k_cospi.h

38

lo = x - hi;

lib/libm/src/k_cospi.h

39

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/src/k_cospi.h

40

hi *= pi_hi;

lib/libm/src/k_cospi.h

41

_2sumF(hi, lo);

lib/libm/src/k_cospi.h

42

return (__kernel_cos(hi, lo));

lib/libm/src/k_sinpi.h

35

double_t hi, lo;

lib/libm/src/k_sinpi.h

37

hi = (float)x;

lib/libm/src/k_sinpi.h

38

lo = x - hi;

lib/libm/src/k_sinpi.h

39

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/src/k_sinpi.h

40

hi *= pi_hi;

lib/libm/src/k_sinpi.h

41

_2sumF(hi, lo);

lib/libm/src/k_sinpi.h

42

return (__kernel_sin(hi, lo, 1));

lib/libm/src/math_private.h

893

RETURNF((rp)->hi); \

lib/libm/src/math_private.h

894

RETURNF((rp)->hi + (rp)->lo); \

lib/libm/src/math_private.h

898

RETURNI((rp)->hi); \

lib/libm/src/math_private.h

899

RETURNI((rp)->hi + (rp)->lo); \

lib/libm/src/s_cosl.c

101

hi = __kernel_cosl(hi, lo);

lib/libm/src/s_cosl.c

104

hi = - __kernel_sinl(hi, lo, 1);

lib/libm/src/s_cosl.c

107

hi = - __kernel_cosl(hi, lo);

lib/libm/src/s_cosl.c

110

hi = __kernel_sinl(hi, lo, 1);

lib/libm/src/s_cosl.c

114

RETURNI(hi);

lib/libm/src/s_cosl.c

76

long double hi, lo;

lib/libm/src/s_cosl.c

96

hi = y[0];

lib/libm/src/s_expm1.c

134

double y,hi,lo,c,t,e,hxs,hfx,r1;

lib/libm/src/s_expm1.c

168

{hi = x - ln2_hi; lo = ln2_lo; k = 1;}

lib/libm/src/s_expm1.c

170

{hi = x + ln2_hi; lo = -ln2_lo; k = -1;}

lib/libm/src/s_expm1.c

174

hi = x - t*ln2_hi; /* t*ln2_hi is exact here */

lib/libm/src/s_expm1.c

177

x = hi - lo;

lib/libm/src/s_expm1.c

178

c = (hi-x)-lo;

lib/libm/src/s_expm1f.c

42

float y,hi,lo,c,t,e,hxs,hfx,r1;

lib/libm/src/s_expm1f.c

73

{hi = x - ln2_hi; lo = ln2_lo; k = 1;}

lib/libm/src/s_expm1f.c

75

{hi = x + ln2_hi; lo = -ln2_lo; k = -1;}

lib/libm/src/s_expm1f.c

79

hi = x - t*ln2_hi; /* t*ln2_hi is exact here */

lib/libm/src/s_expm1f.c

82

x = hi - lo;

lib/libm/src/s_expm1f.c

83

c = (hi-x)-lo;

lib/libm/src/s_fma.c

100

INSERT_WORD64(sum.hi, hibits);

lib/libm/src/s_fma.c

103

return (sum.hi);

lib/libm/src/s_fma.c

131

EXTRACT_WORD64(hibits, sum.hi);

lib/libm/src/s_fma.c

137

INSERT_WORD64(sum.hi, hibits);

lib/libm/src/s_fma.c

140

return (ldexp(sum.hi, scale));

lib/libm/src/s_fma.c

168

ret.hi = p + q;

lib/libm/src/s_fma.c

169

ret.lo = p - ret.hi + q + la * lb;

lib/libm/src/s_fma.c

264

r = dd_add(xy.hi, zs);

lib/libm/src/s_fma.c

268

if (r.hi == 0.0) {

lib/libm/src/s_fma.c

276

return (xy.hi + vzs + ldexp(xy.lo, spread));

lib/libm/src/s_fma.c

287

return (ldexp(r.hi + adj, spread));

lib/libm/src/s_fma.c

291

if (spread + ilogb(r.hi) > -1023)

lib/libm/src/s_fma.c

292

return (ldexp(r.hi + adj, spread));

lib/libm/src/s_fma.c

294

return (add_and_denormalize(r.hi, adj, spread));

lib/libm/src/s_fma.c

55

double hi;

lib/libm/src/s_fma.c

70

ret.hi = a + b;

lib/libm/src/s_fma.c

71

s = ret.hi - a;

lib/libm/src/s_fma.c

72

ret.lo = (a - (ret.hi - s)) + (b - s);

lib/libm/src/s_fma.c

95

EXTRACT_WORD64(hibits, sum.hi);

lib/libm/src/s_fmal.c

124

u.extu_ld = sum.hi;

lib/libm/src/s_fmal.c

127

sum.hi = nextafterl(sum.hi, INFINITY * sum.lo);

lib/libm/src/s_fmal.c

129

return (ldexp((double)sum.hi, scale));

lib/libm/src/s_fmal.c

161

ret.hi = p + q;

lib/libm/src/s_fmal.c

162

ret.lo = p - ret.hi + q + la * lb;

lib/libm/src/s_fmal.c

249

r = dd_add(xy.hi, zs);

lib/libm/src/s_fmal.c

253

if (r.hi == 0.0) {

lib/libm/src/s_fmal.c

261

return (xy.hi + vzs + ldexpl(xy.lo, spread));

lib/libm/src/s_fmal.c

272

return (ldexpl(r.hi + adj, spread));

lib/libm/src/s_fmal.c

276

if (spread + ilogbl(r.hi) > -16383)

lib/libm/src/s_fmal.c

277

return (ldexpl(r.hi + adj, spread));

lib/libm/src/s_fmal.c

279

return (add_and_denormalize(r.hi, adj, spread));

lib/libm/src/s_fmal.c

52

long double hi;

lib/libm/src/s_fmal.c

67

ret.hi = a + b;

lib/libm/src/s_fmal.c

68

s = ret.hi - a;

lib/libm/src/s_fmal.c

69

ret.lo = (a - (ret.hi - s)) + (b - s);

lib/libm/src/s_fmal.c

92

u.extu_ld = sum.hi;

lib/libm/src/s_fmal.c

94

sum.hi = nextafterl(sum.hi, INFINITY * sum.lo);

lib/libm/src/s_fmal.c

96

return (sum.hi);

lib/libm/src/s_sinl.c

103

RETURNI(hi);

lib/libm/src/s_sinl.c

62

long double hi, lo;

lib/libm/src/s_sinl.c

80

hi = __kernel_sinl(z.extu_ld, 0, 0);

lib/libm/src/s_sinl.c

81

RETURNI(s ? -hi : hi);

lib/libm/src/s_sinl.c

85

hi = y[0];

lib/libm/src/s_sinl.c

90

hi = __kernel_sinl(hi, lo, 1);

lib/libm/src/s_sinl.c

93

hi = __kernel_cosl(hi, lo);

lib/libm/src/s_sinl.c

96

hi = - __kernel_sinl(hi, lo, 1);

lib/libm/src/s_sinl.c

99

hi = - __kernel_cosl(hi, lo);

lib/libm/src/s_sinpi.c

103

INSERT_WORDS(hi, hx, 0);

lib/libm/src/s_sinpi.c

104

hi *= 0x1p53;

lib/libm/src/s_sinpi.c

105

lo = x * 0x1p53 - hi;

lib/libm/src/s_sinpi.c

106

s = (pi_lo + pi_hi) * lo + pi_lo * hi +

lib/libm/src/s_sinpi.c

107

pi_hi * hi;

lib/libm/src/s_sinpi.c

86

double ax, hi, lo, s;

lib/libm/src/s_sinpif.c

56

float ax, hi, lo, s;

lib/libm/src/s_sinpif.c

68

SET_FLOAT_WORD(hi, hx & 0xffff0000);

lib/libm/src/s_sinpif.c

69

hi *= 0x1p23F;

lib/libm/src/s_sinpif.c

70

lo = x * 0x1p23F - hi;

lib/libm/src/s_sinpif.c

71

s = (pi_lo + pi_hi) * lo + pi_lo * hi +

lib/libm/src/s_sinpif.c

72

pi_hi * hi;

lib/libm/src/s_tanhl.c

121

long double hi,lo,s,x2,z;

lib/libm/src/s_tanhl.c

168

k_hexpl(2*fabsl(x), &hi, &lo);

lib/libm/src/s_tanhl.c

170

z = divl(hi, lo, -0.5, hi, lo, 0.5);

lib/libm/src/s_tanhl.c

172

z = one - one/(lo+0.5+hi);

lib/libm/src/s_tanl.c

100

hi = __kernel_tanl(hi, lo, 1);

lib/libm/src/s_tanl.c

104

RETURNI(hi);

lib/libm/src/s_tanl.c

67

long double hi, lo;

lib/libm/src/s_tanl.c

85

hi = __kernel_tanl(z.extu_ld, 0, 0);

lib/libm/src/s_tanl.c

86

RETURNI(s ? -hi : hi);

lib/libm/src/s_tanl.c

90

hi = y[0];

lib/libm/src/s_tanl.c

96

hi = __kernel_tanl(hi, lo, 0);

lib/libm/src/s_tanpi.c

100

hi = (float)x;

lib/libm/src/s_tanpi.c

101

lo = x - hi;

lib/libm/src/s_tanpi.c

102

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/src/s_tanpi.c

103

hi *= pi_hi;

lib/libm/src/s_tanpi.c

104

_2sumF(hi, lo);

lib/libm/src/s_tanpi.c

105

t = - __kernel_tan(hi, lo, -1);

lib/libm/src/s_tanpi.c

117

double ax, hi, lo, odd, t;

lib/libm/src/s_tanpi.c

134

INSERT_WORDS(hi, hx, 0);

lib/libm/src/s_tanpi.c

135

hi *= 0x1p53;

lib/libm/src/s_tanpi.c

136

lo = x * 0x1p53 - hi;

lib/libm/src/s_tanpi.c

137

t = (pi_lo + pi_hi) * lo + pi_lo * hi +

lib/libm/src/s_tanpi.c

138

pi_hi * hi;

lib/libm/src/s_tanpi.c

89

double_t hi, lo, t;

lib/libm/src/s_tanpi.c

92

hi = (float)x;

lib/libm/src/s_tanpi.c

93

lo = x - hi;

lib/libm/src/s_tanpi.c

94

lo = lo * (pi_lo + pi_hi) + hi * pi_lo;

lib/libm/src/s_tanpi.c

95

hi *= pi_hi;

lib/libm/src/s_tanpi.c

96

_2sumF(hi, lo);

lib/libm/src/s_tanpi.c

97

t = __kernel_tan(hi, lo, 1);

lib/libm/src/s_tanpif.c

65

float ax, hi, lo, odd, t;

lib/libm/src/s_tanpif.c

77

SET_FLOAT_WORD(hi, hx & 0xffff0000);

lib/libm/src/s_tanpif.c

78

hi *= 0x1p23F;

lib/libm/src/s_tanpif.c

79

lo = x * 0x1p23F - hi;

lib/libm/src/s_tanpif.c

80

t = (pi_lo + pi_hi) * lo + pi_lo * hi +

lib/libm/src/s_tanpif.c

81

pi_hi * hi;

lib/libusbhid/parse.c

119

hid_item_t *hi = s->cur.next->next;

lib/libusbhid/parse.c

121

s->cur.next = hi;

lib/libusbhid/parse.c

159

hid_item_t *hi;

lib/libusbhid/parse.c

372

hi = malloc(sizeof *hi);

lib/libusbhid/parse.c

373

*hi = s->cur;

lib/libusbhid/parse.c

374

c->next = hi;

lib/libusbhid/parse.c

377

hi = c->next;

lib/libusbhid/parse.c

378

if (hi == NULL)

lib/libusbhid/parse.c

380

s->cur = *hi;

lib/libusbhid/parse.c

381

free(hi);

lib/libutil/efun.c

178

estrtoi(const char * nptr, int base, intmax_t lo, intmax_t hi)

lib/libutil/efun.c

181

intmax_t rv = strtoi(nptr, NULL, base, lo, hi, &e);

lib/libutil/efun.c

186

nptr, base, lo, hi);

lib/libutil/efun.c

192

estrtou(const char * nptr, int base, uintmax_t lo, uintmax_t hi)

lib/libutil/efun.c

195

uintmax_t rv = strtou(nptr, NULL, base, lo, hi, &e);

lib/libutil/efun.c

200

nptr, base, lo, hi);

lib/libutil/strpct.c

113

unsigned hi;

lib/libutil/strpct.c

120

x.hi += y.hi;

lib/libutil/strpct.c

122

x.hi++;

lib/libutil/strpct.c

131

x.hi--;

lib/libutil/strpct.c

148

return x.hi > 0 || x.lo >= y;

libexec/ld.elf_so/arch/powerpc/ppc_reloc.c

282

uint16_t tmp16 = hi(tmp);

sbin/newfs_msdos/newfs_msdos.c

204

argtou(const char *arg, u_int lo, u_int hi, const char *msg)

sbin/newfs_msdos/newfs_msdos.c

210

if (x < lo || x > hi)

sbin/routed/main.c

824

u_long hi) /* and before this */

sbin/routed/main.c

826

tp->tv_sec = (time_t)(hi == lo

sbin/routed/main.c

828

: (lo + arc4random() % ((hi - lo))));

sys/arch/aarch64/aarch64/aarch64_tlb.c

79

tlb_invalidate_asids(tlb_asid_t lo, tlb_asid_t hi)

sys/arch/aarch64/aarch64/aarch64_tlb.c

81

for (; lo <= hi; lo++) {

sys/arch/aarch64/aarch64/trap.c

596

#define THUMB_32BIT(hi) (((hi) & 0xe000) == 0xe000 && ((hi) & 0x1800))

sys/arch/aarch64/aarch64/trap.c

611

uint16_t hi, lo;

sys/arch/aarch64/aarch64/trap.c

613

if (ufetch_16(p, &hi))

sys/arch/aarch64/aarch64/trap.c

615

LE16TOH(hi);

sys/arch/aarch64/aarch64/trap.c

617

if (!THUMB_32BIT(hi)) {

sys/arch/aarch64/aarch64/trap.c

619

*insn = hi;

sys/arch/aarch64/aarch64/trap.c

628

*insn = ((uint32_t)hi << 16) | lo;

sys/arch/amiga/dev/clock.c

250

u_char hi, hi2, lo;

sys/arch/amiga/dev/clock.c

255

hi = draco_ioct->io_timerhi;

sys/arch/amiga/dev/clock.c

257

interval = ((hi<<8) | lo);

sys/arch/amiga/dev/clock.c

266

hi = clockcia->tahi;

sys/arch/amiga/dev/clock.c

269

if (hi != hi2) {

sys/arch/amiga/dev/clock.c

271

hi = hi2;

sys/arch/amiga/dev/clock.c

274

interval = (amiga_clk_interval - 1) - ((hi<<8) | lo);

sys/arch/amiga/dev/grf_cv.c

1817

int hi,lo;

sys/arch/amiga/dev/grf_cv.c

1820

hi = RCrt(ba, CRT_ID_HWGC_ORIGIN_Y_HI);

sys/arch/amiga/dev/grf_cv.c

1823

pos->y = (hi << 8) + lo;

sys/arch/amiga/dev/grf_cv.c

1824

hi = RCrt(ba, CRT_ID_HWGC_ORIGIN_X_HI);

sys/arch/amiga/dev/grf_cv.c

1826

pos->x = (hi << 8) + lo;

sys/arch/amiga/dev/grf_cv3d.c

1680

int hi,lo;

sys/arch/amiga/dev/grf_cv3d.c

1683

hi = RCrt(ba, CRT_ID_HWGC_ORIGIN_Y_HI);

sys/arch/amiga/dev/grf_cv3d.c

1686

pos->y = (hi << 8) + lo;

sys/arch/amiga/dev/grf_cv3d.c

1687

hi = RCrt(ba, CRT_ID_HWGC_ORIGIN_X_HI);

sys/arch/amiga/dev/grf_cv3d.c

1689

pos->x = (hi << 8) + lo;

sys/arch/arm/amlogic/meson_pwm.c

127

u_int period, duty, clk_div, hi, lo;

sys/arch/arm/amlogic/meson_pwm.c

137

hi = __SHIFTOUT(val, MESON_PWM_DUTYCYCLE_HIGH);

sys/arch/arm/amlogic/meson_pwm.c

144

hi = __SHIFTOUT(val, MESON_PWM_DUTYCYCLE_HIGH);

sys/arch/arm/amlogic/meson_pwm.c

154

duty_hz = (uint64_t)hi * clk_div;

sys/arch/arm/amlogic/meson_pwm.c

155

period_hz = (uint64_t)(hi + lo) * clk_div;

sys/arch/arm/amlogic/meson_pwm.c

181

u_int period, duty, clk_div, hi, lo;

sys/arch/arm/amlogic/meson_pwm.c

212

hi = duty_hz;

sys/arch/arm/amlogic/meson_pwm.c

234

__SHIFTIN(hi, MESON_PWM_DUTYCYCLE_HIGH) |

sys/arch/arm/amlogic/meson_pwm.c

254

__SHIFTIN(hi, MESON_PWM_DUTYCYCLE_HIGH) |

sys/arch/arm/amlogic/meson_pwm.c

273

sc->sc_clkfreq / (clk_div + 1), hi, lo, hi * 100 / (hi + lo));

sys/arch/arm/arm32/arm32_tlb.c

101

for (; lo <= hi; lo++) {

sys/arch/arm/arm32/arm32_tlb.c

96

tlb_invalidate_asids(tlb_asid_t lo, tlb_asid_t hi)

sys/arch/arm/arm32/fault.c

930

#define THUMB_32BIT(hi) (((hi) & 0xe000) == 0xe000 && ((hi) & 0x1800))

sys/arch/arm/cortex/a9tmr.c

169

uint32_t lo, hi;

sys/arch/arm/cortex/a9tmr.c

172

hi = a9tmr_global_read(sc, TMR_GBL_CTR_U);

sys/arch/arm/cortex/a9tmr.c

174

} while (hi != a9tmr_global_read(sc, TMR_GBL_CTR_U));

sys/arch/arm/cortex/a9tmr.c

176

return ((uint64_t)hi << 32) | lo;

sys/arch/arm/ep93xx/epclk.c

102

uint32_t hi, lo, scalar = 4222124650UL; \

sys/arch/arm/ep93xx/epclk.c

105

: "=&r"(lo), "=&r"(hi) \

sys/arch/arm/ep93xx/epclk.c

108

(y) = hi; \

sys/arch/arm/include/asm.h

83

#define __BITS(hi,lo) ((~((~0)<<((hi)+1)))&((~0)<<(lo)))

sys/arch/arm/sa11x0/sa1111.c

224

sc->sc_imask.hi = 0;

sys/arch/arm/sa11x0/sa1111.c

230

sc->sc_imask.hi |= (1 << irq);

sys/arch/arm/sa11x0/sa1111.c

237

sc->sc_imask.hi);

sys/arch/arm/sa11x0/sa1111.c

239

sc->sc_imask.hi));

sys/arch/arm/sa11x0/sa1111_var.h

43

uint32_t hi; /* bits 32..54 */

sys/arch/emips/ebus/icap_ebus.c

363

u_int32_t isr, saf = 0, hi, lo;

sys/arch/emips/ebus/icap_ebus.c

390

hi = sc->sc_dp->BufferAddressHi32; /* BUGBUG 64bit */

sys/arch/emips/ebus/icap_ebus.c

392

__USE(hi);

sys/arch/emips/ebus/if_le_ebus.c

629

uint32_t isr, saf, hi, lo, fl;

sys/arch/emips/ebus/if_le_ebus.c

650

hi = sc->sc_regs->BufferAddressHi32; /* BUGBUG 64bit */

sys/arch/emips/ebus/if_le_ebus.c

652

__USE(hi);

sys/arch/emips/stand/common/enic.c

122

unsigned int isr, saf, hi, lo, fl;

sys/arch/emips/stand/common/enic.c

149

hi = regs->BufferAddressHi32; /* BUGBUG 64bit */

sys/arch/emips/stand/common/enic.c

151

__USE(hi);

sys/arch/emips/stand/common/enic.c

165

printf("enic: invalid saf=x%x (lo=%x, hi=%x)\n", saf, lo, hi);

sys/arch/emips/stand/common/start.h

50

uint32_t hi;

sys/arch/evbarm/lubbock/sacc_obio.c

197

intstat.hi =

sys/arch/evbarm/lubbock/sacc_obio.c

199

DPRINTF(("sacc_obio_intr_dispatch: %x %x\n", intstat.lo, intstat.hi));

sys/arch/evbarm/lubbock/sacc_obio.c

217

while ((i = fls32(intstat.hi) - 1) >= 0) {

sys/arch/evbarm/lubbock/sacc_obio.c

224

intstat.hi &= ~(1U<<i);

sys/arch/evbmips/loongson/dev/glx.c

177

uint64_t lo, hi;

sys/arch/evbmips/loongson/dev/glx.c

189

hi = (uint32_t)pci_conf_read(glxbase_pc, glxbase_tag, PCI_MSR_HI32);

sys/arch/evbmips/loongson/dev/glx.c

191

return (hi << 32) | lo;

sys/arch/evbppc/virtex/dev/if_temac.c

292

gmi_write_8(uint32_t addr, uint32_t lo, uint32_t hi)

sys/arch/evbppc/virtex/dev/if_temac.c

294

mtidcr(IDCR_HIF_ARG1, hi);

sys/arch/evbppc/virtex/dev/if_temac.c

299

gmi_read_8(uint32_t addr, uint32_t *lo, uint32_t *hi)

sys/arch/evbppc/virtex/dev/if_temac.c

302

*hi = mfidcr(IDCR_HIF_ARG1);

sys/arch/hpcarm/dev/sacc_hpcarm.c

140

intstat.hi =

sys/arch/hpcarm/dev/sacc_hpcarm.c

142

DPRINTF(("sacc_intr: %x %x\n", intstat.lo, intstat.hi));

sys/arch/hpcarm/dev/sacc_hpcarm.c

162

if (intstat.hi & mask) {

sys/arch/i386/isa/lms.c

222

u_char hi, lo;

sys/arch/i386/isa/lms.c

232

hi = bus_space_read_1(iot, ioh, LMS_DATA);

sys/arch/i386/isa/lms.c

235

dx = ((hi & 0x0f) << 4) | (lo & 0x0f);

sys/arch/i386/isa/lms.c

240

hi = bus_space_read_1(iot, ioh, LMS_DATA);

sys/arch/i386/isa/lms.c

243

dy = ((hi & 0x0f) << 4) | (lo & 0x0f);

sys/arch/i386/isa/lms.c

248

buttons = ((hi & 0x80) ? 0 : 0x1) |

sys/arch/i386/isa/lms.c

249

((hi & 0x40) ? 0 : 0x2) |

sys/arch/i386/isa/lms.c

250

((hi & 0x20) ? 0 : 0x4);

sys/arch/mips/include/asm.h

118

lui t9,%hi(_mcount); \

sys/arch/mips/include/asm.h

134

lui gp,%hi(%neg(%gp_rel(x))); \

sys/arch/mips/include/asm.h

67

#define __BITS(hi,lo) ((~((~0)<<((hi)+1)))&((~0)<<(lo)))

sys/arch/mips/include/asm.h

94

lui t9,%hi(_mcount); \

sys/arch/mips/mips/db_interface.c

535

const uint32_t hi = mipsNN_cp0_watchhi_read(i);

sys/arch/mips/mips/db_interface.c

539

"watchhi", i, FLDWIDTH - 8, "", hi);

sys/arch/or1k/include/asm.h

36

#define __BITS(hi,lo) ((~((~0)<<((hi)+1)))&((~0)<<(lo)))

sys/arch/playstation2/include/bus.h

253

u_int32_t lo, hi; \

sys/arch/playstation2/include/bus.h

264

: "=r"(lo), "=r"(hi) : "r"(a) : "$8"); \

sys/arch/playstation2/include/bus.h

265

((u_int64_t)hi << 32) | lo; \

sys/arch/powerpc/fpu/fpu_explode.c

174

fpu_stof(struct fpn *fp, u_int hi)

sys/arch/powerpc/fpu/fpu_explode.c

180

exp = (hi >> (32 - 1 - SNG_EXPBITS)) & mask(SNG_EXPBITS);

sys/arch/powerpc/fpu/fpu_explode.c

181

frac = hi & mask(SNG_FRACBITS);

sys/arch/powerpc/fpu/fpu_explode.c

192

fpu_dtof(struct fpn *fp, u_int hi, u_int lo)

sys/arch/powerpc/fpu/fpu_explode.c

198

exp = (hi >> (32 - 1 - DBL_EXPBITS)) & mask(DBL_EXPBITS);

sys/arch/powerpc/fpu/fpu_explode.c

199

frac = hi & mask(DBL_FRACBITS - 32);

sys/arch/powerpc/fpu/fpu_explode.c

216

u_int hi, lo;

sys/arch/powerpc/fpu/fpu_explode.c

219

hi = (u_int)(i >> 32);

sys/arch/powerpc/fpu/fpu_explode.c

221

fp->fp_sign = hi >> 31;

sys/arch/powerpc/fpu/fpu_explode.c

235

class = fpu_stof(fp, hi);

sys/arch/powerpc/fpu/fpu_explode.c

239

class = fpu_dtof(fp, hi, lo);

sys/arch/powerpc/fpu/fpu_implode.c

511

u_int *hi, *lo;

sys/arch/powerpc/fpu/fpu_implode.c

515

hi = (u_int *)p;

sys/arch/powerpc/fpu/fpu_implode.c

516

lo = hi + 1;

sys/arch/powerpc/fpu/fpu_implode.c

531

DPRINTF(FPE_REG, ("fpu_implode: long %x %x\n", *hi, *lo));

sys/arch/powerpc/fpu/fpu_implode.c

536

*hi = 0;

sys/arch/powerpc/fpu/fpu_implode.c

542

*hi = fpu_ftos(fe, fp, &cx);

sys/arch/powerpc/fpu/fpu_implode.c

544

DPRINTF(FPE_REG, ("fpu_implode: single %x\n", *hi));

sys/arch/powerpc/fpu/fpu_implode.c

549

DPRINTF(FPE_REG, ("fpu_implode: double %x %x\n", *hi, *lo));

sys/arch/powerpc/ibm4xx/pmap.c

1254

register_t msr, pid, hi;

sys/arch/powerpc/ibm4xx/pmap.c

1269

: [msr] "=&r" (msr), [pid] "=&r" (pid), [hi] "=&r" (hi)

sys/arch/powerpc/ibm4xx/pmap.c

1433

u_long hi, lo, i;

sys/arch/powerpc/ibm4xx/pmap.c

1448

hi = (va & TLB_EPN_MASK) | (sz << TLB_SIZE_SHFT) | TLB_VALID;

sys/arch/powerpc/ibm4xx/pmap.c

1503

: [ctx] "r" (ctx), [i] "r" (i), [lo] "r" (lo), [hi] "r" (hi));

sys/arch/powerpc/ibm4xx/pmap.c

1610

u_int lo, hi, sz;

sys/arch/powerpc/ibm4xx/pmap.c

1618

: [lo] "=&r" (lo), [hi] "=&r" (hi)

sys/arch/powerpc/ibm4xx/pmap.c

1621

KASSERT(hi & TLB_VALID);

sys/arch/powerpc/ibm4xx/pmap.c

1628

sz = tlbsize[(hi & TLB_SIZE_MASK) >> TLB_SIZE_SHFT];

sys/arch/powerpc/ibm4xx/pmap.c

1632

va = (hi & TLB_EPN_MASK) + (base & (sz - 1)); /* sz = 2^n */

sys/arch/powerpc/ibm4xx/pmap.c

1801

u_int lo, hi;

sys/arch/powerpc/ibm4xx/pmap.c

1819

hi = va | TLB_VALID | szmask;

sys/arch/powerpc/ibm4xx/pmap.c

1829

: : [i] "r" (tlb_nreserved), [lo] "r" (lo), [hi] "r" (hi));

sys/arch/powerpc/include/spr.h

44

register_t hi, l;

sys/arch/powerpc/include/spr.h

48

: "=r"(l), "=r"(hi) : "K"(reg));

sys/arch/powerpc/include/spr.h

49

ret = ((uint64_t)hi << 32) | l;

sys/arch/powerpc/include/spr.h

56

volatile register_t hi, l; \

sys/arch/powerpc/include/spr.h

59

hi = (val >> 32); \

sys/arch/powerpc/include/spr.h

71

: : "K"(reg), "r"(l), "r"(hi)); \

sys/arch/riscv/fdt/clint_fdt.c

91

uint32_t hi, lo;

sys/arch/riscv/fdt/clint_fdt.c

93

hi = CLINT_READ(sc, CLINT_MTIME_HI);

sys/arch/riscv/fdt/clint_fdt.c

96

} while (hi != CLINT_READ(sc, CLINT_MTIME_HI));

sys/arch/riscv/fdt/clint_fdt.c

98

__SHIFTIN(hi, __BITS(63, 32)) |

sys/arch/riscv/riscv/riscv_tlb.c

100

for (asid = lo; asid <= hi; asid++) {

sys/arch/riscv/riscv/riscv_tlb.c

76

tlb_invalidate_asids(tlb_asid_t lo, tlb_asid_t hi)

sys/arch/riscv/riscv/riscv_tlb.c

79

for (asid = lo; asid <= hi; asid++) {

sys/arch/sandpoint/stand/altboot/vge.c

326

txd->tf[0].hi = htole32(len << 16);

sys/arch/sandpoint/stand/altboot/vge.c

64

uint32_t hi;

sys/arch/sandpoint/stand/altboot/wm.c

60

uint32_t hi; /* 63:32 */

sys/arch/sandpoint/stand/altboot/wm.c

66

uint32_t hi; /* 63:32 */

sys/arch/sgimips/dev/int.c

608

u_char lo, hi;

sys/arch/sgimips/dev/int.c

617

hi = bus_space_read_1(iot, ioh, INT1_TIMER_1);

sys/arch/sgimips/dev/int.c

624

hi = bus_space_read_1(iot, ioh, INT2_TIMER_1);

sys/arch/sgimips/dev/int.c

631

count = 0xffff - ((hi << 8) | lo);

sys/arch/shark/isa/clock.c

232

unsigned hi; /* high 32 bits */

sys/arch/shark/isa/clock.c

278

timer0count.hi = 0;

sys/arch/shark/isa/clock.c

280

timer0_at_last_clockintr.hi = 0;

sys/arch/shark/isa/clock.c

330

timer0count.hi++;

sys/arch/shark/isa/clock.c

386

u_char lo, hi;

sys/arch/shark/isa/clock.c

394

hi = inb(IO_TIMER1 + TIMER_CNTR0);

sys/arch/shark/isa/clock.c

396

return ((hi << 8) | lo);

sys/arch/shark/ofw/ofw.c

596

paddr_t hi, start;

sys/arch/shark/ofw/ofw.c

610

hi = of_decode_int((unsigned char *)

sys/arch/shark/ofw/ofw.c

615

if (hi & 1) { /* then I/O space */

sys/arch/shark/ofw/ofw.c

633

paddr_t hi, start;

sys/arch/shark/ofw/ofw.c

660

hi = of_decode_int((unsigned char *)

sys/arch/shark/ofw/ofw.c

665

if (hi & 1) { /* then I/O space */

sys/arch/sparc/dev/ebus.c

356

if (ea->ea_reg[n].hi < PCI_MAPREG_START) {

sys/arch/sparc/dev/ebus.c

357

ea->ea_reg[n].hi = PCI_MAPREG_START

sys/arch/sparc/dev/ebus.c

358

+ ea->ea_reg[n].hi * sizeof(pcireg_t);

sys/arch/sparc/dev/ebus.c

412

ea->ea_reg[i].hi, ea->ea_reg[i].lo);

sys/arch/sparc/include/asm.h

124

.text; save %sp,-CC64FSZ,%sp; sethi %hi(1b),%o0; call _mcount; \

sys/arch/sparc/include/asm.h

129

.text; save %sp,-96,%sp; sethi %hi(1b),%o0; call _mcount; \

sys/arch/sparc/include/asm.h

136

.text; save %sp,-CC64FSZ,%sp; sethi %hi(1b),%o0; call mcount; \

sys/arch/sparc/include/asm.h

141

.text; save %sp,-96,%sp; sethi %hi(1b),%o0; call mcount; \

sys/arch/sparc/include/asm.h

225

sethi %hi(what), r0; \

sys/arch/sparc/include/asm.h

232

sethi %hi(what), r2; \

sys/arch/sparc/include/asm.h

80

sethi %hi(_GLOBAL_OFFSET_TABLE_-4),dest; \

sys/arch/sparc/include/asm.h

89

sethi %hi(_C_LABEL(_GLOBAL_OFFSET_TABLE_)-(3b-.)),dest; \

sys/arch/sparc/include/openfirm.h

54

#define CELL2HDQ(hi,lo) (lo)

sys/arch/sparc/sparc/promlib.c

845

uint32_t hi, lo;

sys/arch/sparc/sparc/promlib.c

848

hi = (offset >> 32) & ((uint32_t)-1);

sys/arch/sparc/sparc/promlib.c

849

(*obpvec->pv_v2devops.v2_seek)(handle, hi, lo);

sys/arch/sparc/stand/bootxx/promlib.c

91

uint32_t hi, lo;

sys/arch/sparc/stand/bootxx/promlib.c

94

hi = (offset >> 32) & ((uint32_t)-1);

sys/arch/sparc/stand/bootxx/promlib.c

95

(*obpvec->pv_v2devops.v2_seek)(handle, hi, lo);

sys/arch/sparc/stand/ofwboot/loadfile_machdep.c

346

hi(pa), lo(pa)));

sys/arch/sparc/stand/ofwboot/loadfile_machdep.c

364

dtlb_enter(va, hi(data), lo(data));

sys/arch/sparc/stand/ofwboot/loadfile_machdep.c

422

hi(pa), lo(pa)));

sys/arch/sparc/stand/ofwboot/loadfile_machdep.c

656

dtlb_replace(dtlb_store[i].te_va, hi(data), lo(data));

sys/arch/sparc/stand/ofwboot/loadfile_machdep.c

659

itlb_enter(dtlb_store[i].te_va, hi(data), lo(data));

sys/arch/sparc64/dev/ebus.c

314

uint32_t hi, lo, intr;

sys/arch/sparc64/dev/ebus.c

336

hi = ea->ea_reg[i].hi & sc->sc_intmapmask.hi;

sys/arch/sparc64/dev/ebus.c

341

ea->ea_reg[i].hi, ea->ea_reg[i].lo, hi, lo));

sys/arch/sparc64/dev/ebus.c

345

sc->sc_intmap[k].hi, sc->sc_intmap[k].lo,

sys/arch/sparc64/dev/ebus.c

347

if (hi == sc->sc_intmap[k].hi &&

sys/arch/sparc64/dev/ebus_mainbus.c

209

bus_addr_t hi, lo;

sys/arch/sparc64/dev/ebus_mainbus.c

226

hi = offset >> 32UL;

sys/arch/sparc64/dev/ebus_mainbus.c

230

DPRINTF(EDB_BUSMAP, (" (hi %08x lo %08x)", (u_int)hi, (u_int)lo));

sys/arch/sparc64/dev/ebus_mainbus.c

234

if (hi != range[i].child_hi)

sys/arch/sparc64/include/locore.h

159

sethi %hi(0b), %o0; \

sys/arch/sparc64/include/locore.h

77

sethi %hi(what), %o0; \

sys/arch/x68k/dev/ite_tv.c

311

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

315

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

318

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

320

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x68k/dev/ite_tv.c

339

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

343

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

346

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

348

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x68k/dev/ite_tv.c

367

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

372

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

375

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

377

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x68k/dev/ite_tv.c

416

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

420

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

423

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

425

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x68k/dev/ite_tv.c

452

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

457

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

460

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

462

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x68k/dev/ite_tv.c

485

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

489

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

492

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

494

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x68k/dev/ite_tv.c

521

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

526

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

529

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

531

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x68k/dev/ite_tv.c

568

short fh, hi, lo;

sys/arch/x68k/dev/ite_tv.c

573

hi = ip->save_char & 0x7f;

sys/arch/x68k/dev/ite_tv.c

576

if (hi >= 0x21 && hi <= 0x7e && lo >= 0x21 && lo <= 0x7e) {

sys/arch/x68k/dev/ite_tv.c

578

kf = (volatile uint16_t *)tv_kfont[hi];

sys/arch/x86/x86/cpu_rng.c

126

uint32_t lo, hi;

sys/arch/x86/x86/cpu_rng.c

131

__asm __volatile("rdrand %0; setc %1" : "=r"(hi), "=qm"(rndsts));

sys/arch/x86/x86/cpu_rng.c

133

*out = (uint64_t)lo | ((uint64_t)hi << 32);

sys/arch/x86/x86/cpu_rng.c

135

explicit_memset(&hi, 0, sizeof(hi));

sys/arch/x86/x86/cpu_rng.c

160

uint32_t lo, hi;

sys/arch/x86/x86/cpu_rng.c

165

__asm __volatile("rdseed %0; setc %1" : "=r"(hi), "=qm"(rndsts));

sys/arch/x86/x86/cpu_rng.c

169

*out = (uint64_t)lo | ((uint64_t)hi << 32);

sys/arch/x86/x86/cpu_rng.c

171

explicit_memset(&hi, 0, sizeof(hi));

sys/arch/x86/x86/lapic.c

178

x2apic_write_icr(uint32_t hi, uint32_t lo)

sys/arch/x86/x86/lapic.c

180

x2apic_writereg64(LAPIC_ICRLO, ((uint64_t)hi << 32) | lo);

sys/compat/linux/arch/amd64/linux_syscallargs.h

715

syscallarg(unsigned int) hi;

sys/compat/linux/arch/amd64/linux_systrace_args.c

1335

uarg[1] = SCARG(p, hi); /* unsigned int */

sys/compat/linux/arch/i386/linux_syscallargs.h

365

syscallarg(unsigned int) hi;

sys/compat/linux/arch/i386/linux_systrace_args.c

683

uarg[1] = SCARG(p, hi); /* unsigned int */

sys/compat/linux/arch/mips/linux_syscallargs.h

316

syscallarg(unsigned int) hi;

sys/compat/linux/common/linux_file.c

150

linux_hilo_to_off_t(unsigned long hi, unsigned long lo)

sys/compat/linux/common/linux_file.c

159

(void) hi;

sys/compat/linux/common/linux_file.c

162

return (((off_t)hi) << 32) | lo;

sys/compat/linux32/arch/amd64/linux32_systrace_args.c

648

uarg[1] = SCARG(p, hi); /* unsigned int */

sys/compat/linux32/common/linux32_misc.c

386

linux32_hilo_to_off_t(unsigned long hi, unsigned long lo)

sys/compat/linux32/common/linux32_misc.c

388

return (((off_t)hi) << 32) | lo;

sys/crypto/aes/arch/arm/aes_neon.c

215

bytes2nybbles(uint8x16_t *restrict lo, uint8x16_t *restrict hi, uint8x16_t x)

sys/crypto/aes/arch/arm/aes_neon.c

219

*hi = of & vshrq_n_u8(x, 4);

sys/crypto/aes/arch/arm/aes_neon.c

229

uint8x16_t lo, hi;

sys/crypto/aes/arch/arm/aes_neon.c

231

bytes2nybbles(&lo, &hi, x);

sys/crypto/aes/arch/arm/aes_neon.c

232

return vqtbl1q_u8(t[0], lo) ^ vqtbl1q_u8(t[1], hi);

sys/crypto/aes/arch/x86/aes_ssse3.c

161

bytes2nybbles(__m128i *restrict lo, __m128i *restrict hi, __m128i x)

sys/crypto/aes/arch/x86/aes_ssse3.c

165

*hi = _mm_srli_epi32(x & ~of.m, 4);

sys/crypto/aes/arch/x86/aes_ssse3.c

189

__m128i lo, hi;

sys/crypto/aes/arch/x86/aes_ssse3.c

191

bytes2nybbles(&lo, &hi, x);

sys/crypto/aes/arch/x86/aes_ssse3.c

192

return _mm_shuffle_epi8(t[0].m, lo) ^ _mm_shuffle_epi8(t[1].m, hi);

sys/crypto/arch/x86/immintrin.h

106

#define _mm_alignr_epi8(hi,lo,bytes) \

sys/crypto/arch/x86/immintrin.h

107

(__m128i)__builtin_ia32_palignr128((__v2di)(__m128i)(hi), \

sys/crypto/arch/x86/immintrin.h

110

#define _mm_alignr_epi8(hi,lo,bytes) \

sys/crypto/arch/x86/immintrin.h

111

(__m128i)__builtin_ia32_palignr128((__v16qi)(__m128i)(hi), \

sys/crypto/blake2/blake2s.c

252

uint32_t hi = B->h[i];

sys/crypto/blake2/blake2s.c

255

*d++ = hi;

sys/crypto/blake2/blake2s.c

256

hi >>= 8;

sys/crypto/chacha/arch/x86/chacha_sse2.c

156

__m128 hi = (__m128)_mm_unpacklo_epi32(c, d); /* (c[0], d[0], ...) */

sys/crypto/chacha/arch/x86/chacha_sse2.c

159

return (__m128i)_mm_movelh_ps(lo, hi);

sys/crypto/chacha/arch/x86/chacha_sse2.c

166

__m128 hi = (__m128)_mm_unpacklo_epi32(c, d); /* (..., c[1], d[1]) */

sys/crypto/chacha/arch/x86/chacha_sse2.c

169

return (__m128i)_mm_movehl_ps(hi, lo);

sys/crypto/chacha/arch/x86/chacha_sse2.c

176

__m128 hi = (__m128)_mm_unpackhi_epi32(c, d); /* (c[2], d[2], ...) */

sys/crypto/chacha/arch/x86/chacha_sse2.c

179

return (__m128i)_mm_movelh_ps(lo, hi);

sys/crypto/chacha/arch/x86/chacha_sse2.c

186

__m128 hi = (__m128)_mm_unpackhi_epi32(c, d); /* (..., c[3], d[3]) */

sys/crypto/chacha/arch/x86/chacha_sse2.c

189

return (__m128i)_mm_movehl_ps(hi, lo);

sys/dev/acpi/hpacel_acpi.c

411

uint8_t hi, lo;

sys/dev/acpi/hpacel_acpi.c

435

rv[1] = hpacel_reg_read(hdl, reg[1], &hi);

sys/dev/acpi/hpacel_acpi.c

446

hi = (hi & 0x10) ? hi | 0xE0 : hi & ~0xE0;

sys/dev/acpi/hpacel_acpi.c

448

*out = (hi << 8) | lo;

sys/dev/acpi/thinkpad_acpi.c

844

ACPI_INTEGER hi;

sys/dev/acpi/thinkpad_acpi.c

856

rv = acpiec_bus_read(sc->sc_ecdev, 0x85, &hi, 1);

sys/dev/acpi/thinkpad_acpi.c

862

rpm = ((((int)hi) << 8) | ((int)lo));

sys/dev/ebus/ebusreg.h

102

uint32_t hi; /* high phys addr mask */

sys/dev/ebus/ebusreg.h

110

uint32_t hi; /* high phys addr */

sys/dev/ebus/ebusreg.h

74

uint32_t hi; /* high bits of physaddr */

sys/dev/ebus/ebusreg.h

79

#define EBUS_ADDR_FROM_REG(reg) BUS_ADDR((reg)->hi, (reg)->lo)

sys/dev/goldfish/gfrtc.c

136

const uint64_t hi = GOLDFISH_RTC_READ(sc, GOLDFISH_RTC_TIME_HIGH);

sys/dev/goldfish/gfrtc.c

138

return (hi << 32) | lo;

sys/dev/goldfish/gfrtc.c

81

const uint32_t hi = (uint32_t)(nsec >> 32);

sys/dev/goldfish/gfrtc.c

84

GOLDFISH_RTC_WRITE(sc, GOLDFISH_RTC_TIME_HIGH, hi);

sys/dev/hid/hid.c

110

struct hid_item *hi = s->cur.next->next;

sys/dev/hid/hid.c

112

s->cur.next = hi;

sys/dev/hid/hid.c

127

struct hid_item *hi;

sys/dev/hid/hid.c

311

hi = kmem_alloc(sizeof(*hi), KM_SLEEP);

sys/dev/hid/hid.c

312

*hi = *c;

sys/dev/hid/hid.c

313

c->next = hi;

sys/dev/hid/hid.c

316

hi = c->next;

sys/dev/hid/hid.c

317

if (hi == NULL)

sys/dev/hid/hid.c

320

*c = *hi;

sys/dev/hid/hid.c

322

kmem_free(hi, sizeof(*hi));

sys/dev/hid/hid.c

388

int lo, hi;

sys/dev/hid/hid.c

391

lo = hi = -1;

sys/dev/hid/hid.c

408

hi = h.loc.pos + h.loc.size * h.loc.count;

sys/dev/hid/hid.c

409

DPRINTFN(2,("hid_report_size: lo=%d hi=%d\n", lo, hi));

sys/dev/hid/hid.c

413

return (hi - lo + 7) / 8;

sys/dev/hid/hid.c

508

struct hid_item hi;

sys/dev/hid/hid.c

516

while (hid_get_item(hd, &hi)) {

sys/dev/hid/hid.c

519

hi.kind, hi.report_ID, hi.usage, coll_usage));

sys/dev/hid/hid.c

521

if (hi.kind == hid_collection &&

sys/dev/hid/hid.c

522

(hi.collection == HCOLL_APPLICATION ||

sys/dev/hid/hid.c

523

hi.collection == HCOLL_PHYSICAL ||

sys/dev/hid/hid.c

524

hi.collection == HCOLL_LOGICAL))

sys/dev/hid/hid.c

525

coll_usage = hi.usage;

sys/dev/hid/hid.c

527

if ((hi.kind == hid_collection ||

sys/dev/hid/hid.c

528

hi.kind == hid_endcollection) &&

sys/dev/hid/hid.c

530

hi.report_ID == id) {

sys/dev/hid/hid.c

536

if (hi.kind == hid_endcollection)

sys/dev/i2c/axppmic.c

829

uint8_t val, lo, hi;

sys/dev/i2c/axppmic.c

891

axppmic_read(sc->sc_i2c, sc->sc_addr, AXP_BATSENSE_HI_REG, &hi, 0) == 0 &&

sys/dev/i2c/axppmic.c

894

e->value_cur = AXP_ADC_RAW(hi, lo) * c->batsense_step;

sys/dev/i2c/axppmic.c

901

axppmic_read(sc->sc_i2c, sc->sc_addr, AXP_BATTCHG_HI_REG, &hi, 0) == 0 &&

sys/dev/i2c/axppmic.c

904

e->value_cur = AXP_ADC_RAW(hi, lo) * c->charge_step;

sys/dev/i2c/axppmic.c

911

axppmic_read(sc->sc_i2c, sc->sc_addr, AXP_BATTDISCHG_HI_REG, &hi, 0) == 0 &&

sys/dev/i2c/axppmic.c

914

e->value_cur = AXP_ADC_RAW(hi, lo) * c->discharge_step;

sys/dev/i2c/axppmic.c

919

axppmic_read(sc->sc_i2c, sc->sc_addr, AXP_BATT_MAX_CAP_HI_REG, &hi, 0) == 0 &&

sys/dev/i2c/axppmic.c

921

e->state = (hi & AXP_BATT_MAX_CAP_VALID) ? ENVSYS_SVALID : ENVSYS_SINVALID;

sys/dev/i2c/axppmic.c

922

e->value_cur = AXP_COULOMB_RAW(hi, lo) * c->maxcap_step;

sys/dev/i2c/axppmic.c

927

axppmic_read(sc->sc_i2c, sc->sc_addr, AXP_BATT_COULOMB_HI_REG, &hi, 0) == 0 &&

sys/dev/i2c/axppmic.c

929

e->state = (hi & AXP_BATT_COULOMB_VALID) ? ENVSYS_SVALID : ENVSYS_SINVALID;

sys/dev/i2c/axppmic.c

930

e->value_cur = AXP_COULOMB_RAW(hi, lo) * c->coulomb_step;

sys/dev/i2c/tsllux.c

750

uint16_t hi, lo;

sys/dev/i2c/tsllux.c

760

hi = TSL2561_AGC_THI_13MS;

sys/dev/i2c/tsllux.c

765

hi = TSL2561_AGC_THI_101MS;

sys/dev/i2c/tsllux.c

771

hi = TSL2561_AGC_THI_402MS;

sys/dev/i2c/tsllux.c

788

} else if (adc0 > hi &&

sys/dev/ic/advlib.h

80

#define MAKEWORD(lo, hi) ((u_int16_t) (((u_int16_t) (lo)) | \

sys/dev/ic/advlib.h

81

((u_int16_t) (hi) << 8)))

sys/dev/ic/advlib.h

83

#define MAKELONG(lo, hi) ((u_int32_t) (((u_int32_t) (lo)) | \

sys/dev/ic/advlib.h

84

((u_int32_t) (hi) << 16)))

sys/dev/ic/am7930.c

184

uint lo, hi;

sys/dev/ic/am7930.c

188

hi = AM7930_DREAD(sc, AM7930_DREG_DR);

sys/dev/ic/am7930.c

189

return (hi << 8) | lo;

sys/dev/ic/arn5008.c

2504

int i, lo, hi;

sys/dev/ic/arn5008.c

2509

hi = i;

sys/dev/ic/arn5008.c

2510

lo = hi - 1;

sys/dev/ic/arn5008.c

2512

lo = hi;

sys/dev/ic/arn5008.c

2513

else if (hi == nicepts)

sys/dev/ic/arn5008.c

2514

hi = lo;

sys/dev/ic/arn5008.c

2517

pwrPdg[hi], vpdPdg[hi]);

sys/dev/ic/arn5008.c

2637

int i, lo, hi;

sys/dev/ic/arn5008.c

2646

hi = i;

sys/dev/ic/arn5008.c

2647

lo = hi - 1;

sys/dev/ic/arn5008.c

2649

lo = hi;

sys/dev/ic/arn5008.c

2650

else if (hi == nchans || tgt[hi].bChannel == AR_BCHAN_UNUSED)

sys/dev/ic/arn5008.c

2651

hi = lo;

sys/dev/ic/arn5008.c

2657

tgt[hi].bChannel, tgt[hi].tPow2x[i]);

sys/dev/ic/arn5008.c

2669

int i, lo, hi;

sys/dev/ic/arn5008.c

2678

hi = i;

sys/dev/ic/arn5008.c

2679

lo = hi - 1;

sys/dev/ic/arn5008.c

2681

lo = hi;

sys/dev/ic/arn5008.c

2682

else if (hi == nchans || tgt[hi].bChannel == AR_BCHAN_UNUSED)

sys/dev/ic/arn5008.c

2683

hi = lo;

sys/dev/ic/arn5008.c

2689

tgt[hi].bChannel, tgt[hi].tPow2x[i]);

sys/dev/ic/arn5416.c

364

int i, lo, hi, npiers;

sys/dev/ic/arn5416.c

378

athn_get_pier_ival(fbin, pierfreq, npiers, &lo, &hi);

sys/dev/ic/arn5416.c

381

hipier.fbin = pierfreq[hi];

sys/dev/ic/arn9003.c

2772

const uint32_t *hi)

sys/dev/ic/arn9003.c

2797

txsum = (hi[i] & 0x7ff) << 16 | lo[i] >> 16;

sys/dev/ic/arn9003.c

2799

((hi[i] >> 11) & 0x1f);

sys/dev/ic/arn9003.c

2800

rosum = (hi[i + NBINS] & 0x7ff) << 16 | hi[i + NBINS] >> 16;

sys/dev/ic/arn9003.c

3064

uint32_t lo[48], hi[48];

sys/dev/ic/arn9003.c

3077

for (i = 0; i < __arraycount(hi); i++)

sys/dev/ic/arn9003.c

3078

hi[i] = AR_READ(sc, AR_PHY_CHAN_INFO_TAB(0, i));

sys/dev/ic/arn9003.c

3084

if (ar9003_compute_predistortion(sc, lo, hi) != 0)

sys/dev/ic/arn9003.c

3308

int i, delta, lo, hi;

sys/dev/ic/arn9003.c

3310

lo = hi = -1;

sys/dev/ic/arn9003.c

3318

if (delta <= 0 && (hi == -1 || delta > fbin - fbins[hi]))

sys/dev/ic/arn9003.c

3319

hi = i;

sys/dev/ic/arn9003.c

3322

lo = hi;

sys/dev/ic/arn9003.c

3323

else if (hi == -1)

sys/dev/ic/arn9003.c

3324

hi = lo;

sys/dev/ic/arn9003.c

3329

fbins[hi], tgt[hi].tPow2x[i]);

sys/dev/ic/arn9003.c

3340

int i, delta, lo, hi;

sys/dev/ic/arn9003.c

3342

lo = hi = -1;

sys/dev/ic/arn9003.c

3350

if (delta <= 0 && (hi == -1 || delta > fbin - fbins[hi]))

sys/dev/ic/arn9003.c

3351

hi = i;

sys/dev/ic/arn9003.c

3354

lo = hi;

sys/dev/ic/arn9003.c

3355

else if (hi == -1)

sys/dev/ic/arn9003.c

3356

hi = lo;

sys/dev/ic/arn9003.c

3361

fbins[hi], tgt[hi].tPow2x[i]);

sys/dev/ic/arn9280.c

423

int i, lo, hi, npiers;

sys/dev/ic/arn9280.c

439

athn_get_pier_ival(fbin, pierfreq, npiers, &lo, &hi);

sys/dev/ic/arn9280.c

442

pwr = (pierdata[lo].pwrPdg[0][0] + pierdata[hi].pwrPdg[0][0]) / 2;

sys/dev/ic/arn9280.c

446

pcdac = pierdata[hi].pcdac[0][0];

sys/dev/ic/arn9280.c

454

fbin, lo, hi, pwr, pcdac, idx);

sys/dev/ic/arn9285.c

715

int i, lo, hi, npiers;

sys/dev/ic/arn9285.c

723

athn_get_pier_ival(fbin, pierfreq, npiers, &lo, &hi);

sys/dev/ic/arn9285.c

726

hipier.fbin = pierfreq[hi];

sys/dev/ic/arn9287.c

273

int i, lo, hi, npiers;

sys/dev/ic/arn9287.c

282

athn_get_pier_ival(fbin, pierfreq, npiers, &lo, &hi);

sys/dev/ic/arn9287.c

285

hipier.fbin = pierfreq[hi];

sys/dev/ic/arn9287.c

314

int lo, hi, npiers;

sys/dev/ic/arn9287.c

323

athn_get_pier_ival(fbin, pierfreq, npiers, &lo, &hi);

sys/dev/ic/arn9287.c

327

pierfreq[hi], pierdata[hi].pwrPdg[0][0]);

sys/dev/ic/arn9287.c

329

*pwr = (pierdata[lo].pwrPdg[0][0] + pierdata[hi].pwrPdg[0][0]) / 2;

sys/dev/ic/arn9380.c

838

int lo, hi, npiers;

sys/dev/ic/arn9380.c

852

athn_get_pier_ival(fbin, pierfreq, npiers, &lo, &hi);

sys/dev/ic/arn9380.c

856

pierfreq[hi], pierdata[hi].refPower);

sys/dev/ic/arn9380.c

859

pierfreq[hi], pierdata[hi].tempMeas);

sys/dev/ic/athn.c

1059

uint32_t type, lo, hi;

sys/dev/ic/athn.c

1121

hi = LE_READ_2(&addr[4]);

sys/dev/ic/athn.c

1122

lo = lo >> 1 | hi << 31;

sys/dev/ic/athn.c

1123

hi = hi >> 1;

sys/dev/ic/athn.c

1125

lo = hi = 0;

sys/dev/ic/athn.c

1127

AR_WRITE(sc, AR_KEYTABLE_MAC1(entry), hi | AR_KEYTABLE_VALID);

sys/dev/ic/athn.c

1698

int *lo, int *hi)

sys/dev/ic/athn.c

1706

*hi = i;

sys/dev/ic/athn.c

1707

*lo = *hi - 1;

sys/dev/ic/athn.c

1709

*lo = *hi;

sys/dev/ic/athn.c

1710

else if (*hi == npiers || pierfreq[*hi] == AR_BCHAN_UNUSED)

sys/dev/ic/athn.c

1711

*hi = *lo;

sys/dev/ic/athn.c

2721

uint32_t val, lo, hi;

sys/dev/ic/athn.c

2725

lo = hi = 0xffffffff;

sys/dev/ic/athn.c

2728

lo = hi = 0;

sys/dev/ic/athn.c

2734

lo = hi = 0xffffffff;

sys/dev/ic/athn.c

2747

hi |= 1 << (bit - 32);

sys/dev/ic/athn.c

2754

AR_WRITE(sc, AR_MCAST_FIL1, hi);

sys/dev/ic/athnreg.h

1310

#define AR_TSF_TO_TU(hi, lo) ((hi) << 22 | (lo) >> 10)

sys/dev/ic/bwfmreg.h

663

uint32_t hi;

sys/dev/ic/bwi.c

5326

#define LO_ADJUST(hi, lo) { .ctrl_hi = hi, .ctrl_lo = lo }

sys/dev/ic/dwc_gmac.c

403

uint32_t hi, lo;

sys/dev/ic/dwc_gmac.c

405

hi = enaddr[4] | (enaddr[5] << 8);

sys/dev/ic/dwc_gmac.c

408

bus_space_write_4(sc->sc_bst, sc->sc_bsh, AWIN_GMAC_MAC_ADDR0HI, hi);

sys/dev/ic/hd44780_subr.c

618

uint8_t hi;

sys/dev/ic/hd44780_subr.c

624

hi = HD_ROW1_ADDR + sc->sc_vcols;

sys/dev/ic/hd44780_subr.c

626

for (; (addr < hi) && (i < io->len); addr++, i++) {

sys/dev/ic/hd44780_subr.c

635

hi = HD_ROW2_ADDR + sc->sc_vcols;

sys/dev/ic/hd44780_subr.c

640

for (; (addr < hi) && (i < io->len); addr++, i++) {

sys/dev/ic/mpt_mpilib.h

4270

#define SET_HOST_INDEX_0100(t, hi) \

sys/dev/ic/mpt_mpilib.h

4272

(((hi) << TARGET_MODE_REPLY_0100_SHIFT_HOST_INDEX) & \

sys/dev/ic/rt2661.c

2828

int lo, hi, dbm;

sys/dev/ic/rt2661.c

2840

hi = lo + 0x20;

sys/dev/ic/rt2661.c

2852

hi -= 2 * (-74 - dbm);

sys/dev/ic/rt2661.c

2853

if (hi < lo)

sys/dev/ic/rt2661.c

2854

hi = lo;

sys/dev/ic/rt2661.c

2856

if (bbp17 > hi)

sys/dev/ic/rt2661.c

2857

bbp17 = hi;

sys/dev/ic/rt2661.c

2859

bbp17 = uimin(bbp17 + 1, hi);

sys/dev/ic/rt2661.c

2868

bbp17 = hi;

sys/dev/ieee1394/firewire.c

1428

src->businfo.eui64.hi = fc->eui.hi;

sys/dev/ieee1394/firewire.c

1626

fwdev->eui.hi, fwdev->eui.lo);

sys/dev/ieee1394/firewire.c

1630

fwdev->eui.hi, fwdev->eui.lo);

sys/dev/ieee1394/firewire.c

1820

if (tfwdev->eui.hi > fwdev->eui.hi ||

sys/dev/ieee1394/firewire.c

1821

(tfwdev->eui.hi == fwdev->eui.hi &&

sys/dev/ieee1394/firewire.c

1833

fw_linkspeed[fwdev->speed], fwdev->eui.hi, fwdev->eui.lo);

sys/dev/ieee1394/firewire.c

2039

locs[IEEE1394IFCF_EUIHI] = fwdev->eui.hi;

sys/dev/ieee1394/firewire.h

250

uint32_t hi, lo;

sys/dev/ieee1394/firewire.h

254

((eui)->hi >> (8*(3-(x)))): \

sys/dev/ieee1394/firewire.h

258

((x).hi == (y).hi && (x).lo == (y).lo)

sys/dev/ieee1394/firewire.h

61

uint32_t hi;

sys/dev/ieee1394/fwcrom.c

570

src.businfo.eui64.hi = 0x11223344;

sys/dev/ieee1394/fwdev.c

580

fwb = fw_bindlookup(fc, bindreq->start.hi, bindreq->start.lo);

sys/dev/ieee1394/fwdev.c

596

if (bindreq->start.hi > 0xffff ) {

sys/dev/ieee1394/fwdev.c

606

fwb->start = ((u_int64_t)bindreq->start.hi << 32) |

sys/dev/ieee1394/fwdev.c

628

devinfo->eui.hi = fc->eui.hi;

sys/dev/ieee1394/fwdev.c

636

devinfo->eui.hi = fwdev->eui.hi;

sys/dev/ieee1394/fwmem.c

249

fms->eui.hi, fms->eui.lo);

sys/dev/ieee1394/fwmem.c

88

NULL, 0, &fwmem_eui64.hi,

sys/dev/ieee1394/fwohci.c

495

sc->fc.eui.hi = OREAD(sc, FWOHCIGUID_H);

sys/dev/ieee1394/if_fwip.c

198

hwaddr->sender_unique_ID_hi = htonl(sc->sc_fd.fc->eui.hi);

sys/dev/ieee1394/if_fwip.c

412

sc->sc_last_dest.hi = 0;

sys/dev/ieee1394/if_fwip.c

498

sc->sc_last_dest.hi = 0;

sys/dev/ieee1394/if_fwip.c

620

eui.hi = ntohl(destfw->sender_unique_ID_hi);

sys/dev/ieee1394/if_fwip.c

622

if (sc->sc_last_dest.hi != eui.hi ||

sys/dev/ieee1394/if_fwip.c

774

p2[0] = htonl(fd->eui.hi);

sys/dev/ieee1394/if_fwip.c

877

p[0] = htonl(fd->eui.hi);

sys/dev/ieee1394/sbp.c

1016

printf("sbp_post_explore: EUI:%08x%08x ", fwdev->eui.hi, fwdev->eui.lo);

sys/dev/ieee1394/sbp.c

2354

ocb->ind_ptr[i].hi = htonl(s->ds_len << 16);

sys/dev/ieee1394/sbp.c

655

fwdev->eui.hi,

sys/dev/ieee1394/sbp.h

71

uint32_t hi,lo;

sys/dev/mvme/memcreg.h

64

#define MEMC_BASE_ADDRESS(hi,lo) (((hi) << 24) | (((lo) & 0xc0) << 22))

sys/dev/ofw/ofw_pci.h

83

#define OFW_PCI_PHYS_HI_BUS(hi) \

sys/dev/ofw/ofw_pci.h

84

(((hi) & OFW_PCI_PHYS_HI_BUSMASK) >> OFW_PCI_PHYS_HI_BUSSHIFT)

sys/dev/ofw/ofw_pci.h

85

#define OFW_PCI_PHYS_HI_DEVICE(hi) \

sys/dev/ofw/ofw_pci.h

86

(((hi) & OFW_PCI_PHYS_HI_DEVICEMASK) >> OFW_PCI_PHYS_HI_DEVICESHIFT)

sys/dev/ofw/ofw_pci.h

87

#define OFW_PCI_PHYS_HI_FUNCTION(hi) \

sys/dev/ofw/ofw_pci.h

88

(((hi) & OFW_PCI_PHYS_HI_FUNCTIONMASK) >> OFW_PCI_PHYS_HI_FUNCTIONSHIFT)

sys/dev/pci/agp_i810.c

678

pcireg_t lo, hi;

sys/dev/pci/agp_i810.c

694

hi = pci_conf_read(pc, tag, AGP_I965_IFPADDR+4);

sys/dev/pci/agp_i810.c

704

addr = ((uint64_t)hi << 32) | lo;

sys/dev/pci/agp_i810.c

705

if (hi) {

sys/dev/pci/agp_i810.c

708

": %"PRIx64"\n", ((uint64_t)hi << 32) | lo);

sys/dev/pci/agp_i810.c

737

hi = __SHIFTOUT(addr, __BITS(63, 32));

sys/dev/pci/agp_i810.c

739

pci_conf_write(pc, tag, AGP_I965_IFPADDR+4, hi);

sys/dev/pci/cxgb/cxgb_main.c

1049

int hi, int port)

sys/dev/pci/cxgb/cxgb_main.c

1062

req->max = hi;

sys/dev/pci/esa.c

1690

uint16_t hi, lo;

sys/dev/pci/esa.c

1695

hi = esa_read_assp(sc, ESA_MEMTYPE_INTERNAL_DATA, data_offset +

sys/dev/pci/esa.c

1700

addr = lo | ((uint32_t)hi << 16);

sys/dev/pci/if_iwn.c

1728

aprint_normal("chan lo=%d, chan hi=%d\n", band->lo, band->hi);

sys/dev/pci/if_iwn.c

3771

sc->bands[i].lo <= chan && chan <= sc->bands[i].hi)

sys/dev/pci/if_iwnreg.h

1635

uint8_t hi; /* high channel number */

sys/dev/pci/if_mcx.c

8227

uint32_t hi, lo, ni;

sys/dev/pci/if_mcx.c

8229

hi = mcx_rd(sc, MCX_INTERNAL_TIMER_H);

sys/dev/pci/if_mcx.c

8235

if (ni == hi)

sys/dev/pci/if_mcx.c

8238

hi = ni;

sys/dev/pci/if_mcx.c

8241

return (((uint64_t)hi << 32) | (uint64_t)lo);

sys/dev/pci/if_wm.c

16534

uint16_t lo, hi;

sys/dev/pci/if_wm.c

16538

hi = (uint16_t)((mreg >> 16) & 0xffff);

sys/dev/pci/if_wm.c

16540

wm_access_phy_wakeup_reg_bm(dev, BM_MTA(i) + 1, &hi, 0, true);

sys/dev/pci/if_wm.c

17353

uint16_t lo, hi;

sys/dev/pci/if_wm.c

17356

hi = (uint16_t)((mac_reg >> 16) & 0xffff);

sys/dev/pci/if_wm.c

17358

wm_access_phy_wakeup_reg_bm(dev, BM_RAR_M(i), &hi, 0, true);

sys/dev/pci/if_wm.c

17362

hi = (uint16_t)((mac_reg & RAL_AV) >> 16);

sys/dev/pci/if_wm.c

17364

wm_access_phy_wakeup_reg_bm(dev, BM_RAR_CTRL(i), &hi, 0, true);

sys/dev/pci/pci_subr.c

1504

uint32_t lo, hi;

sys/dev/pci/pci_subr.c

1515

hi = regs[o2i(capoff + PCI_HT_MSI_ADDR_HI)];

sys/dev/pci/pci_subr.c

1517

printf(" Address high register: 0x%08x\n", hi);

sys/dev/pci/pci_subr.c

1519

(uint64_t)hi << 32 | (lo & PCI_HT_MSI_ADDR_LO_MASK));

sys/dev/pci/pci_subr.c

3323

pcireg_t lo, hi;

sys/dev/pci/pci_subr.c

3330

hi = regs[o2i(extcapoff

sys/dev/pci/pci_subr.c

3333

"0x%08x\n", hi);

sys/dev/pci/pci_subr.c

3347

"0x%016" PRIx64 "\n", ((uint64_t)hi << 32) + lo);

sys/dev/pci/pci_subr.c

3478

pcireg_t lo, hi;

sys/dev/pci/pci_subr.c

3483

hi = regs[o2i(extcapoff + PCI_SERIAL_HIGH)];

sys/dev/pci/pci_subr.c

3485

hi >> 24, (hi >> 16) & 0xff, (hi >> 8) & 0xff, hi & 0xff,

sys/dev/pci/piixpm.c

447

uint8_t lo, hi;

sys/dev/pci/piixpm.c

474

hi = piixpm_sb800_pmread(sc, AMDFCH41_PM_DECODE_EN1);

sys/dev/pci/piixpm.c

475

base_addr = (uint16_t)hi << 8;

sys/dev/pci/piixpm.c

484

hi = piixpm_sb800_pmread(sc, SB800_PM_SMBUS0EN_HI);

sys/dev/pci/piixpm.c

485

base_addr = ((uint16_t)hi << 8) & SB800_PM_SMBUS0EN_BADDR;

sys/dev/pci/qat/qatvar.h

1109

uint32_t lo, hi;

sys/dev/pci/qat/qatvar.h

1112

hi = (uint32_t)((value & 0xffffffff00000000ULL) >> 32);

sys/dev/pci/qat/qatvar.h

1114

qat_etr_bank_ring_write_4(sc, bank, ring, ETR_RING_UBASE, hi);

sys/dev/pci/veritefb.c

2220

size_t size, uint32_t lo, uint32_t hi, bool install_csucode,

sys/dev/pci/veritefb.c

2248

if (entry < lo || entry >= hi) {

sys/dev/pci/veritefb.c

2251

entry, lo, hi);

sys/dev/pci/veritefb.c

2280

(uint64_t)paddr + roundup(memsz, 4) > hi) {

sys/dev/pci/voyager.c

456

uint32_t reg = 0, hi, lo;

sys/dev/pci/voyager.c

473

hi = steps * duty_cycle / 1000;

sys/dev/pci/voyager.c

474

if (hi < 1)

sys/dev/pci/voyager.c

475

hi = 1;

sys/dev/pci/voyager.c

476

lo = steps - hi;

sys/dev/pci/voyager.c

478

hi = steps - 1;

sys/dev/pci/voyager.c

481

DPRINTF("%d hz -> %d, %d, %d / %d\n", freq, factor, steps, lo, hi);

sys/dev/pci/voyager.c

482

reg = ((hi - 1) & 0xfff) << SM502_PWM_CLOCK_HIGH_SHIFT;

sys/dev/pcmcia/if_cnw.c

270

int hi, lo;

sys/dev/pcmcia/if_cnw.c

279

hi = bus_space_read_1(sc->sc_memt, sc->sc_memh, offs + 1);

sys/dev/pcmcia/if_cnw.c

280

return ((hi << 8) | lo);

sys/dev/sbus/cgtwelve.c

355

uint32_t hi = (idx >> 8) & 0xff;

sys/dev/sbus/cgtwelve.c

358

hi |= hi << 8 | hi << 16;

sys/dev/sbus/cgtwelve.c

360

bus_space_write_4(sc->sc_tag, sc->sc_regh, CG12DAC_ADDR1, hi);

sys/dev/tc/pxg.c

273

volatile uint32_t *hi;

sys/dev/tc/pxg.c

280

hi = (volatile uint32_t *)si->si_slotbase +

sys/dev/tc/pxg.c

284

it = hi[0] & 15;

sys/dev/tc/pxg.c

285

hi[0] = 0;

sys/dev/tc/pxg.c

287

hi[2] = 0;

sys/dev/usb/if_mue.c

684

uint32_t lo, hi;

sys/dev/usb/if_mue.c

687

hi = MUE_ENADDR_HI(enaddr);

sys/dev/usb/if_mue.c

690

mue_csr_write(un, MUE_RX_ADDRH, hi);

sys/dev/usb/if_otus.c

2300

uint32_t lo, hi;

sys/dev/usb/if_otus.c

2308

lo = hi = 0xffffffff;

sys/dev/usb/if_otus.c

2311

lo = hi = 0;

sys/dev/usb/if_otus.c

2317

lo = hi = 0xffffffff;

sys/dev/usb/if_otus.c

2324

hi |= 1 << (bit - 32);

sys/dev/usb/if_otus.c

2330

hi |= 1 << 31; /* Make sure the broadcast bit is set. */

sys/dev/usb/if_otus.c

2332

otus_write(sc, AR_MAC_REG_GROUP_HASH_TBL_H, hi);

sys/dev/vmt/vmtvar.h

43

#define VM_REG_CMD(hi, low) \

sys/dev/vmt/vmtvar.h

44

(__SHIFTIN((hi), VM_REG_HIGH_MASK) | __SHIFTIN((low), VM_REG_LOW_MASK))

sys/dev/wsfont/wsfont.c

1081

int hi, lo;

sys/dev/wsfont/wsfont.c

1086

hi = (c >> 8);

sys/dev/wsfont/wsfont.c

1090

if (hi < map1->base || hi >= map1->base + map1->size)

sys/dev/wsfont/wsfont.c

1093

map2 = map1->level2[hi - map1->base];

sys/dev/wsfont/wsfont.c

1096

if (hi == 0 && font->encoding == WSDISPLAY_FONTENC_ISO)

sys/fs/efs/efs_subr.c

420

int hi, lo, mid;

sys/fs/efs/efs_subr.c

519

hi = numextents - 1;

sys/fs/efs/efs_subr.c

521

while (lo <= hi) {

sys/fs/efs/efs_subr.c

525

mid = (lo + hi) / 2;

sys/fs/efs/efs_subr.c

547

hi = mid - 1;

sys/fs/efs/efs_subr.c

557

if (lo > hi) {

sys/fs/nfs/server/nfs_nfsdport.c

135

int hi, try;

sys/fs/nfs/server/nfs_nfsdport.c

139

hi = ((int)(vaddr_t)vp / sizeof(struct vnode)) % NUM_HEURISTIC;

sys/fs/nfs/server/nfs_nfsdport.c

140

nh = &nfsheur[hi];

sys/fs/nfs/server/nfs_nfsdport.c

142

if (nfsheur[hi].nh_vp == vp) {

sys/fs/nfs/server/nfs_nfsdport.c

143

nh = &nfsheur[hi];

sys/fs/nfs/server/nfs_nfsdport.c

146

if (nfsheur[hi].nh_use > 0)

sys/fs/nfs/server/nfs_nfsdport.c

147

--nfsheur[hi].nh_use;

sys/fs/nfs/server/nfs_nfsdport.c

148

hi = (hi + 1) % NUM_HEURISTIC;

sys/fs/nfs/server/nfs_nfsdport.c

149

if (nfsheur[hi].nh_use < nh->nh_use)

sys/fs/nfs/server/nfs_nfsdport.c

150

nh = &nfsheur[hi];

sys/kern/kern_descrip.c

1005

fd_map_alloc(int n, uint32_t **lo, uint32_t **hi)

sys/kern/kern_descrip.c

1016

*hi = (uint32_t *)(ptr + szlo);

sys/kern/kern_descrip.c

1023

fd_map_free(int n, uint32_t *lo, uint32_t *hi)

sys/kern/kern_descrip.c

1031

KASSERT(hi == (uint32_t *)((uint8_t *)lo + szlo));

sys/kern/kern_descrip.c

895

int i, lim, last, error, hi;

sys/kern/kern_descrip.c

916

hi = fd_next_zero(fdp, fdp->fd_himap, off,

sys/kern/kern_descrip.c

918

if (hi == -1)

sys/kern/kern_descrip.c

920

i = fd_next_zero(fdp, &fdp->fd_lomap[hi],

sys/kern/kern_descrip.c

921

hi > off ? 0 : i & NDENTRYMASK, NDENTRIES);

sys/kern/kern_descrip.c

927

want = (hi + 1) << NDENTRYSHIFT;

sys/kern/kern_descrip.c

930

i += (hi << NDENTRYSHIFT);

sys/kern/kern_history.c

148

int lcv, hi;

sys/kern/kern_history.c

161

hi = -1;

sys/kern/kern_history.c

191

hi = lcv;

sys/kern/kern_history.c

196

if (hi == -1)

sys/kern/kern_history.c

200

kernhist_entry_print(&hists[hi]->e[cur[hi]], pr);

sys/kern/kern_history.c

202

cur[hi] = (cur[hi] + 1) % (hists[hi]->n);

sys/kern/kern_history.c

203

if (cur[hi] == hists[hi]->f)

sys/kern/kern_history.c

204

cur[hi] = -1;

sys/kern/kern_tc.c

149

uint32_t lo, hi;

sys/kern/kern_tc.c

197

if (__predict_true(sechi == time__second32.hi) &&

sys/kern/kern_tc.c

198

__predict_true(uphi == time__uptime32.hi)) {

sys/kern/kern_tc.c

204

atomic_store_relaxed(&time__second32.hi, 0xffffffff);

sys/kern/kern_tc.c

205

atomic_store_relaxed(&time__uptime32.hi, 0xffffffff);

sys/kern/kern_tc.c

210

atomic_store_relaxed(&time__second32.hi, sechi);

sys/kern/kern_tc.c

211

atomic_store_relaxed(&time__uptime32.hi, uphi);

sys/kern/kern_tc.c

217

uint32_t lo, hi;

sys/kern/kern_tc.c

221

hi = atomic_load_relaxed(&time__second32.hi);

sys/kern/kern_tc.c

222

if (__predict_true(hi != 0xffffffff))

sys/kern/kern_tc.c

229

} while (hi != atomic_load_relaxed(&time__second32.hi));

sys/kern/kern_tc.c

231

return ((time_t)hi << 32) | lo;

sys/kern/kern_tc.c

237

uint32_t lo, hi;

sys/kern/kern_tc.c

241

hi = atomic_load_relaxed(&time__uptime32.hi);

sys/kern/kern_tc.c

242

if (__predict_true(hi != 0xffffffff))

sys/kern/kern_tc.c

249

} while (hi != atomic_load_relaxed(&time__uptime32.hi));

sys/kern/kern_tc.c

251

return ((time_t)hi << 32) | lo;

sys/kern/subr_cpufreq.c

379

uint32_t f, hi, i = 0, lo = 0;

sys/kern/subr_cpufreq.c

385

hi = cf->cf_state_count;

sys/kern/subr_cpufreq.c

387

while (lo < hi) {

sys/kern/subr_cpufreq.c

389

i = (lo + hi) >> 1;

sys/kern/subr_cpufreq.c

395

hi = i;

sys/net/toeplitz.h

64

uint16_t hi, lo;

sys/net/toeplitz.h

66

hi = stoeplitz_cache_entry(scache, n16 >> 8);

sys/net/toeplitz.h

69

return (hi ^ bswap16(lo));

sys/net/toeplitz.h

83

uint16_t lo, hi;

sys/net/toeplitz.h

86

hi = stoeplitz_cache_entry(scache, h16 >> 8);

sys/net/toeplitz.h

89

return (hi ^ bswap16(lo));

sys/net/toeplitz.h

91

return (bswap16(hi) ^ lo);

sys/net80211/ieee80211_crypto_tkip.c

453

static __inline u16 Mk16(u8 hi, u8 lo)

sys/net80211/ieee80211_crypto_tkip.c

455

return lo | (((u16) hi) << 8);

sys/netinet/dccp_usrreq.c

1718

dp->ref_seq.hi = dp->seq_snd >> 24;

sys/netinet/dccp_usrreq.c

2119

dp->ref_pseq.hi = 0;

sys/netinet/dccp_usrreq.c

472

dp->ref_seq.hi = dp->seq_snd >> 24;

sys/netinet/dccp_usrreq.c

489

ntohl(dh->dh_seq) >> 8, dp->ref_pseq.hi, dp->ref_pseq.lo));

sys/netinet/dccp_usrreq.c

537

dp->ref_pseq.hi = seqnr >> 24;

sys/netinet/dccp_usrreq.c

563

dp->ref_pseq.hi = seqnr >> 24;

sys/netinet/dccp_var.h

59

(((u_int64_t)(ref.hi + 1) << 24) | S) % 281474976710656ll: \

sys/netinet/dccp_var.h

60

(((u_int64_t)ref.hi << 24) | S) % 281474976710656ll)

sys/netinet/dccp_var.h

63

u_int32_t hi;

sys/netinet/tcp_vtw.c

563

uint32_t hi = tag & fat->mask;

sys/netinet/tcp_vtw.c

565

fatp_t *fr = fat->hash[hi];

sys/netinet/tcp_vtw.c

577

KASSERT(fat->hash[hi] == fp);

sys/netinet/tcp_vtw.c

580

fat->hash[hi]

sys/netinet/tcp_vtw.c

591

fr = fat->hash[hi];

sys/netinet/tcp_vtw.c

638

uint32_t hi = tag & fat->mask;

sys/netinet/tcp_vtw.c

640

fatp_t *fr = fat->port[hi];

sys/netinet/tcp_vtw.c

652

KASSERT(fat->port[hi] == fp);

sys/netinet/tcp_vtw.c

655

fat->port[hi]

sys/nfs/nfs_subs.c

1852

off_t lo, hi;

sys/nfs/nfs_subs.c

1857

hi = lo + len;

sys/nfs/nfs_subs.c

1859

return (lo >= np->n_pushedlo && hi <= np->n_pushedhi);

sys/nfs/nfs_subs.c

1866

off_t lo, hi;

sys/nfs/nfs_subs.c

1871

hi = lo + len;

sys/nfs/nfs_subs.c

1873

return (lo >= np->n_pushlo && hi <= np->n_pushhi);

sys/nfs/nfs_subs.c

1880

off_t lo, hi;

sys/nfs/nfs_subs.c

1883

hi = lo + len;

sys/nfs/nfs_subs.c

1887

np->n_pushedhi = hi;

sys/nfs/nfs_subs.c

1890

if (hi > np->n_pushedhi)

sys/nfs/nfs_subs.c

1891

np->n_pushedhi = hi;

sys/nfs/nfs_subs.c

1905

off_t lo, hi;

sys/nfs/nfs_subs.c

1911

hi = lo + len;

sys/nfs/nfs_subs.c

1913

if (lo > np->n_pushedhi || hi < np->n_pushedlo)

sys/nfs/nfs_subs.c

1916

np->n_pushedlo = hi;

sys/nfs/nfs_subs.c

1917

else if (hi >= np->n_pushedhi)

sys/nfs/nfs_subs.c

1925

if ((np->n_pushedlo - lo) > (hi - np->n_pushedhi))

sys/nfs/nfs_subs.c

1928

np->n_pushedlo = hi;

sys/nfs/nfs_subs.c

1940

off_t lo, hi;

sys/nfs/nfs_subs.c

1943

hi = lo + len;

sys/nfs/nfs_subs.c

1947

np->n_pushhi = hi;

sys/nfs/nfs_subs.c

1952

if (hi > np->n_pushhi)

sys/nfs/nfs_subs.c

1953

np->n_pushhi = hi;

sys/nfs/nfs_subs.c

1965

off_t lo, hi;

sys/nfs/nfs_subs.c

1971

hi = lo + len;

sys/nfs/nfs_subs.c

1973

if (lo > np->n_pushhi || hi < np->n_pushlo)

sys/nfs/nfs_subs.c

1977

np->n_pushlo = hi;

sys/nfs/nfs_subs.c

1978

else if (hi >= np->n_pushhi)

sys/nfs/nfs_subs.c

1986

if ((np->n_pushlo - lo) > (hi - np->n_pushhi))

sys/nfs/nfs_subs.c

1989

np->n_pushlo = hi;

sys/uvm/uvm_aobj.h

66

#define uao_dropswap_range(obj, lo, hi) /* nothing */

tests/dev/audio/audiotest.c

5599

int hi;

tests/dev/audio/audiotest.c

5615

hi = *ai_gain;

tests/dev/audio/audiotest.c

5618

for (lo = hi - 1; lo >= 0; lo--) {

tests/dev/audio/audiotest.c

5626

if (*ai_gain != hi) {

tests/dev/audio/audiotest.c

5641

if (hi < 0) {

tests/dev/audio/audiotest.c

5646

gain[0] = hi;

tests/dev/audio/audiotest.c

5651

gain[1] = hi;

tests/dev/usb/t_hid.c

106

struct hid_item hi;

tests/dev/usb/t_hid.c

116

&hi);

tests/dev/usb/t_hid.c

118

MYu_ATF_CHECK_EQ(hi.loc.size, 32);

tests/dev/usb/t_hid.c

119

MYu_ATF_CHECK_EQ(hi.loc.count, 1);

tests/dev/usb/t_hid.c

120

MYu_ATF_CHECK_EQ(hi.loc.pos, 0);

tests/dev/usb/t_hid.c

121

MYx_ATF_CHECK_EQ(hi.flags, 0);

tests/dev/usb/t_hid.c

122

MYd_ATF_CHECK_EQ(hi.logical_minimum, -2147483648);

tests/dev/usb/t_hid.c

123

MYd_ATF_CHECK_EQ(hi.logical_maximum, 2147483647);

tests/dev/usb/t_hid.c

124

MYd_ATF_CHECK_EQ(hi.physical_minimum, -2147483648);

tests/dev/usb/t_hid.c

125

MYd_ATF_CHECK_EQ(hi.physical_maximum, 2147483647);

tests/dev/usb/t_hid.c

127

&hi.loc), -2147483648);

tests/dev/usb/t_hid.c

129

&hi.loc), -1);

tests/dev/usb/t_hid.c

131

&hi.loc), 1);

tests/dev/usb/t_hid.c

133

&hi.loc), 2147483647);

tests/dev/usb/t_hid.c

137

&hi);

tests/dev/usb/t_hid.c

139

MYu_ATF_CHECK_EQ(hi.loc.size, 16);

tests/dev/usb/t_hid.c

140

MYu_ATF_CHECK_EQ(hi.loc.count, 1);

tests/dev/usb/t_hid.c

141

MYu_ATF_CHECK_EQ(hi.loc.pos, 32);

tests/dev/usb/t_hid.c

142

MYx_ATF_CHECK_EQ(hi.flags, 0);

tests/dev/usb/t_hid.c

143

MYd_ATF_CHECK_EQ(hi.logical_minimum, -32768);

tests/dev/usb/t_hid.c

144

MYd_ATF_CHECK_EQ(hi.logical_maximum, 32767);

tests/dev/usb/t_hid.c

145

MYd_ATF_CHECK_EQ(hi.physical_minimum, -32768);

tests/dev/usb/t_hid.c

146

MYd_ATF_CHECK_EQ(hi.physical_maximum, 32767);

tests/dev/usb/t_hid.c

148

&hi.loc), -32768);

tests/dev/usb/t_hid.c

150

&hi.loc), -1);

tests/dev/usb/t_hid.c

152

&hi.loc), 1);

tests/dev/usb/t_hid.c

154

&hi.loc), 32767);

tests/dev/usb/t_hid.c

158

&hi);

tests/dev/usb/t_hid.c

160

MYu_ATF_CHECK_EQ(hi.loc.size, 8);

tests/dev/usb/t_hid.c

161

MYu_ATF_CHECK_EQ(hi.loc.count, 1);

tests/dev/usb/t_hid.c

162

MYu_ATF_CHECK_EQ(hi.loc.pos, 48);

tests/dev/usb/t_hid.c

163

MYx_ATF_CHECK_EQ(hi.flags, 0);

tests/dev/usb/t_hid.c

164

MYd_ATF_CHECK_EQ(hi.logical_minimum, -128);

tests/dev/usb/t_hid.c

165

MYd_ATF_CHECK_EQ(hi.logical_maximum, 127);

tests/dev/usb/t_hid.c

166

MYd_ATF_CHECK_EQ(hi.physical_minimum, -128);

tests/dev/usb/t_hid.c

167

MYd_ATF_CHECK_EQ(hi.physical_maximum, 127);

tests/dev/usb/t_hid.c

169

&hi.loc), -128);

tests/dev/usb/t_hid.c

171

&hi.loc), -1);

tests/dev/usb/t_hid.c

173

&hi.loc), 1);

tests/dev/usb/t_hid.c

175

&hi.loc), 127);

tests/dev/usb/t_hid.c

180

hid_input, &hi);

tests/dev/usb/t_hid.c

182

MYu_ATF_CHECK_EQ(hi.loc.size, 32);

tests/dev/usb/t_hid.c

183

MYu_ATF_CHECK_EQ(hi.loc.count, 1);

tests/dev/usb/t_hid.c

184

MYu_ATF_CHECK_EQ(hi.loc.pos, 0);

tests/dev/usb/t_hid.c

185

MYx_ATF_CHECK_EQ(hi.flags, 0);

tests/dev/usb/t_hid.c

187

&hi.loc), 0x0);

tests/dev/usb/t_hid.c

189

&hi.loc), 0x1);

tests/dev/usb/t_hid.c

191

&hi.loc), 0xfffffffe);

tests/dev/usb/t_hid.c

193

&hi.loc), 0xffffffff);

tests/dev/usb/t_hid.c

197

hid_input, &hi);

tests/dev/usb/t_hid.c

199

MYu_ATF_CHECK_EQ(hi.loc.size, 16);

tests/dev/usb/t_hid.c

200

MYu_ATF_CHECK_EQ(hi.loc.count, 1);

tests/dev/usb/t_hid.c

201

MYu_ATF_CHECK_EQ(hi.loc.pos, 32);

tests/dev/usb/t_hid.c

202

MYx_ATF_CHECK_EQ(hi.flags, 0);

tests/dev/usb/t_hid.c

204

&hi.loc), 0x0);

tests/dev/usb/t_hid.c

206

&hi.loc), 0x1);

tests/dev/usb/t_hid.c

208

&hi.loc), 0xfffe);

tests/dev/usb/t_hid.c

210

&hi.loc), 0xffff);

tests/dev/usb/t_hid.c

214

hid_input, &hi);

tests/dev/usb/t_hid.c

216

MYu_ATF_CHECK_EQ(hi.loc.size, 8);

tests/dev/usb/t_hid.c

217

MYu_ATF_CHECK_EQ(hi.loc.count, 1);

tests/dev/usb/t_hid.c

218

MYu_ATF_CHECK_EQ(hi.loc.pos, 48);

tests/dev/usb/t_hid.c

219

MYx_ATF_CHECK_EQ(hi.flags, 0);

tests/dev/usb/t_hid.c

221

&hi.loc), 0x0);

tests/dev/usb/t_hid.c

223

&hi.loc), 0x1);

tests/dev/usb/t_hid.c

225

&hi.loc), 0xfe);

tests/dev/usb/t_hid.c

227

&hi.loc), 0xff);

tests/dev/usb/t_hid.c

244

struct hid_item hi;

tests/dev/usb/t_hid.c

252

while (hid_get_item(hdp, &hi) > 0) {

tests/lib/libc/db/h_lfsr.c

63

HASHINFO hi;

tests/lib/libc/db/h_lfsr.c

68

memset(&hi, 0, sizeof(hi));

tests/lib/libc/db/h_lfsr.c

70

hi.bsize = pagesize;

tests/lib/libc/db/h_lfsr.c

71

hi.nelem = 65536;

tests/lib/libc/db/h_lfsr.c

72

hi.ffactor = 128;

tests/lib/libc/db/h_lfsr.c

77

db = dbopen(NULL, O_CREAT|O_TRUNC|O_RDWR, 0, DB_HASH, &hi);

tests/lib/libc/stdlib/t_strtoi.c

180

rv = strtoi(t[i].str, &end, t[i].base, t[i].lo, t[i].hi, &e);

tests/lib/libc/stdlib/t_strtoi.c

193

rv = strtoi(f[i].str, &end, f[i].base, f[i].lo, f[i].hi, &e);

tests/lib/libc/stdlib/t_strtoi.c

238

rv = strtoi(t[i].str, &end, t[i].base, t[i].lo, t[i].hi, &e);

tests/lib/libc/stdlib/t_strtoi.c

291

rv = strtoi(t[i].str, &end, t[i].base, t[i].lo, t[i].hi, &e);

tests/lib/libc/stdlib/t_strtoi.c

326

rv = strtoi(t[i].str, &end, t[i].base, t[i].lo, t[i].hi, &e);

tests/lib/libc/stdlib/t_strtoi.c

381

rv = strtoi(t[i].str, &end, t[i].base, t[i].lo, t[i].hi, &e);

tests/lib/libc/stdlib/t_strtoi.c

53

intmax_t hi;

tests/lib/libc/stdlib/t_strtoi.c

66

t->lo, t->hi, rv);

tests/lib/libc/stdlib/t_strtoi.c

85

t->str, t->base, t->lo, t->hi, rstatus, rstatus ? "('" : "",

tests/lib/libc/stdlib/t_strtoi.c

97

"expected '%s'", end, t->str, t->base, t->lo, t->hi,

tests/lib/libusbhid/t_usbhid.c

118

hid_item_t hi;

tests/lib/libusbhid/t_usbhid.c

126

ATF_REQUIRE(hid_locate(hrd, 0xff000001U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

128

MYd_ATF_CHECK_EQ(hi.logical_minimum, -128);

tests/lib/libusbhid/t_usbhid.c

129

MYd_ATF_CHECK_EQ(hi.logical_maximum, 127);

tests/lib/libusbhid/t_usbhid.c

130

ATF_REQUIRE(hid_locate(hrd, 0xff000002U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

132

MYd_ATF_CHECK_EQ(hi.logical_minimum, -32768);

tests/lib/libusbhid/t_usbhid.c

133

MYd_ATF_CHECK_EQ(hi.logical_maximum, 32767);

tests/lib/libusbhid/t_usbhid.c

134

ATF_REQUIRE(hid_locate(hrd, 0xff000003U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

136

MYd_ATF_CHECK_EQ(hi.logical_minimum, -2147483648);

tests/lib/libusbhid/t_usbhid.c

137

MYd_ATF_CHECK_EQ(hi.logical_maximum, 2147483647);

tests/lib/libusbhid/t_usbhid.c

145

ATF_REQUIRE(hid_locate(hrd, 0xff000011U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

147

ATF_CHECK(hi.logical_minimum > hi.logical_maximum);

tests/lib/libusbhid/t_usbhid.c

148

minimum = (uint32_t)hi.logical_minimum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

150

maximum = (uint32_t)hi.logical_maximum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

152

ATF_REQUIRE(hid_locate(hrd, 0xff000012U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

154

ATF_CHECK(hi.logical_minimum > hi.logical_maximum);

tests/lib/libusbhid/t_usbhid.c

155

minimum = hi.logical_minimum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

157

maximum = hi.logical_maximum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

159

ATF_REQUIRE(hid_locate(hrd, 0xff000013U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

161

ATF_CHECK(hi.logical_minimum > hi.logical_maximum);

tests/lib/libusbhid/t_usbhid.c

162

minimum = hi.logical_minimum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

164

maximum = hi.logical_maximum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

181

hid_item_t hi;

tests/lib/libusbhid/t_usbhid.c

189

ATF_REQUIRE(hid_locate(hrd, 0xff000001U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

191

MYd_ATF_CHECK_EQ(hi.physical_minimum, -128);

tests/lib/libusbhid/t_usbhid.c

192

MYd_ATF_CHECK_EQ(hi.physical_maximum, 127);

tests/lib/libusbhid/t_usbhid.c

193

ATF_REQUIRE(hid_locate(hrd, 0xff000002U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

195

MYd_ATF_CHECK_EQ(hi.physical_minimum, -32768);

tests/lib/libusbhid/t_usbhid.c

196

MYd_ATF_CHECK_EQ(hi.physical_maximum, 32767);

tests/lib/libusbhid/t_usbhid.c

197

ATF_REQUIRE(hid_locate(hrd, 0xff000003U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

199

MYd_ATF_CHECK_EQ(hi.physical_minimum, -2147483648);

tests/lib/libusbhid/t_usbhid.c

200

MYd_ATF_CHECK_EQ(hi.physical_maximum, 2147483647);

tests/lib/libusbhid/t_usbhid.c

208

ATF_REQUIRE(hid_locate(hrd, 0xff000011U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

210

ATF_CHECK(hi.physical_minimum > hi.physical_maximum);

tests/lib/libusbhid/t_usbhid.c

211

minimum = (uint32_t)hi.physical_minimum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

213

maximum = (uint32_t)hi.physical_maximum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

215

ATF_REQUIRE(hid_locate(hrd, 0xff000012U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

217

ATF_CHECK(hi.physical_minimum > hi.physical_maximum);

tests/lib/libusbhid/t_usbhid.c

218

minimum = hi.physical_minimum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

220

maximum = hi.physical_maximum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

222

ATF_REQUIRE(hid_locate(hrd, 0xff000013U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

224

ATF_CHECK(hi.physical_minimum > hi.physical_maximum);

tests/lib/libusbhid/t_usbhid.c

225

minimum = hi.physical_minimum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

227

maximum = hi.physical_maximum & ((1ULL<<hi.report_size)-1);

tests/lib/libusbhid/t_usbhid.c

243

hid_item_t hi;

tests/lib/libusbhid/t_usbhid.c

254

ATF_REQUIRE(hid_locate(hrd, 0xff000001U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

256

data = hid_get_data(range_test_minimum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

258

data = hid_get_data(range_test_negative_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

260

data = hid_get_data(range_test_positive_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

262

data = hid_get_data(range_test_maximum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

265

ATF_REQUIRE(hid_locate(hrd, 0xff000002U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

267

data = hid_get_data(range_test_minimum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

269

data = hid_get_data(range_test_negative_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

271

data = hid_get_data(range_test_positive_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

273

data = hid_get_data(range_test_maximum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

276

ATF_REQUIRE(hid_locate(hrd, 0xff000003U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

278

data = hid_get_data(range_test_minimum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

280

data = hid_get_data(range_test_negative_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

282

data = hid_get_data(range_test_positive_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

284

data = hid_get_data(range_test_maximum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

293

ATF_REQUIRE(hid_locate(hrd, 0xff000011U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

295

udat = hid_get_data(unsigned_range_test_minimum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

297

udat = hid_get_data(unsigned_range_test_positive_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

299

udat = hid_get_data(unsigned_range_test_negative_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

301

udat = hid_get_data(unsigned_range_test_maximum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

304

ATF_REQUIRE(hid_locate(hrd, 0xff000012U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

306

udat = hid_get_data(unsigned_range_test_minimum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

308

udat = hid_get_data(unsigned_range_test_positive_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

310

udat = hid_get_data(unsigned_range_test_negative_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

312

udat = hid_get_data(unsigned_range_test_maximum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

315

ATF_REQUIRE(hid_locate(hrd, 0xff000013U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

317

udat = hid_get_data(unsigned_range_test_minimum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

319

udat = hid_get_data(unsigned_range_test_positive_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

321

udat = hid_get_data(unsigned_range_test_negative_one_report, &hi);

tests/lib/libusbhid/t_usbhid.c

323

udat = hid_get_data(unsigned_range_test_maximum_report, &hi);

tests/lib/libusbhid/t_usbhid.c

339

hid_item_t hi;

tests/lib/libusbhid/t_usbhid.c

348

ATF_REQUIRE(hid_locate(hrd, 0xff000001U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

350

hid_set_data(test_data_minimum, &hi, -128);

tests/lib/libusbhid/t_usbhid.c

351

hid_set_data(test_data_negative_one, &hi, -1);

tests/lib/libusbhid/t_usbhid.c

352

hid_set_data(test_data_positive_one, &hi, 1);

tests/lib/libusbhid/t_usbhid.c

353

hid_set_data(test_data_maximum, &hi, 127);

tests/lib/libusbhid/t_usbhid.c

354

ATF_REQUIRE(hid_locate(hrd, 0xff000002U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

356

hid_set_data(test_data_minimum, &hi, -32768);

tests/lib/libusbhid/t_usbhid.c

357

hid_set_data(test_data_negative_one, &hi, -1);

tests/lib/libusbhid/t_usbhid.c

358

hid_set_data(test_data_positive_one, &hi, 1);

tests/lib/libusbhid/t_usbhid.c

359

hid_set_data(test_data_maximum, &hi, 32767);

tests/lib/libusbhid/t_usbhid.c

360

ATF_REQUIRE(hid_locate(hrd, 0xff000003U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

362

hid_set_data(test_data_minimum, &hi, -2147483648);

tests/lib/libusbhid/t_usbhid.c

363

hid_set_data(test_data_negative_one, &hi, -1);

tests/lib/libusbhid/t_usbhid.c

364

hid_set_data(test_data_positive_one, &hi, 1);

tests/lib/libusbhid/t_usbhid.c

365

hid_set_data(test_data_maximum, &hi, 2147483647);

tests/lib/libusbhid/t_usbhid.c

383

ATF_REQUIRE(hid_locate(hrd, 0xff000011U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

385

hid_set_data(test_data_minimum, &hi, 0);

tests/lib/libusbhid/t_usbhid.c

386

hid_set_data(test_data_positive_one, &hi, 1);

tests/lib/libusbhid/t_usbhid.c

387

hid_set_data(test_data_negative_one, &hi, 0xfffffffe);

tests/lib/libusbhid/t_usbhid.c

388

hid_set_data(test_data_maximum, &hi, 0xffffffff);

tests/lib/libusbhid/t_usbhid.c

389

ATF_REQUIRE(hid_locate(hrd, 0xff000012U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

391

hid_set_data(test_data_minimum, &hi, 0);

tests/lib/libusbhid/t_usbhid.c

392

hid_set_data(test_data_positive_one, &hi, 1);

tests/lib/libusbhid/t_usbhid.c

393

hid_set_data(test_data_negative_one, &hi, 0xfffe);

tests/lib/libusbhid/t_usbhid.c

394

hid_set_data(test_data_maximum, &hi, 0xffff);

tests/lib/libusbhid/t_usbhid.c

395

ATF_REQUIRE(hid_locate(hrd, 0xff000013U, hid_input, &hi,

tests/lib/libusbhid/t_usbhid.c

397

hid_set_data(test_data_minimum, &hi, 0);

tests/lib/libusbhid/t_usbhid.c

398

hid_set_data(test_data_positive_one, &hi, 1);

tests/lib/libusbhid/t_usbhid.c

399

hid_set_data(test_data_negative_one, &hi, 0xfffffffe);

tests/lib/libusbhid/t_usbhid.c

400

hid_set_data(test_data_maximum, &hi, 0xffffffff);

tests/lib/libusbhid/t_usbhid.c

428

hid_item_t hi;

tests/lib/libusbhid/t_usbhid.c

434

while (hid_get_item(hd, &hi) > 0) {

usr.bin/indent/lexi.c

281

unsigned hi = typenames.len;

usr.bin/indent/lexi.c

283

while (lo < hi) {

usr.bin/indent/lexi.c

284

unsigned mid = (lo + hi) / 2;

usr.bin/indent/lexi.c

289

hi = mid;

usr.bin/lock/lock.c

225

if (signal(SIGINT, hi) == SIG_ERR)

usr.bin/lock/lock.c

227

if (signal(SIGQUIT, hi) == SIG_ERR)

usr.bin/lock/lock.c

229

if (signal(SIGTSTP, hi) == SIG_ERR)

usr.bin/lock/lock.c

233

if (signal(SIGALRM, hi) == SIG_ERR)

usr.bin/lock/lock.c

266

hi(0);

usr.bin/lock/lock.c

84

static void hi(int);

usr.bin/make/arch.c

156

HashIter hi;

usr.bin/make/arch.c

158

HashIter_Init(&hi, &a->members);

usr.bin/make/arch.c

159

while (HashIter_Next(&hi))

usr.bin/make/arch.c

160

free(hi.entry->value);

usr.bin/make/dir.c

511

HashIter hi;

usr.bin/make/dir.c

512

HashIter_Init(&hi, tbl);

usr.bin/make/dir.c

513

while (HashIter_Next(&hi))

usr.bin/make/dir.c

514

free(hi.entry->value);

usr.bin/make/dir.c

651

HashIter hi;

usr.bin/make/dir.c

659

HashIter_InitSet(&hi, &dir->files);

usr.bin/make/dir.c

660

while (HashIter_Next(&hi)) {

usr.bin/make/dir.c

661

const char *base = hi.entry->key;

usr.bin/make/hash.c

311

HashIter_Next(HashIter *hi)

usr.bin/make/hash.c

313

HashTable *t = hi->table;

usr.bin/make/hash.c

314

HashEntry *he = hi->entry;

usr.bin/make/hash.c

322

if (hi->nextBucket >= bucketsSize)

usr.bin/make/hash.c

324

he = buckets[hi->nextBucket++];

usr.bin/make/hash.c

326

hi->entry = he;

usr.bin/make/hash.h

123

HashIter_Init(HashIter *hi, HashTable *t)

usr.bin/make/hash.h

125

hi->table = t;

usr.bin/make/hash.h

126

hi->nextBucket = 0;

usr.bin/make/hash.h

127

hi->entry = NULL;

usr.bin/make/hash.h

172

HashIter_InitSet(HashIter *hi, HashSet *set)

usr.bin/make/hash.h

174

HashIter_Init(hi, &set->tbl);

usr.bin/make/main.c

1991

HashIter hi;

usr.bin/make/main.c

1994

HashIter_Init(&hi, &cached_realpaths);

usr.bin/make/main.c

1995

more = HashIter_Next(&hi);

usr.bin/make/main.c

1997

HashEntry *he = hi.entry;

usr.bin/make/main.c

1998

more = HashIter_Next(&hi);

usr.bin/make/parse.c

2965

HashIter hi;

usr.bin/make/parse.c

2974

HashIter_Init(&hi, &guards);

usr.bin/make/parse.c

2975

while (HashIter_Next(&hi)) {

usr.bin/make/parse.c

2976

Guard *guard = hi.entry->value;

usr.bin/make/var.c

4927

HashIter hi;

usr.bin/make/var.c

4933

HashIter_Init(&hi, &scope->vars);

usr.bin/make/var.c

4934

while (HashIter_Next(&hi))

usr.bin/make/var.c

4935

*(const char **)Vector_Push(&vec) = hi.entry->key;

usr.bin/make/var.c

631

HashIter hi;

usr.bin/make/var.c

632

HashIter_Init(&hi, &scope->vars);

usr.bin/make/var.c

633

while (HashIter_Next(&hi)) {

usr.bin/make/var.c

634

Var *v = hi.entry->value;

usr.bin/make/var.c

822

HashIter hi;

usr.bin/make/var.c

825

HashIter_Init(&hi, &SCOPE_GLOBAL->vars);

usr.bin/make/var.c

826

while (HashIter_Next(&hi)) {

usr.bin/make/var.c

827

Var *var = hi.entry->value;

usr.bin/nc/netcat.c

1476

int hi, lo, cp;

usr.bin/nc/netcat.c

1484

hi = strtoport(n, uflag);

usr.bin/nc/netcat.c

1486

if (lo > hi) {

usr.bin/nc/netcat.c

1487

cp = hi;

usr.bin/nc/netcat.c

1488

hi = lo;

usr.bin/nc/netcat.c

1497

for (x = 0; x <= hi - lo; x++) {

usr.bin/nc/netcat.c

1504

for (cp = lo; cp <= hi; cp++) {

usr.bin/nc/netcat.c

1513

hi = strtoport(p, uflag);

usr.bin/nc/netcat.c

1514

if (asprintf(&tmp, "%d", hi) != -1)

usr.bin/usbhidaction/usbhidaction.c

247

int u, lo, hi, range;

usr.bin/usbhidaction/usbhidaction.c

322

hi = h.usage_maximum;

usr.bin/usbhidaction/usbhidaction.c

326

hi = h.usage;

usr.bin/usbhidaction/usbhidaction.c

329

for (u = lo; u <= hi; u++) {

usr.bin/xlint/lint1/cgram.y

1966

$$.hi = $$.lo;

usr.bin/xlint/lint1/cgram.y

1970

$$.hi = to_int_constant($3, true);

usr.bin/xlint/lint1/init.c

974

initialization_add_designator_subscript(init, range.hi);

usr.bin/xlint/lint1/lint1.h

483

size_t hi; /* inclusive */

usr.sbin/fwctl/fwcontrol.c

1020

uint32_t hi, lo;

usr.sbin/fwctl/fwcontrol.c

1021

memcpy(&hi, &target.octet[0], sizeof(hi));

usr.sbin/fwctl/fwcontrol.c

1023

eui.hi = ntohl(hi);

usr.sbin/fwctl/fwcontrol.c

1025

sysctl_set_int("hw.fwmem.eui64_hi", eui.hi);

usr.sbin/fwctl/fwcontrol.c

94

uint32_t hi, lo;

usr.sbin/fwctl/fwcontrol.c

95

hi = htonl(fweui->hi);

usr.sbin/fwctl/fwcontrol.c

97

memcpy(&eui->octet[0], &hi, sizeof(hi));

usr.sbin/inetd/parse_v2.c

408

int hi, lo;

usr.sbin/inetd/parse_v2.c

409

if ((hi = hex_to_bits(cp[1])) == -1

usr.sbin/inetd/parse_v2.c

415

*start = (char)((hi << 4) | lo);

usr.sbin/ldpd/fsm.c

103

SLIST_FOREACH(hi, &hello_info_head, infos)

usr.sbin/ldpd/fsm.c

104

if (hi->ldp_id.s_addr == pduid->ldp_id.s_addr &&

usr.sbin/ldpd/fsm.c

105

sockaddr_cmp(&hi->transport_address.sa, &traddr.sa) == 0)

usr.sbin/ldpd/fsm.c

107

if (hi == NULL) {

usr.sbin/ldpd/fsm.c

108

hi = calloc(1, sizeof(*hi));

usr.sbin/ldpd/fsm.c

109

if (!hi) {

usr.sbin/ldpd/fsm.c

113

hi->ldp_id.s_addr = pduid->ldp_id.s_addr;

usr.sbin/ldpd/fsm.c

114

memcpy(&hi->transport_address, &traddr, traddr.sa.sa_len);

usr.sbin/ldpd/fsm.c

115

SLIST_INSERT_HEAD(&hello_info_head, hi, infos);

usr.sbin/ldpd/fsm.c

121

hi->keepalive = ntohs(ht->ch.holdtime);

usr.sbin/ldpd/fsm.c

124

hi->keepalive = LDP_HELLO_KEEP;

usr.sbin/ldpd/fsm.c

126

hi->keepalive = LDP_THELLO_KEEP;

usr.sbin/ldpd/fsm.c

136

(hi->transport_address.sa.sa_family == AF_INET &&

usr.sbin/ldpd/fsm.c

137

ntohl(hi->transport_address.sin.sin_addr.s_addr) <

usr.sbin/ldpd/fsm.c

140

&hi->transport_address.sa,

usr.sbin/ldpd/fsm.c

60

struct hello_info *hi = NULL;

usr.sbin/ldpd/ldp_command.c

544

struct hello_info *hi;

usr.sbin/ldpd/ldp_command.c

546

SLIST_FOREACH(hi, &hello_info_head, infos) {

usr.sbin/ldpd/ldp_command.c

549

inet_ntoa(hi->ldp_id),

usr.sbin/ldpd/ldp_command.c

550

hi->keepalive,

usr.sbin/ldpd/ldp_command.c

551

hi->transport_address.sa.sa_family != 0 ?

usr.sbin/ldpd/ldp_command.c

552

satos(&hi->transport_address.sa) : "None");

usr.sbin/ldpd/socketops.c

1043

SLIST_FOREACH(hi, &hello_info_head, infos) {

usr.sbin/ldpd/socketops.c

1045

&hi->transport_address.sa) == 0) {

usr.sbin/ldpd/socketops.c

1046

peer_ldp_id = &hi->ldp_id;

usr.sbin/ldpd/socketops.c

1107

struct hello_info *hi;

usr.sbin/ldpd/socketops.c

1191

SLIST_FOREACH(hi, &hello_info_head, infos)

usr.sbin/ldpd/socketops.c

1192

if (hi->ldp_id.s_addr == rpdu->ldp_id.s_addr)

usr.sbin/ldpd/socketops.c

1194

if (hi == NULL) {

usr.sbin/ldpd/socketops.c

733

struct hello_info *hi, *hinext;

usr.sbin/ldpd/socketops.c

777

SLIST_FOREACH_SAFE(hi, &hello_info_head, infos, hinext) {

usr.sbin/ldpd/socketops.c

778

if (hi->keepalive != 0xFFFF)

usr.sbin/ldpd/socketops.c

779

hi->keepalive--;

usr.sbin/ldpd/socketops.c

780

if (hi->keepalive < 1)

usr.sbin/ldpd/socketops.c

781

SLIST_REMOVE(&hello_info_head, hi, hello_info, infos);

usr.sbin/ldpd/socketops.c

997

struct hello_info *hi;

usr.sbin/rpc.statd/statd.c

388

reset_host(DBT *key, HostInfo *hi, void *ptr)

usr.sbin/rpc.statd/statd.c

391

if (hi->monList) {

usr.sbin/rpc.statd/statd.c

392

hi->notifyReqd = *(time_t *) ptr;

usr.sbin/rpc.statd/statd.c

393

hi->attempts = 0;

usr.sbin/rpc.statd/statd.c

394

hi->monList = NULL;

usr.sbin/rpc.statd/statd.c

395

change_host((char *)key->data, hi);

usr.sbin/rpc.statd/statd.c

407

check_work(DBT *key, HostInfo *hi, void *ptr)

usr.sbin/rpc.statd/statd.c

409

return hi->notifyReqd ? -1 : 0;

usr.sbin/rpc.statd/statd.c

419

unmon_host(DBT *key, HostInfo *hi, void *ptr)

usr.sbin/rpc.statd/statd.c

423

if (do_unmon(name, hi, ptr))

usr.sbin/rpc.statd/statd.c

424

change_host(name, hi);

usr.sbin/rpc.statd/statd.c

435

notify_one(DBT *key, HostInfo *hi, void *ptr)

usr.sbin/rpc.statd/statd.c

441

if (hi->notifyReqd == 0 || hi->notifyReqd > now)

usr.sbin/rpc.statd/statd.c

462

if (notify_one_host(name) || hi->attempts++ >= 44) {

usr.sbin/rpc.statd/statd.c

464

hi->notifyReqd = 0;

usr.sbin/rpc.statd/statd.c

465

hi->attempts = 0;

usr.sbin/rpc.statd/statd.c

468

if (hi->attempts < 10)

usr.sbin/rpc.statd/statd.c

469

hi->notifyReqd += 5;

usr.sbin/rpc.statd/statd.c

470

else if (hi->attempts < 20)

usr.sbin/rpc.statd/statd.c

471

hi->notifyReqd += 60;

usr.sbin/rpc.statd/statd.c

473

hi->notifyReqd += 60 * 60;

usr.sbin/rpc.statd/statd.c

475

change_host(name, hi);

usr.sbin/sdpd/service.c

487

int lo, hi;

usr.sbin/sdpd/service.c

492

lo = hi = -1;

usr.sbin/sdpd/service.c

498

while (a > hi) {

usr.sbin/sdpd/service.c

504

lo = hi = ui;

usr.sbin/sdpd/service.c

508

hi = (uint16_t)(ui);

usr.sbin/tprof/ksyms.c

145

size_t hi;

usr.sbin/tprof/ksyms.c

154

hi = nsyms - 1;

usr.sbin/tprof/ksyms.c

156

while (lo < hi) {

usr.sbin/tprof/ksyms.c

157

const size_t mid = (lo + hi) / 2;

usr.sbin/tprof/ksyms.c

161

assert(sym->value >= syms[hi]->value);

usr.sbin/tprof/ksyms.c

163

hi = mid;

usr.sbin/traceroute/traceroute.c

1649

struct hostinfo *hi;

usr.sbin/traceroute/traceroute.c

1654

hi = calloc(1, sizeof(*hi));

usr.sbin/traceroute/traceroute.c

1655

if (hi == NULL)

usr.sbin/traceroute/traceroute.c

1658

hi->name = strdup(hname);

usr.sbin/traceroute/traceroute.c

1659

if (!hi->name)

usr.sbin/traceroute/traceroute.c

1661

hi->n = 1;

usr.sbin/traceroute/traceroute.c

1662

hi->addrs = calloc(1, sizeof(hi->addrs[0]));

usr.sbin/traceroute/traceroute.c

1663

if (hi->addrs == NULL)

usr.sbin/traceroute/traceroute.c

1665

hi->addrs[0] = addr.s_addr;

usr.sbin/traceroute/traceroute.c

1666

return hi;

usr.sbin/traceroute/traceroute.c

1674

hi->name = strdup(hp->h_name);

usr.sbin/traceroute/traceroute.c

1675

if (!hi->name)

usr.sbin/traceroute/traceroute.c

1679

hi->n = n;

usr.sbin/traceroute/traceroute.c

1680

hi->addrs = calloc(n, sizeof(hi->addrs[0]));

usr.sbin/traceroute/traceroute.c

1681

if (hi->addrs == NULL)

usr.sbin/traceroute/traceroute.c

1683

for (ap = hi->addrs, p = hp->h_addr_list; *p != NULL; ++ap, ++p)

usr.sbin/traceroute/traceroute.c

1685

return hi;

usr.sbin/traceroute/traceroute.c

1689

freehostinfo(struct hostinfo *hi)

usr.sbin/traceroute/traceroute.c

1691

if (hi->name != NULL) {

usr.sbin/traceroute/traceroute.c

1692

free(hi->name);

usr.sbin/traceroute/traceroute.c

1693

hi->name = NULL;

usr.sbin/traceroute/traceroute.c

1695

free(hi->addrs);

usr.sbin/traceroute/traceroute.c

1696

free(hi);

usr.sbin/traceroute/traceroute.c

1702

struct hostinfo *hi;

usr.sbin/traceroute/traceroute.c

1704

hi = gethostinfo(hname);

usr.sbin/traceroute/traceroute.c

1705

*ap = hi->addrs[0];

usr.sbin/traceroute/traceroute.c

1706

freehostinfo(hi);

usr.sbin/traceroute/traceroute.c

442

struct hostinfo *hi;

usr.sbin/traceroute/traceroute.c

629

hi = gethostinfo(hostname);

usr.sbin/traceroute/traceroute.c

630

setsin(to, hi->addrs[0]);

usr.sbin/traceroute/traceroute.c

631

if (hi->n > 1)

usr.sbin/traceroute/traceroute.c

634

hostname = hi->name;

usr.sbin/traceroute/traceroute.c

635

hi->name = NULL;

usr.sbin/traceroute/traceroute.c

636

freehostinfo(hi);

usr.sbin/traceroute/traceroute.c

858

hi = gethostinfo(source);

usr.sbin/traceroute/traceroute.c

859

source = hi->name;

usr.sbin/traceroute/traceroute.c

860

hi->name = NULL;

usr.sbin/traceroute/traceroute.c

866

setsin(from, hi->addrs[0]);

usr.sbin/traceroute/traceroute.c

867

if (hi->n > 1)

usr.sbin/traceroute/traceroute.c

875

for (i = hi->n, ap = hi->addrs; i > 0; --i, ++ap)

usr.sbin/traceroute/traceroute.c

883

freehostinfo(hi);

usr.sbin/user/user.c

687

getnextgid(int *gidp, int lo, int hi)

usr.sbin/user/user.c

689

for (*gidp = lo ; *gidp < hi ; *gidp += 1) {