NEON Détection de dépassement de capacité

Question

J'ai une longue boucle où des ajouts de vecteurs au néon sont effectués sur des éléments de 8 bits. Le problème est qu'après un certain temps, il est presque certain que certains ou tous les composants du vecteur sont saturés à cause du débordement. Existe-t-il un moyen rapide de détecter ceci afin que je puisse vider les résultats, zéro le vecteur et continuer? J'ai déjà essayé en vérifiant les drapeaux C et V mais il semble que les opérations au néon ne les définissent pas.

edit: voici le code d'intérêt, un peu simplifié. En outre, je suis passé à 16 bits, mais il faudra encore déborder

int16x8_t Sum; 
for(int C = 0; C < 100; C++) 
{ 
    // Sum += |a - b| 
    Sum = vabaq_u16(
     Sum,      
     vld1q_u16((uint16_t *)a), 
     vld1q_u16((uint16_t *)b) 
    ); 
} 

Answer 1

Si vous utilisez VQADD pour la somme, non seulement il sature (pince) les valeurs au lieu de déborder et d'emballage autour (qui peut être souhaitable dans lui-même), mais il établira également le drapeau de saturation (bit 27) dans le FPSCR chaque fois que cela se produit. Une fois défini, ce drapeau doit être effacé manuellement en réécrivant la valeur FPSCR avec le bit 27 mis à zéro. Une alternative possible, en fonction de la façon dont le reste de l'algorithme utilise le résultat, pourrait être de diviser votre accumulateur sur deux registres et d'utiliser une opération d'élargissement (VABAL) sur chaque moitié des vecteurs d'entrée pour accumuler 16 bits éléments, vous pouvez simplement vider le résultat à un intervalle prédéterminé sans jamais avoir besoin de vérifier explicitement. Comme le nombre minimal de valeurs 8 bits non signées requises pour déborder d'un accumulateur de 16 bits est de 258 (65535/255 = 257), alors si la boucle vide le résultat tous les 257 ou moins de dépassements d'itérations deviennent impossibles.