Lines Matching refs:xbuf
55 static inline void xsave(struct xsave_buffer *xbuf, uint64_t rfbm) in xsave() argument
61 : : "D" (xbuf), "a" (rfbm_lo), "d" (rfbm_hi) in xsave()
65 static inline void xrstor(struct xsave_buffer *xbuf, uint64_t rfbm) in xrstor() argument
71 : : "D" (xbuf), "a" (rfbm_lo), "d" (rfbm_hi)); in xrstor()
176 struct xsave_buffer *xbuf; in alloc_xbuf() local
179 xbuf = aligned_alloc(64, xbuf_size); in alloc_xbuf()
180 if (!xbuf) in alloc_xbuf()
182 return xbuf; in alloc_xbuf()
202 static void set_rand_tiledata(struct xsave_buffer *xbuf) in set_rand_tiledata() argument
204 int *ptr = (int *)&xbuf->bytes[xtiledata.xbuf_offset]; in set_rand_tiledata()
268 void *xbuf = ctx->uc_mcontext.fpregs; in handle_noperm() local
283 sw_bytes = get_fpx_sw_bytes(xbuf); in handle_noperm()
300 features = get_fpx_sw_bytes_features(xbuf); in handle_noperm()
317 static inline bool xrstor_safe(struct xsave_buffer *xbuf, uint64_t mask) in xrstor_safe() argument
320 xrstor(xbuf, mask); in xrstor_safe()
342 static inline bool load_rand_tiledata(struct xsave_buffer *xbuf) in load_rand_tiledata() argument
344 clear_xstate_header(xbuf); in load_rand_tiledata()
345 set_xstatebv(xbuf, XFEATURE_MASK_XTILEDATA); in load_rand_tiledata()
346 set_rand_tiledata(xbuf); in load_rand_tiledata()
347 return xrstor_safe(xbuf, XFEATURE_MASK_XTILEDATA); in load_rand_tiledata()
611 static inline void validate_tiledata_regs_same(struct xsave_buffer *xbuf) in validate_tiledata_regs_same() argument
613 int ret = __validate_tiledata_regs(xbuf); in validate_tiledata_regs_same()
619 static inline void validate_tiledata_regs_changed(struct xsave_buffer *xbuf) in validate_tiledata_regs_changed() argument
621 int ret = __validate_tiledata_regs(xbuf); in validate_tiledata_regs_changed()
692 struct xsave_buffer *xbuf; in check_tiledata() local
695 xbuf = alloc_xbuf(); in check_tiledata()
696 if (!xbuf) in check_tiledata()
703 load_rand_tiledata(xbuf); in check_tiledata()
711 validate_tiledata_regs_same(xbuf); in check_tiledata()
714 load_rand_tiledata(xbuf); in check_tiledata()
728 free(xbuf); in check_tiledata()