Lines Matching refs:p
488 char *p = (char*)&HT_HASH(ht, (ht)->nTableMask); \
494 _mm256_storeu_si256((__m256i*)p, ymm0); \
495 _mm256_storeu_si256((__m256i*)(p+32), ymm0); \
496 p += 64; \
502 char *p = (char*)&HT_HASH(ht, (ht)->nTableMask); \
508 _mm_storeu_si128((__m128i*)p, xmm0); \
509 _mm_storeu_si128((__m128i*)(p+16), xmm0); \
510 _mm_storeu_si128((__m128i*)(p+32), xmm0); \
511 _mm_storeu_si128((__m128i*)(p+48), xmm0); \
512 p += 64; \
518 char *p = (char*)&HT_HASH(ht, (ht)->nTableMask); \
523 vst1q_s32((int32_t*)p, t); \
524 vst1q_s32((int32_t*)(p+16), t); \
525 vst1q_s32((int32_t*)(p+32), t); \
526 vst1q_s32((int32_t*)(p+48), t); \
527 p += 64; \
705 #define GC_REFCOUNT(p) zend_gc_refcount(&(p)->gc) argument
706 #define GC_SET_REFCOUNT(p, rc) zend_gc_set_refcount(&(p)->gc, rc) argument
707 #define GC_ADDREF(p) zend_gc_addref(&(p)->gc) argument
708 #define GC_DELREF(p) zend_gc_delref(&(p)->gc) argument
709 #define GC_ADDREF_EX(p, rc) zend_gc_addref_ex(&(p)->gc, rc) argument
710 #define GC_DELREF_EX(p, rc) zend_gc_delref_ex(&(p)->gc, rc) argument
711 #define GC_TRY_ADDREF(p) zend_gc_try_addref(&(p)->gc) argument
712 #define GC_TRY_DELREF(p) zend_gc_try_delref(&(p)->gc) argument
714 #define GC_DTOR(p) \ argument
716 zend_refcounted_h *_p = &(p)->gc; \
724 #define GC_DTOR_NO_REF(p) \ argument
726 zend_refcounted_h *_p = &(p)->gc; \
752 #define GC_TYPE_INFO(p) (p)->gc.u.type_info argument
753 #define GC_TYPE(p) zval_gc_type(GC_TYPE_INFO(p)) argument
754 #define GC_FLAGS(p) zval_gc_flags(GC_TYPE_INFO(p)) argument
755 #define GC_INFO(p) zval_gc_info(GC_TYPE_INFO(p)) argument
757 #define GC_ADD_FLAGS(p, flags) do { \ argument
758 GC_TYPE_INFO(p) |= (flags) << GC_FLAGS_SHIFT; \
760 #define GC_DEL_FLAGS(p, flags) do { \ argument
761 GC_TYPE_INFO(p) &= ~((flags) << GC_FLAGS_SHIFT); \
861 #define GC_IS_RECURSIVE(p) \ argument
862 (GC_FLAGS(p) & GC_PROTECTED)
864 #define GC_PROTECT_RECURSION(p) do { \ argument
865 GC_ADD_FLAGS(p, GC_PROTECTED); \
868 #define GC_UNPROTECT_RECURSION(p) do { \ argument
869 GC_DEL_FLAGS(p, GC_PROTECTED); \
872 #define GC_TRY_PROTECT_RECURSION(p) do { \ argument
873 if (!(GC_FLAGS(p) & GC_IMMUTABLE)) GC_PROTECT_RECURSION(p); \
876 #define GC_TRY_UNPROTECT_RECURSION(p) do { \ argument
877 if (!(GC_FLAGS(p) & GC_IMMUTABLE)) GC_UNPROTECT_RECURSION(p); \
1024 #define GC_AST(p) ((zend_ast*)(((char*)p) + sizeof(zend_ast_ref))) argument
1146 #define ZVAL_NEW_RES(z, h, p, t) do { \ argument
1154 _res->ptr = (p); \
1160 #define ZVAL_NEW_PERSISTENT_RES(z, h, p, t) do { \ argument
1169 _res->ptr = (p); \
1237 #define ZVAL_PTR(z, p) do { \ argument
1238 Z_PTR_P(z) = (p); \
1252 #define ZVAL_ALIAS_PTR(z, p) do { \ argument
1253 Z_PTR_P(z) = (p); \
1294 # define ZEND_RC_MOD_CHECK(p) do { \ argument
1296 uint8_t type = zval_gc_type((p)->u.type_info); \
1298 ZEND_ASSERT(!(zval_gc_flags((p)->u.type_info) & GC_IMMUTABLE)); \
1299 …ZEND_ASSERT((zval_gc_flags((p)->u.type_info) & (GC_PERSISTENT|GC_PERSISTENT_LOCAL)) != GC_PERSISTE…
1303 # define GC_MAKE_PERSISTENT_LOCAL(p) do { \ argument
1304 GC_ADD_FLAGS(p, GC_PERSISTENT_LOCAL); \
1307 # define ZEND_RC_MOD_CHECK(p) \ argument
1309 # define GC_MAKE_PERSISTENT_LOCAL(p) \ argument
1313 static zend_always_inline uint32_t zend_gc_refcount(const zend_refcounted_h *p) { in zend_gc_refcount() argument
1314 return p->refcount; in zend_gc_refcount()
1317 static zend_always_inline uint32_t zend_gc_set_refcount(zend_refcounted_h *p, uint32_t rc) { in zend_gc_set_refcount() argument
1318 p->refcount = rc; in zend_gc_set_refcount()
1319 return p->refcount; in zend_gc_set_refcount()
1322 static zend_always_inline uint32_t zend_gc_addref(zend_refcounted_h *p) { in zend_gc_addref() argument
1323 ZEND_RC_MOD_CHECK(p); in zend_gc_addref()
1324 return ++(p->refcount); in zend_gc_addref()
1327 static zend_always_inline void zend_gc_try_addref(zend_refcounted_h *p) { in zend_gc_try_addref() argument
1328 if (!(p->u.type_info & GC_IMMUTABLE)) { in zend_gc_try_addref()
1329 ZEND_RC_MOD_CHECK(p); in zend_gc_try_addref()
1330 ++p->refcount; in zend_gc_try_addref()
1334 static zend_always_inline void zend_gc_try_delref(zend_refcounted_h *p) { in zend_gc_try_delref() argument
1335 if (!(p->u.type_info & GC_IMMUTABLE)) { in zend_gc_try_delref()
1336 ZEND_RC_MOD_CHECK(p); in zend_gc_try_delref()
1337 --p->refcount; in zend_gc_try_delref()
1341 static zend_always_inline uint32_t zend_gc_delref(zend_refcounted_h *p) { in zend_gc_delref() argument
1342 ZEND_ASSERT(p->refcount > 0); in zend_gc_delref()
1343 ZEND_RC_MOD_CHECK(p); in zend_gc_delref()
1344 return --(p->refcount); in zend_gc_delref()
1347 static zend_always_inline uint32_t zend_gc_addref_ex(zend_refcounted_h *p, uint32_t rc) { in zend_gc_addref_ex() argument
1348 ZEND_RC_MOD_CHECK(p); in zend_gc_addref_ex()
1349 p->refcount += rc; in zend_gc_addref_ex()
1350 return p->refcount; in zend_gc_addref_ex()
1353 static zend_always_inline uint32_t zend_gc_delref_ex(zend_refcounted_h *p, uint32_t rc) { in zend_gc_delref_ex() argument
1354 ZEND_RC_MOD_CHECK(p); in zend_gc_delref_ex()
1355 p->refcount -= rc; in zend_gc_delref_ex()
1356 return p->refcount; in zend_gc_delref_ex()
